Ignore:
Timestamp:
Aug 14, 2019, 9:34:19 AM (4 months ago)
Author:
matszpk
Message:

CLRadeonExtender: ROCm: MSgPack metadata parsing - kernel args parsing.

File:
1 edited

Legend:

Unmodified
Added
Removed
  • CLRadeonExtender/trunk/amdbin/ROCmBinaries.cpp

    r4889 r4890  
    20072007}
    20082008
     2009static void parseROCmMetadataKernelArgMsgPack(MsgPackArrayParser& argsParser,
     2010                        ROCmKernelArgInfo& argInfo)
     2011{
     2012}
     2013
    20092014enum {
    20102015    ROCMMP_KERNEL_ARGS = 0, ROCMMP_KERNEL_DEVICE_ENQUEUE_SYMBOL,
     
    20222027static const char* rocmMetadataMPKernelNames[] =
    20232028{
    2024     "args", "device_enqueue_symbol", "group_segment_fixed_size", "kernarg_segment_align",
    2025     "kernarg_segment_size", "language", "language_version", "max_flat_workgroup_size",
    2026     "name", "private_segment_fixed_size", "reqd_workgroup_size", "sgpr_count",
    2027     "sgpr_spill_count", "symbol", "vec_type_hint", "vgpr_count", "vgpr_spill_count",
    2028     "wavefront_size", "workgroup_size_hint"
     2029    ".args", ".device_enqueue_symbol", ".group_segment_fixed_size", ".kernarg_segment_align",
     2030    ".kernarg_segment_size", ".language", ".language_version", ".max_flat_workgroup_size",
     2031    ".name", ".private_segment_fixed_size", ".reqd_workgroup_size", ".sgpr_count",
     2032    ".sgpr_spill_count", ".symbol", ".vec_type_hint", ".vgpr_count", ".vgpr_spill_count",
     2033    ".wavefront_size", ".workgroup_size_hint"
    20292034};
    20302035
     
    20462051        {
    20472052            case ROCMMP_KERNEL_ARGS:
    2048                 break;
     2053            {
     2054                MsgPackArrayParser argsParser = kParser.parseValueArray();
     2055                while (argsParser.haveElements())
     2056                {
     2057                    ROCmKernelArgInfo arg{};
     2058                    parseROCmMetadataKernelArgMsgPack(kernelsParser, arg);
     2059                    kernel.argInfos.push_back(arg);
     2060                }
     2061                break;
     2062            }
    20492063            case ROCMMP_KERNEL_DEVICE_ENQUEUE_SYMBOL:
    20502064                kernel.deviceEnqueueSymbol = kParser.parseValueString();
     
    21402154                ROCmKernelMetadata kernel{};
    21412155                parseROCmMetadataKernelMsgPack(kernelsParser, kernel);
     2156                kernels.push_back(kernel);
    21422157            }
    21432158        }
Note: See TracChangeset for help on using the changeset viewer.