AI/rocm-systems
2
0
Fork 0
Code Issues Pull Requests Actions Packages Projects Releases Wiki Activity

doc improvements and fixes SWDEV-523395,SWDEV-516979 (#314)

Browse Source 
* doc improvements and fixes SWDEV-523395,SWDEV-516979

* Adding changes from PR 231
This commit is contained in:
Bhardwaj, Gopesh
2025-03-26 10:09:08 +05:30
committed by GitHub
parent 2061c52817
commit 6d6eec230c
5 changed files with 387 additions and 354 deletions
Download Patch File Download Diff File Expand all files Collapse all files
README.md
+24 -8
View File
@@ -13,14 +13,30 @@ ROCProfiler-SDK is AMD’s new and improved tooling infrastructure, providing a
## GPU Metrics
- GPU hardware counters
- Dispatch Counter Collection
- Device Counter Collection
- PC Sampling (Host Trap)
## API Trace Support
- HIP API tracing
- HIP kernel tracing
- HSA API tracing
- HSA operation tracing
- Marker(ROCTx) tracing
- PC Sampling (Beta)
- RCCL tracing
- Kokkoks tracing
- Marker (ROCTx) tracing
- Memory copy tracing
- Memory allocation tracing
- Page Migration Event tracing
- Scratch Memory tracing
- RCCL API tracing
- rocDecode API tracing
- rocjpeg API tracing
## Parallelism API Support
- HIP
- HSA
- MPI
- Kokkos-Tools (KokkosP)
- OpenMP-Tools (OMPT)
## Tool Support
@@ -83,7 +99,7 @@ Please report in the Github Issues.
- Using PC sampling on multi-threaded applications might fail with `HSA_STATUS_ERROR_EXCEPTION`.Furthermore, if three or more threads launch operations to the same agent, and if PC sampling is enabled, the `HSA_STATUS_ERROR_EXCEPTION` might appear.
- gfx11 and gfx12 requires a stable power state for counter collection. This includes Radeon 7000 GPUs.
- gfx10, gfx11 and gfx12 requires a stable power state for counter collection. This includes Radeon 7000 GPUs.
```bash
# For device <N>. Use 'rocm-smi' or 'amd-smi monitor' to see device number.
sudo amd-smi set -g <N> -l stable_std
@@ -91,7 +107,7 @@ Please report in the Github Issues.
sudo amd-smi set -g <N> -l auto
```
The gfx version can be found via `amd-smi static --asic -g <N>` in the `TARGET_GRAPHICS_VERSION` field:
The gfx version can be found via `amd-smi static --asic -g <N>` in the `TARGET_GRAPHICS_VERSION` field:
```bash
$ amd-smi static -a -g 2
source/docs/api-reference/counter_collection_services.rst
+1 -1
View File
@@ -355,7 +355,7 @@ Select Function
select() only returns counter values which match the dimension indexes provided by the user in expression. This operation is to allow a user to state they only want to select specific dimensions index. Supported dimensions include ``DIMENSION_XCC, DIMENSION_AID, DIMENSION_SHADER_ENGINE, DIMENSION_AGENT, DIMENSION_SHADER_ARRAY, DIMENSION_WGP, DIMENSION_INSTANCE``. For example ``select(Y, [DIMENSION_XCC=[0],DIMENSION_SHADER_ENGINE=[2]])`` gives counter values which are from DIMENSION_XCC= 0 and DIMENSION_SHADER_ENGINE= 2 for Y Metric.
Let's say Y has XCC, SHADER_ENGINE(SE), WGP dimensions with sizes 2, 4, 4 respectively.
Let's say Y has XCC, SHADER_ENGINE (SE), WGP dimensions with sizes 2, 4, 4 respectively.
Raw Counter Data in 3D space:
source/docs/conceptual/comparing-with-legacy-tools.rst
+25 -4
View File
@@ -74,7 +74,7 @@ ROCprofiler-SDK introduces a new command-line tool, `rocprofv3`, which is a more
- New option to trace scratch memory operations
-
* - Basic tracing options
- Marker Trace(ROCTx)
- Marker Trace (ROCTx)
- `--roctx-trace`
- `--roctx-trace`
- `--marker-trace`
@@ -155,7 +155,28 @@ ROCprofiler-SDK introduces a new command-line tool, `rocprofv3`, which is a more
- *Not Available*
- *Not Available*
- `--rccl-trace`
- For collecting RCCL(ROCm Communication Collectives Library. Also pronounced as 'Rickle' ) Traces
- For collecting RCCL (ROCm Communication Collectives Library. Also pronounced as 'Rickle' ) Traces
-
* - Advanced tracing options
- Scratch memory trace
- *Not Available*
- *Not Available*
- `--scratch-memory-trace`
- Collecting scratch memory event traces.
-
* - Advanced tracing options
- rocDecode trace
- *Not Available*
- *Not Available*
- `--rocdecode-trace`
- Tracing rocDecode library.
-
* - Advanced tracing options
- rocJPEG trace
- *Not Available*
- *Not Available*
- `--rocjpeg-trace`
- Tracing rocJPEG library.
-
* - Aggregate tracing options
- Sys Trace
@@ -332,8 +353,8 @@ ROCprofiler-SDK introduces a new command-line tool, `rocprofv3`, which is a more
- Providing Custom metrics file
- `-m` <metric file>
- `-m` <metric file>
- Not available
- Not yet in rocprofv3
- `-E` <metric file> --pmc <counter>
- In rocprofv3, this option has changed to provide a file with custom metrics and collect performance counters from the command line using --pmc option
-
* - Advanced options
- Preload
source/docs/data/counter_collection.csv
+5 -9
View File
@@ -1,9 +1,5 @@
"Correlation_Id","Dispatch_Id","Agent_Id","Queue_Id","Process_Id","Thread_Id","Grid_Size","Kernel_Id","Kernel_Name","Workgroup_Size","LDS_Block_Size","Scratch_Size","VGPR_Count","SGPR_Count","Counter_Name","Counter_Value","Start_Timestamp","End_Timestamp"
1,1,1,1,19396,19396,1048576,16,"void addition_kernel<float>(float*, float const*, float const*, int, int)",64,0,0,8,16,"SQ_WAVES",16384,2228955885095594,2228955885119754
2,2,1,1,19396,19396,1048576,19,"subtract_kernel(float*, float const*, float const*, int, int)",64,0,0,8,16,"SQ_WAVES",16384,2228955885095594,2228955885119754
5,5,1,2,19396,19396,1048576,16,"void addition_kernel<float>(float*, float const*, float const*, int, int)",64,0,0,8,16,"SQ_WAVES",16384,2228955885095594,2228955885119754
9,9,1,3,19396,19396,1048576,16,"void addition_kernel<float>(float*, float const*, float const*, int, int)",64,0,0,8,16,"SQ_WAVES",16384,2228955885095594,2228955885119754
13,13,1,4,19396,19396,1048576,16,"void addition_kernel<float>(float*, float const*, float const*, int, int)",64,0,0,8,16,"SQ_WAVES",16384,2228955885095594,2228955885119754
3,3,1,1,19396,19396,1048576,17,"multiply_kernel(float*, float const*, float const*, int, int)",64,0,0,8,16,"SQ_WAVES",16384,2228955885095594,2228955885119754
6,6,1,2,19396,19396,1048576,19,"subtract_kernel(float*, float const*, float const*, int, int)",64,0,0,8,16,"SQ_WAVES",16384,2228955885095594,2228955885119754
"Correlation_Id","Dispatch_Id","Agent_Id","Queue_Id","Process_Id","Thread_Id","Grid_Size","Kernel_Id","Kernel_Name","Workgroup_Size","LDS_Block_Size","Scratch_Size","VGPR_Count","Accum_VGPR_Count","SGPR_Count","Counter_Name","Counter_Value","Start_Timestamp","End_Timestamp"
1,1,"Agent 1",1,15606,15606,1048576,17,"void addition_kernel<float>(float*, float const*, float const*, int, int)",64,0,0,8,0,16,"SQ_WAVES",16384.000000,3200098838431081,3200098838483232
2,2,"Agent 1",1,15606,15606,1048576,20,"subtract_kernel(float*, float const*, float const*, int, int)",64,0,0,8,0,16,"SQ_WAVES",16384.000000,3200098838589014,3200098838638794
3,3,"Agent 1",1,15606,15606,1048576,19,"multiply_kernel(float*, float const*, float const*, int, int)",64,0,0,8,0,16,"SQ_WAVES",16384.000000,3200098838746207,3200098838793025
4,4,"Agent 1",1,15606,15606,1048576,18,"divide_kernel(float*, float const*, float const*, int, int)",64,0,0,12,0,16,"SQ_WAVES",16384.000000,3200098838879399,3200098838927550
1 Correlation_Id Dispatch_Id Agent_Id Queue_Id Process_Id Thread_Id Grid_Size Kernel_Id Kernel_Name Workgroup_Size LDS_Block_Size Scratch_Size VGPR_Count Accum_VGPR_Count SGPR_Count Counter_Name Counter_Value Start_Timestamp End_Timestamp
2 1 1 1 Agent 1 1 19396 15606 19396 15606 1048576 16 17 void addition_kernel<float>(float*, float const*, float const*, int, int) 64 0 0 8 0 16 SQ_WAVES 16384 16384.000000 2228955885095594 3200098838431081 2228955885119754 3200098838483232
3 2 2 1 Agent 1 1 19396 15606 19396 15606 1048576 19 20 subtract_kernel(float*, float const*, float const*, int, int) 64 0 0 8 0 16 SQ_WAVES 16384 16384.000000 2228955885095594 3200098838589014 2228955885119754 3200098838638794
4 5 3 5 3 1 Agent 1 2 1 19396 15606 19396 15606 1048576 16 19 void addition_kernel<float>(float*, float const*, float const*, int, int) multiply_kernel(float*, float const*, float const*, int, int) 64 0 0 8 0 16 SQ_WAVES 16384 16384.000000 2228955885095594 3200098838746207 2228955885119754 3200098838793025
5 9 4 9 4 1 Agent 1 3 1 19396 15606 19396 15606 1048576 16 18 void addition_kernel<float>(float*, float const*, float const*, int, int) divide_kernel(float*, float const*, float const*, int, int) 64 0 0 8 12 0 16 SQ_WAVES 16384 16384.000000 2228955885095594 3200098838879399 2228955885119754 3200098838927550
13 13 1 4 19396 19396 1048576 16 void addition_kernel<float>(float*, float const*, float const*, int, int) 64 0 0 8 16 SQ_WAVES 16384 2228955885095594 2228955885119754
3 3 1 1 19396 19396 1048576 17 multiply_kernel(float*, float const*, float const*, int, int) 64 0 0 8 16 SQ_WAVES 16384 2228955885095594 2228955885119754
6 6 1 2 19396 19396 1048576 19 subtract_kernel(float*, float const*, float const*, int, int) 64 0 0 8 16 SQ_WAVES 16384 2228955885095594 2228955885119754
source/docs/how-to/using-rocprofv3.rst
+332 -332
View File
@@ -1,6 +1,6 @@
.. meta::
:description: ROCprofiler-SDK is a tooling infrastructure for profiling general-purpose GPU compute applications running on the ROCm software
:keywords: ROCprofiler-SDK tool usage, rocprofv3 user manual, rocprofv3 usage, rocprogv3 user guide, using rocprofv3, ROCprofiler-SDK tool user guide, ROCprofiler-SDK tool user manual, using ROCprofiler-SDK tool, ROCprofiler-SDK command-line tool, ROCprofiler-SDK CLI, ROCprofiler-SDK command line tool
:keywords: ROCprofiler-SDK tool usage, rocprofv3 user manual, rocprofv3 usage, rocprofv3 user guide, using rocprofv3, ROCprofiler-SDK tool user guide, ROCprofiler-SDK tool user manual, using ROCprofiler-SDK tool, ROCprofiler-SDK command-line tool, ROCprofiler-SDK CLI, ROCprofiler-SDK command line tool
.. _using-rocprofv3:
@@ -649,32 +649,32 @@ Here is a sample input.json file for collecting tracing summary:
Here is the input schema (properties) of JSON or YAML input files:
- **``jobs``** *(array)*: ``rocprofv3`` input data per application run.
- **jobs** *(array)*: ``rocprofv3`` input data per application run.
- **Items** *(object)*: Data for ``rocprofv3``
- **``hip_trace``** *(boolean)*
- **``hip_runtime_trace``** *(boolean)*
- **``hip_compiler_trace``** *(boolean)*
- **``marker_trace``** *(boolean)*
- **``kernel_trace``** *(boolean)*
- **``memory_copy_trace``** *(boolean)*
- **``memory_allocation_trace``** *(boolean)*
- **``scratch_memory_trace``** *(boolean)*
- **``stats``** *(boolean)*
- **``hsa_trace``** *(boolean)*
- **``hsa_core_trace``** *(boolean)*
- **``hsa_amd_trace``** *(boolean)*
- **``hsa_finalize_trace``** *(boolean)*
- **``hsa_image_trace``** *(boolean)*
- **``sys_trace``** *(boolean)*
- **``mangled_kernels``** *(boolean)*
- **``truncate_kernels``** *(boolean)*
- **``output_file``** *(string)*
- **``output_directory``** *(string)*
- **``output_format``** *(array)*
- **``log_level``** *(string)*
- **``preload``** *(array)*
- **hip_trace** *(boolean)*
- **hip_runtime_trace** *(boolean)*
- **hip_compiler_trace** *(boolean)*
- **marker_trace** *(boolean)*
- **kernel_trace** *(boolean)*
- **memory_copy_trace** *(boolean)*
- **memory_allocation_trace** *(boolean)*
- **scratch_memory_trace** *(boolean)*
- **stats** *(boolean)*
- **hsa_trace** *(boolean)*
- **hsa_core_trace** *(boolean)*
- **hsa_amd_trace** *(boolean)*
- **hsa_finalize_trace** *(boolean)*
- **hsa_image_trace** *(boolean)*
- **sys_trace** *(boolean)*
- **mangled_kernels** *(boolean)*
- **truncate_kernels** *(boolean)*
- **output_file** *(string)*
- **output_directory** *(string)*
- **output_format** *(array)*
- **log_level** *(string)*
- **preload** *(array)*
For description of the options specified under job items, see :ref:`cli-options`.
@@ -752,26 +752,26 @@ While the input file in text format can only be used for counter collection, JSO
Here is the input schema (properties) of JSON or YAML input files:
- **``jobs``** *(array)*: ``rocprofv3`` input data per application run
- **jobs** *(array)*: ``rocprofv3`` input data per application run
- **Items** *(object)*: Data for ``rocprofv3``
- **``pmc``** *(array)*: list of counters for collection
- **``kernel_include_regex``** *(string)*
- **``kernel_exclude_regex``** *(string)*
- **``kernel_iteration_range``** *(string)*
- **``mangled_kernels``** *(boolean)*
- **``truncate_kernels``** *(boolean)*
- **``output_file``** *(string)*
- **``output_directory``** *(string)*
- **``output_format``** *(array)*
- **``list_avail``** *(boolean)*
- **``log_level``** *(string)*
- **``preload``** *(array)*
- **``pc_sampling_unit``** *(string)*
- **``pc_sampling_method``** *(string)*
- **``pc_sampling_interval``** *(integer)*
- **``pc_sampling_beta_enabled``** *(boolean)*
- **pmc** *(array)*: list of counters for collection
- **kernel_include_regex** *(string)*
- **kernel_exclude_regex** *(string)*
- **kernel_iteration_range** *(string)*
- **mangled_kernels** *(boolean)*
- **truncate_kernels** *(boolean)*
- **output_file** *(string)*
- **output_directory** *(string)*
- **output_format** *(array)*
- **list_avail** *(boolean)*
- **log_level** *(string)*
- **preload** *(array)*
- **pc_sampling_unit** *(string)*
- **pc_sampling_method** *(string)*
- **pc_sampling_interval** *(integer)*
- **pc_sampling_beta_enabled** *(boolean)*
For description of the options specified under job items, see :ref:`cli-options`.
@@ -883,7 +883,7 @@ Here are the contents of ``counter_collection.csv`` file:
.. csv-table:: Counter collection
:file: /data/counter_collection.csv
:widths: 10,10,10,10,10,10,10,10,10,10,10,10,10,10,10,10,10,10
:widths: 10,10,10,10,10,10,10,10,10,10,10,10,10,10,10,10,10,10,10
:header-rows: 1
For the description of the fields in the output file, see :ref:`output-file-fields`.
@@ -1210,324 +1210,324 @@ Properties
Here are the properties of the JSON output schema:
- **`rocprofiler-sdk-tool`** `(array)`: rocprofv3 data per process (each element represents a process).
- **rocprofiler-sdk-tool** `(array)`: rocprofv3 data per process (each element represents a process).
- **Items** `(object)`: Data for rocprofv3.
- **`metadata`** `(object, required)`: Metadata related to the profiler session.
- **`pid`** `(integer, required)`: Process ID.
- **`init_time`** `(integer, required)`: Initialization time in nanoseconds.
- **`fini_time`** `(integer, required)`: Finalization time in nanoseconds.
- **`agents`** `(array, required)`: List of agents.
- **metadata** `(object, required)`: Metadata related to the profiler session.
- **pid** `(integer, required)`: Process ID.
- **init_time** `(integer, required)`: Initialization time in nanoseconds.
- **fini_time** `(integer, required)`: Finalization time in nanoseconds.
- **agents** `(array, required)`: List of agents.
- **Items** `(object)`: Data for an agent.
- **`size`** `(integer, required)`: Size of the agent data.
- **`id`** `(object, required)`: Identifier for the agent.
- **`handle`** `(integer, required)`: Handle for the agent.
- **`type`** `(integer, required)`: Type of the agent.
- **`cpu_cores_count`** `(integer)`: Number of CPU cores.
- **`simd_count`** `(integer)`: Number of SIMD units.
- **`mem_banks_count`** `(integer)`: Number of memory banks.
- **`caches_count`** `(integer)`: Number of caches.
- **`io_links_count`** `(integer)`: Number of I/O links.
- **`cpu_core_id_base`** `(integer)`: Base ID for CPU cores.
- **`simd_id_base`** `(integer)`: Base ID for SIMD units.
- **`max_waves_per_simd`** `(integer)`: Maximum waves per SIMD.
- **`lds_size_in_kb`** `(integer)`: Size of LDS in KB.
- **`gds_size_in_kb`** `(integer)`: Size of GDS in KB.
- **`num_gws`** `(integer)`: Number of GWS (global work size).
- **`wave_front_size`** `(integer)`: Size of the wave front.
- **`num_xcc`** `(integer)`: Number of XCC (execution compute units).
- **`cu_count`** `(integer)`: Number of compute units (CUs).
- **`array_count`** `(integer)`: Number of arrays.
- **`num_shader_banks`** `(integer)`: Number of shader banks.
- **`simd_arrays_per_engine`** `(integer)`: SIMD arrays per engine.
- **`cu_per_simd_array`** `(integer)`: CUs per SIMD array.
- **`simd_per_cu`** `(integer)`: SIMDs per CU.
- **`max_slots_scratch_cu`** `(integer)`: Maximum slots for scratch CU.
- **`gfx_target_version`** `(integer)`: GFX target version.
- **`vendor_id`** `(integer)`: Vendor ID.
- **`device_id`** `(integer)`: Device ID.
- **`location_id`** `(integer)`: Location ID.
- **`domain`** `(integer)`: Domain identifier.
- **`drm_render_minor`** `(integer)`: DRM render minor version.
- **`num_sdma_engines`** `(integer)`: Number of SDMA engines.
- **`num_sdma_xgmi_engines`** `(integer)`: Number of SDMA XGMI engines.
- **`num_sdma_queues_per_engine`** `(integer)`: Number of SDMA queues per engine.
- **`num_cp_queues`** `(integer)`: Number of CP queues.
- **`max_engine_clk_ccompute`** `(integer)`: Maximum engine clock for compute.
- **`max_engine_clk_fcompute`** `(integer)`: Maximum engine clock for F compute.
- **`sdma_fw_version`** `(object)`: SDMA firmware version.
- **`uCodeSDMA`** `(integer, required)`: SDMA microcode version.
- **`uCodeRes`** `(integer, required)`: Reserved microcode version.
- **`fw_version`** `(object)`: Firmware version.
- **`uCode`** `(integer, required)`: Microcode version.
- **`Major`** `(integer, required)`: Major version.
- **`Minor`** `(integer, required)`: Minor version.
- **`Stepping`** `(integer, required)`: Stepping version.
- **`capability`** `(object, required)`: Agent capability flags.
- **`HotPluggable`** `(integer, required)`: Hot pluggable capability.
- **`HSAMMUPresent`** `(integer, required)`: HSAMMU present capability.
- **`SharedWithGraphics`** `(integer, required)`: Shared with graphics capability.
- **`QueueSizePowerOfTwo`** `(integer, required)`: Queue size is power of two.
- **`QueueSize32bit`** `(integer, required)`: Queue size is 32-bit.
- **`QueueIdleEvent`** `(integer, required)`: Queue idle event.
- **`VALimit`** `(integer, required)`: VA limit.
- **`WatchPointsSupported`** `(integer, required)`: Watch points supported.
- **`WatchPointsTotalBits`** `(integer, required)`: Total bits for watch points.
- **`DoorbellType`** `(integer, required)`: Doorbell type.
- **`AQLQueueDoubleMap`** `(integer, required)`: AQL queue double map.
- **`DebugTrapSupported`** `(integer, required)`: Debug trap supported.
- **`WaveLaunchTrapOverrideSupported`** `(integer, required)`: Wave launch trap override supported.
- **`WaveLaunchModeSupported`** `(integer, required)`: Wave launch mode supported.
- **`PreciseMemoryOperationsSupported`** `(integer, required)`: Precise memory operations supported.
- **`DEPRECATED_SRAM_EDCSupport`** `(integer, required)`: Deprecated SRAM EDC support.
- **`Mem_EDCSupport`** `(integer, required)`: Memory EDC support.
- **`RASEventNotify`** `(integer, required)`: RAS event notify.
- **`ASICRevision`** `(integer, required)`: ASIC revision.
- **`SRAM_EDCSupport`** `(integer, required)`: SRAM EDC support.
- **`SVMAPISupported`** `(integer, required)`: SVM API supported.
- **`CoherentHostAccess`** `(integer, required)`: Coherent host access.
- **`DebugSupportedFirmware`** `(integer, required)`: Debug supported firmware.
- **`Reserved`** `(integer, required)`: Reserved field.
- **`counters`** `(array, required)`: Array of counter objects.
- **size** `(integer, required)`: Size of the agent data.
- **id** `(object, required)`: Identifier for the agent.
- **handle** `(integer, required)`: Handle for the agent.
- **type** `(integer, required)`: Type of the agent.
- **cpu_cores_count** `(integer)`: Number of CPU cores.
- **simd_count** `(integer)`: Number of SIMD units.
- **mem_banks_count** `(integer)`: Number of memory banks.
- **caches_count** `(integer)`: Number of caches.
- **io_links_count** `(integer)`: Number of I/O links.
- **cpu_core_id_base** `(integer)`: Base ID for CPU cores.
- **simd_id_base** `(integer)`: Base ID for SIMD units.
- **max_waves_per_simd** `(integer)`: Maximum waves per SIMD.
- **lds_size_in_kb** `(integer)`: Size of LDS in KB.
- **gds_size_in_kb** `(integer)`: Size of GDS in KB.
- **num_gws** `(integer)`: Number of GWS (global work size).
- **wave_front_size** `(integer)`: Size of the wave front.
- **num_xcc** `(integer)`: Number of XCC (execution compute units).
- **cu_count** `(integer)`: Number of compute units (CUs).
- **array_count** `(integer)`: Number of arrays.
- **num_shader_banks** `(integer)`: Number of shader banks.
- **simd_arrays_per_engine** `(integer)`: SIMD arrays per engine.
- **cu_per_simd_array** `(integer)`: CUs per SIMD array.
- **simd_per_cu** `(integer)`: SIMDs per CU.
- **max_slots_scratch_cu** `(integer)`: Maximum slots for scratch CU.
- **gfx_target_version** `(integer)`: GFX target version.
- **vendor_id** `(integer)`: Vendor ID.
- **device_id** `(integer)`: Device ID.
- **location_id** `(integer)`: Location ID.
- **domain** `(integer)`: Domain identifier.
- **drm_render_minor** `(integer)`: DRM render minor version.
- **num_sdma_engines** `(integer)`: Number of SDMA engines.
- **num_sdma_xgmi_engines** `(integer)`: Number of SDMA XGMI engines.
- **num_sdma_queues_per_engine** `(integer)`: Number of SDMA queues per engine.
- **num_cp_queues** `(integer)`: Number of CP queues.
- **max_engine_clk_ccompute** `(integer)`: Maximum engine clock for compute.
- **max_engine_clk_fcompute** `(integer)`: Maximum engine clock for F compute.
- **sdma_fw_version** `(object)`: SDMA firmware version.
- **uCodeSDMA** `(integer, required)`: SDMA microcode version.
- **uCodeRes** `(integer, required)`: Reserved microcode version.
- **fw_version** `(object)`: Firmware version.
- **uCode** `(integer, required)`: Microcode version.
- **Major** `(integer, required)`: Major version.
- **Minor** `(integer, required)`: Minor version.
- **Stepping** `(integer, required)`: Stepping version.
- **capability** `(object, required)`: Agent capability flags.
- **HotPluggable** `(integer, required)`: Hot pluggable capability.
- **HSAMMUPresent** `(integer, required)`: HSAMMU present capability.
- **SharedWithGraphics** `(integer, required)`: Shared with graphics capability.
- **QueueSizePowerOfTwo** `(integer, required)`: Queue size is power of two.
- **QueueSize32bit** `(integer, required)`: Queue size is 32-bit.
- **QueueIdleEvent** `(integer, required)`: Queue idle event.
- **VALimit** `(integer, required)`: VA limit.
- **WatchPointsSupported** `(integer, required)`: Watch points supported.
- **WatchPointsTotalBits** `(integer, required)`: Total bits for watch points.
- **DoorbellType** `(integer, required)`: Doorbell type.
- **AQLQueueDoubleMap** `(integer, required)`: AQL queue double map.
- **DebugTrapSupported** `(integer, required)`: Debug trap supported.
- **WaveLaunchTrapOverrideSupported** `(integer, required)`: Wave launch trap override supported.
- **WaveLaunchModeSupported** `(integer, required)`: Wave launch mode supported.
- **PreciseMemoryOperationsSupported** `(integer, required)`: Precise memory operations supported.
- **DEPRECATED_SRAM_EDCSupport** `(integer, required)`: Deprecated SRAM EDC support.
- **Mem_EDCSupport** `(integer, required)`: Memory EDC support.
- **RASEventNotify** `(integer, required)`: RAS event notify.
- **ASICRevision** `(integer, required)`: ASIC revision.
- **SRAM_EDCSupport** `(integer, required)`: SRAM EDC support.
- **SVMAPISupported** `(integer, required)`: SVM API supported.
- **CoherentHostAccess** `(integer, required)`: Coherent host access.
- **DebugSupportedFirmware** `(integer, required)`: Debug supported firmware.
- **Reserved** `(integer, required)`: Reserved field.
- **counters** `(array, required)`: Array of counter objects.
- **Items** `(object)`
- **`agent_id`** *(object, required)*: Agent ID information.
- **`handle`** *(integer, required)*: Handle of the agent.
- **`id`** *(object, required)*: Counter ID information.
- **`handle`** *(integer, required)*: Handle of the counter.
- **`is_constant`** *(integer, required)*: Indicator if the counter value is constant.
- **`is_derived`** *(integer, required)*: Indicator if the counter value is derived.
- **`name`** *(string, required)*: Name of the counter.
- **`description`** *(string, required)*: Description of the counter.
- **`block`** *(string, required)*: Block information of the counter.
- **`expression`** *(string, required)*: Expression of the counter.
- **`dimension_ids`** *(array, required)*: Array of dimension IDs.
- **agent_id** *(object, required)*: Agent ID information.
- **handle** *(integer, required)*: Handle of the agent.
- **id** *(object, required)*: Counter ID information.
- **handle** *(integer, required)*: Handle of the counter.
- **is_constant** *(integer, required)*: Indicator if the counter value is constant.
- **is_derived** *(integer, required)*: Indicator if the counter value is derived.
- **name** *(string, required)*: Name of the counter.
- **description** *(string, required)*: Description of the counter.
- **block** *(string, required)*: Block information of the counter.
- **expression** *(string, required)*: Expression of the counter.
- **dimension_ids** *(array, required)*: Array of dimension IDs.
- **Items** *(integer)*: Dimension ID.
- **`strings`** *(object, required)*: String records.
- **`callback_records`** *(array)*: Callback records.
- **strings** *(object, required)*: String records.
- **callback_records** *(array)*: Callback records.
- **Items** *(object)*
- **`kind`** *(string, required)*: Kind of the record.
- **`operations`** *(array, required)*: Array of operations.
- **kind** *(string, required)*: Kind of the record.
- **operations** *(array, required)*: Array of operations.
- **Items** *(string)*: Operation.
- **`buffer_records`** *(array)*: Buffer records.
- **buffer_records** *(array)*: Buffer records.
- **Items** *(object)*
- **`kind`** *(string, required)*: Kind of the record.
- **`operations`** *(array, required)*: Array of operations.
- **kind** *(string, required)*: Kind of the record.
- **operations** *(array, required)*: Array of operations.
- **Items** *(string)*: Operation.
- **`marker_api`** *(array)*: Marker API records.
- **marker_api** *(array)*: Marker API records.
- **Items** *(object)*
- **`key`** *(integer, required)*: Key of the record.
- **`value`** *(string, required)*: Value of the record.
- **`counters`** *(object)*: Counter records.
- **`dimension_ids`** *(array, required)*: Array of dimension IDs.
- **key** *(integer, required)*: Key of the record.
- **value** *(string, required)*: Value of the record.
- **counters** *(object)*: Counter records.
- **dimension_ids** *(array, required)*: Array of dimension IDs.
- **Items** *(object)*
- **`id`** *(integer, required)*: Dimension ID.
- **`instance_size`** *(integer, required)*: Size of the instance.
- **`name`** *(string, required)*: Name of the dimension.
- **``pc_sample_instructions``** *(array)*: Array of decoded
- **id** *(integer, required)*: Dimension ID.
- **instance_size** *(integer, required)*: Size of the instance.
- **name** *(string, required)*: Name of the dimension.
- **pc_sample_instructions** *(array)*: Array of decoded
instructions matching sampled PCs from pc_sample_host_trap
section.
- **``pc_sample_comments``** *(array)*: Comments matching
- **pc_sample_comments** *(array)*: Comments matching
assembly instructions from pc_sample_instructions array. If
debug symbols are available, comments provide instructions
to source-line mapping. Otherwise, a comment is an empty
string.
- **`code_objects`** *(array, required)*: Code object records.
- **code_objects** *(array, required)*: Code object records.
- **Items** *(object)*
- **`size`** *(integer, required)*: Size of the code object.
- **`code_object_id`** *(integer, required)*: ID of the code object.
- **`rocp_agent`** *(object, required)*: ROCP agent information.
- **`handle`** *(integer, required)*: Handle of the ROCP agent.
- **`hsa_agent`** *(object, required)*: HSA agent information.
- **`handle`** *(integer, required)*: Handle of the HSA agent.
- **`uri`** *(string, required)*: URI of the code object.
- **`load_base`** *(integer, required)*: Base address for loading.
- **`load_size`** *(integer, required)*: Size for loading.
- **`load_delta`** *(integer, required)*: Delta for loading.
- **`storage_type`** *(integer, required)*: Type of storage.
- **`memory_base`** *(integer, required)*: Base address for memory.
- **`memory_size`** *(integer, required)*: Size of memory.
- **`kernel_symbols`** *(array, required)*: Kernel symbol records.
- **size** *(integer, required)*: Size of the code object.
- **code_object_id** *(integer, required)*: ID of the code object.
- **rocp_agent** *(object, required)*: ROCP agent information.
- **handle** *(integer, required)*: Handle of the ROCP agent.
- **hsa_agent** *(object, required)*: HSA agent information.
- **handle** *(integer, required)*: Handle of the HSA agent.
- **uri** *(string, required)*: URI of the code object.
- **load_base** *(integer, required)*: Base address for loading.
- **load_size** *(integer, required)*: Size for loading.
- **load_delta** *(integer, required)*: Delta for loading.
- **storage_type** *(integer, required)*: Type of storage.
- **memory_base** *(integer, required)*: Base address for memory.
- **memory_size** *(integer, required)*: Size of memory.
- **kernel_symbols** *(array, required)*: Kernel symbol records.
- **Items** *(object)*
- **`size`** *(integer, required)*: Size of the kernel symbol.
- **`kernel_id`** *(integer, required)*: ID of the kernel.
- **`code_object_id`** *(integer, required)*: ID of the code object.
- **`kernel_name`** *(string, required)*: Name of the kernel.
- **`kernel_object`** *(integer, required)*: Object of the kernel.
- **`kernarg_segment_size`** *(integer, required)*: Size of the kernarg segment.
- **`kernarg_segment_alignment`** *(integer, required)*: Alignment of the kernarg segment.
- **`group_segment_size`** *(integer, required)*: Size of the group segment.
- **`private_segment_size`** *(integer, required)*: Size of the private segment.
- **`formatted_kernel_name`** *(string, required)*: Formatted name of the kernel.
- **`demangled_kernel_name`** *(string, required)*: Demangled name of the kernel.
- **`truncated_kernel_name`** *(string, required)*: Truncated name of the kernel.
- **`callback_records`** *(object, required)*: Callback record details.
- **`counter_collection`** *(array)*: Counter collection records.
- **size** *(integer, required)*: Size of the kernel symbol.
- **kernel_id** *(integer, required)*: ID of the kernel.
- **code_object_id** *(integer, required)*: ID of the code object.
- **kernel_name** *(string, required)*: Name of the kernel.
- **kernel_object** *(integer, required)*: Object of the kernel.
- **kernarg_segment_size** *(integer, required)*: Size of the kernarg segment.
- **kernarg_segment_alignment** *(integer, required)*: Alignment of the kernarg segment.
- **group_segment_size** *(integer, required)*: Size of the group segment.
- **private_segment_size** *(integer, required)*: Size of the private segment.
- **formatted_kernel_name** *(string, required)*: Formatted name of the kernel.
- **demangled_kernel_name** *(string, required)*: Demangled name of the kernel.
- **truncated_kernel_name** *(string, required)*: Truncated name of the kernel.
- **callback_records** *(object, required)*: Callback record details.
- **counter_collection** *(array)*: Counter collection records.
- **Items** *(object)*
- **`dispatch_data`** *(object, required)*: Dispatch data details.
- **`size`** *(integer, required)*: Size of the dispatch data.
- **`correlation_id`** *(object, required)*: Correlation ID information.
- **`internal`** *(integer, required)*: Internal correlation ID.
- **`external`** *(integer, required)*: External correlation ID.
- **`dispatch_info`** *(object, required)*: Dispatch information details.
- **`size`** *(integer, required)*: Size of the dispatch information.
- **`agent_id`** *(object, required)*: Agent ID information.
- **`handle`** *(integer, required)*: Handle of the agent.
- **`queue_id`** *(object, required)*: Queue ID information.
- **`handle`** *(integer, required)*: Handle of the queue.
- **`kernel_id`** *(integer, required)*: ID of the kernel.
- **`dispatch_id`** *(integer, required)*: ID of the dispatch.
- **`private_segment_size`** *(integer, required)*: Size of the private segment.
- **`group_segment_size`** *(integer, required)*: Size of the group segment.
- **`workgroup_size`** *(object, required)*: Workgroup size information.
- **`x`** *(integer, required)*: X dimension.
- **`y`** *(integer, required)*: Y dimension.
- **`z`** *(integer, required)*: Z dimension.
- **`grid_size`** *(object, required)*: Grid size information.
- **`x`** *(integer, required)*: X dimension.
- **`y`** *(integer, required)*: Y dimension.
- **`z`** *(integer, required)*: Z dimension.
- **`records`** *(array, required)*: Records.
- **dispatch_data** *(object, required)*: Dispatch data details.
- **size** *(integer, required)*: Size of the dispatch data.
- **correlation_id** *(object, required)*: Correlation ID information.
- **internal** *(integer, required)*: Internal correlation ID.
- **external** *(integer, required)*: External correlation ID.
- **dispatch_info** *(object, required)*: Dispatch information details.
- **size** *(integer, required)*: Size of the dispatch information.
- **agent_id** *(object, required)*: Agent ID information.
- **handle** *(integer, required)*: Handle of the agent.
- **queue_id** *(object, required)*: Queue ID information.
- **handle** *(integer, required)*: Handle of the queue.
- **kernel_id** *(integer, required)*: ID of the kernel.
- **dispatch_id** *(integer, required)*: ID of the dispatch.
- **private_segment_size** *(integer, required)*: Size of the private segment.
- **group_segment_size** *(integer, required)*: Size of the group segment.
- **workgroup_size** *(object, required)*: Workgroup size information.
- **x** *(integer, required)*: X dimension.
- **y** *(integer, required)*: Y dimension.
- **z** *(integer, required)*: Z dimension.
- **grid_size** *(object, required)*: Grid size information.
- **x** *(integer, required)*: X dimension.
- **y** *(integer, required)*: Y dimension.
- **z** *(integer, required)*: Z dimension.
- **records** *(array, required)*: Records.
- **Items** *(object)*
- **`counter_id`** *(object, required)*: Counter ID information.
- **`handle`** *(integer, required)*: Handle of the counter.
- **`value`** *(number, required)*: Value of the counter.
- **`thread_id`** *(integer, required)*: Thread ID.
- **`arch_vgpr_count`** *(integer, required)*: Count of Architected VGPRs.
- **`accum_vgpr_count`** *(integer, required)*: Count of Accumulation VGPRs.
- **`sgpr_count`** *(integer, required)*: Count of SGPRs.
- **`lds_block_size_v`** *(integer, required)*: Size of LDS block.
- **``pc_sample_host_trap``** *(array)*: Host Trap PC Sampling records.
- **counter_id** *(object, required)*: Counter ID information.
- **handle** *(integer, required)*: Handle of the counter.
- **value** *(number, required)*: Value of the counter.
- **thread_id** *(integer, required)*: Thread ID.
- **arch_vgpr_count** *(integer, required)*: Count of Architected VGPRs.
- **accum_vgpr_count** *(integer, required)*: Count of Accumulation VGPRs.
- **sgpr_count** *(integer, required)*: Count of SGPRs.
- **lds_block_size_v** *(integer, required)*: Size of LDS block.
- **pc_sample_host_trap** *(array)*: Host Trap PC Sampling records.
- **Items** *(object)*
- **``hw_id``** *(object)*: Describes hardware part on which sampled wave was running.
- **``chiplet``** *(integer)*: Chiplet index.
- **``wave_id``** *(integer)*: Wave slot index.
- **``simd_id``** *(integer)*: SIMD index.
- **``pipe_id``** *(integer)*: Pipe index.
- **``cu_or_wgp_id``** *(integer)*: Index of compute unit or workgroup processer.
- **``shader_array_id``** *(integer)*: Shader array index.
- **``shader_engine_id``** *(integer)*: Shader engine
- **hw_id** *(object)*: Describes hardware part on which sampled wave was running.
- **chiplet** *(integer)*: Chiplet index.
- **wave_id** *(integer)*: Wave slot index.
- **simd_id** *(integer)*: SIMD index.
- **pipe_id** *(integer)*: Pipe index.
- **cu_or_wgp_id** *(integer)*: Index of compute unit or workgroup processer.
- **shader_array_id** *(integer)*: Shader array index.
- **shader_engine_id** *(integer)*: Shader engine
index.
- **``workgroup_id``** *(integer)*: Workgroup position in the 3D.
- **``vm_id``** *(integer)*: Virtual memory ID.
- **``queue_id``** *(integer)*: Queue id.
- **``microengine_id``** *(integer)*: ACE
- **workgroup_id** *(integer)*: Workgroup position in the 3D.
- **vm_id** *(integer)*: Virtual memory ID.
- **queue_id** *(integer)*: Queue id.
- **microengine_id** *(integer)*: ACE
(microengine) index.
- **``pc``** *(object)*: Encapsulates information about
- **pc** *(object)*: Encapsulates information about
sampled PC.
- **``code_object_id``** *(integer)*: Code object id.
- **``code_object_offset``** *(integer)*: Offset within the object if the latter is known. Otherwise, virtual address of the PC.
- **``exec_mask``** *(integer)*: Execution mask indicating active SIMD lanes of sampled wave.
- **``timestamp``** *(integer)*: Timestamp.
- **``dispatch_id``** *(integer)*: Dispatch id.
- **``correlation_id``** *(object)*: Correlation ID information.
- **``internal``** *(integer)*: Internal correlation ID.
- **``external``** *(integer)*: External correlation ID.
- **``rocprofiler_dim3_t``** *(object)*: Position of the workgroup in 3D grid.
- **``x``** *(integer)*: Dimension x.
- **``y``** *(integer)*: Dimension y.
- **``z``** *(integer)*: Dimension z.
- **``wave_in_group``** *(integer)*: Wave position within the workgroup (0-31).
- **`buffer_records`** *(object, required)*: Buffer record details.
- **`kernel_dispatch`** *(array)*: Kernel dispatch records.
- **code_object_id** *(integer)*: Code object id.
- **code_object_offset** *(integer)*: Offset within the object if the latter is known. Otherwise, virtual address of the PC.
- **exec_mask** *(integer)*: Execution mask indicating active SIMD lanes of sampled wave.
- **timestamp** *(integer)*: Timestamp.
- **dispatch_id** *(integer)*: Dispatch id.
- **correlation_id** *(object)*: Correlation ID information.
- **internal** *(integer)*: Internal correlation ID.
- **external** *(integer)*: External correlation ID.
- **rocprofiler_dim3_t** *(object)*: Position of the workgroup in 3D grid.
- **x** *(integer)*: Dimension x.
- **y** *(integer)*: Dimension y.
- **z** *(integer)*: Dimension z.
- **wave_in_group** *(integer)*: Wave position within the workgroup (0-31).
- **buffer_records** *(object, required)*: Buffer record details.
- **kernel_dispatch** *(array)*: Kernel dispatch records.
- **Items** *(object)*
- **`size`** *(integer, required)*: Size of the dispatch.
- **`kind`** *(integer, required)*: Kind of the dispatch.
- **`operation`** *(integer, required)*: Operation of the dispatch.
- **`thread_id`** *(integer, required)*: Thread ID.
- **`correlation_id`** *(object, required)*: Correlation ID information.
- **`internal`** *(integer, required)*: Internal correlation ID.
- **`external`** *(integer, required)*: External correlation ID.
- **`start_timestamp`** *(integer, required)*: Start timestamp.
- **`end_timestamp`** *(integer, required)*: End timestamp.
- **`dispatch_info`** *(object, required)*: Dispatch information details.
- **`size`** *(integer, required)*: Size of the dispatch information.
- **`agent_id`** *(object, required)*: Agent ID information.
- **`handle`** *(integer, required)*: Handle of the agent.
- **`queue_id`** *(object, required)*: Queue ID information.
- **`handle`** *(integer, required)*: Handle of the queue.
- **`kernel_id`** *(integer, required)*: ID of the kernel.
- **`dispatch_id`** *(integer, required)*: ID of the dispatch.
- **`private_segment_size`** *(integer, required)*: Size of the private segment.
- **`group_segment_size`** *(integer, required)*: Size of the group segment.
- **`workgroup_size`** *(object, required)*: Workgroup size information.
- **`x`** *(integer, required)*: X dimension.
- **`y`** *(integer, required)*: Y dimension.
- **`z`** *(integer, required)*: Z dimension.
- **`grid_size`** *(object, required)*: Grid size information.
- **`x`** *(integer, required)*: X dimension.
- **`y`** *(integer, required)*: Y dimension.
- **`z`** *(integer, required)*: Z dimension.
- **`hip_api`** *(array)*: HIP API records.
- **size** *(integer, required)*: Size of the dispatch.
- **kind** *(integer, required)*: Kind of the dispatch.
- **operation** *(integer, required)*: Operation of the dispatch.
- **thread_id** *(integer, required)*: Thread ID.
- **correlation_id** *(object, required)*: Correlation ID information.
- **internal** *(integer, required)*: Internal correlation ID.
- **external** *(integer, required)*: External correlation ID.
- **start_timestamp** *(integer, required)*: Start timestamp.
- **end_timestamp** *(integer, required)*: End timestamp.
- **dispatch_info** *(object, required)*: Dispatch information details.
- **size** *(integer, required)*: Size of the dispatch information.
- **agent_id** *(object, required)*: Agent ID information.
- **handle** *(integer, required)*: Handle of the agent.
- **queue_id** *(object, required)*: Queue ID information.
- **handle** *(integer, required)*: Handle of the queue.
- **kernel_id** *(integer, required)*: ID of the kernel.
- **dispatch_id** *(integer, required)*: ID of the dispatch.
- **private_segment_size** *(integer, required)*: Size of the private segment.
- **group_segment_size** *(integer, required)*: Size of the group segment.
- **workgroup_size** *(object, required)*: Workgroup size information.
- **x** *(integer, required)*: X dimension.
- **y** *(integer, required)*: Y dimension.
- **z** *(integer, required)*: Z dimension.
- **grid_size** *(object, required)*: Grid size information.
- **x** *(integer, required)*: X dimension.
- **y** *(integer, required)*: Y dimension.
- **z** *(integer, required)*: Z dimension.
- **hip_api** *(array)*: HIP API records.
- **Items** *(object)*
- **`size`** *(integer, required)*: Size of the HIP API record.
- **`kind`** *(integer, required)*: Kind of the HIP API.
- **`operation`** *(integer, required)*: Operation of the HIP API.
- **`correlation_id`** *(object, required)*: Correlation ID information.
- **`internal`** *(integer, required)*: Internal correlation ID.
- **`external`** *(integer, required)*: External correlation ID.
- **`start_timestamp`** *(integer, required)*: Start timestamp.
- **`end_timestamp`** *(integer, required)*: End timestamp.
- **`thread_id`** *(integer, required)*: Thread ID.
- **`hsa_api`** *(array)*: HSA API records.
- **size** *(integer, required)*: Size of the HIP API record.
- **kind** *(integer, required)*: Kind of the HIP API.
- **operation** *(integer, required)*: Operation of the HIP API.
- **correlation_id** *(object, required)*: Correlation ID information.
- **internal** *(integer, required)*: Internal correlation ID.
- **external** *(integer, required)*: External correlation ID.
- **start_timestamp** *(integer, required)*: Start timestamp.
- **end_timestamp** *(integer, required)*: End timestamp.
- **thread_id** *(integer, required)*: Thread ID.
- **hsa_api** *(array)*: HSA API records.
- **Items** *(object)*
- **`size`** *(integer, required)*: Size of the HSA API record.
- **`kind`** *(integer, required)*: Kind of the HSA API.
- **`operation`** *(integer, required)*: Operation of the HSA API.
- **`correlation_id`** *(object, required)*: Correlation ID information.
- **`internal`** *(integer, required)*: Internal correlation ID.
- **`external`** *(integer, required)*: External correlation ID.
- **`start_timestamp`** *(integer, required)*: Start timestamp.
- **`end_timestamp`** *(integer, required)*: End timestamp.
- **`thread_id`** *(integer, required)*: Thread ID.
- **`marker_api`** *(array)*: Marker (ROCTx) API records.
- **size** *(integer, required)*: Size of the HSA API record.
- **kind** *(integer, required)*: Kind of the HSA API.
- **operation** *(integer, required)*: Operation of the HSA API.
- **correlation_id** *(object, required)*: Correlation ID information.
- **internal** *(integer, required)*: Internal correlation ID.
- **external** *(integer, required)*: External correlation ID.
- **start_timestamp** *(integer, required)*: Start timestamp.
- **end_timestamp** *(integer, required)*: End timestamp.
- **thread_id** *(integer, required)*: Thread ID.
- **marker_api** *(array)*: Marker (ROCTx) API records.
- **Items** *(object)*
- **`size`** *(integer, required)*: Size of the Marker API record.
- **`kind`** *(integer, required)*: Kind of the Marker API.
- **`operation`** *(integer, required)*: Operation of the Marker API.
- **`correlation_id`** *(object, required)*: Correlation ID information.
- **`internal`** *(integer, required)*: Internal correlation ID.
- **`external`** *(integer, required)*: External correlation ID.
- **`start_timestamp`** *(integer, required)*: Start timestamp.
- **`end_timestamp`** *(integer, required)*: End timestamp.
- **`thread_id`** *(integer, required)*: Thread ID.
- **`memory_copy`** *(array)*: Async memory copy records.
- **size** *(integer, required)*: Size of the Marker API record.
- **kind** *(integer, required)*: Kind of the Marker API.
- **operation** *(integer, required)*: Operation of the Marker API.
- **correlation_id** *(object, required)*: Correlation ID information.
- **internal** *(integer, required)*: Internal correlation ID.
- **external** *(integer, required)*: External correlation ID.
- **start_timestamp** *(integer, required)*: Start timestamp.
- **end_timestamp** *(integer, required)*: End timestamp.
- **thread_id** *(integer, required)*: Thread ID.
- **memory_copy** *(array)*: Async memory copy records.
- **Items** *(object)*
- **`size`** *(integer, required)*: Size of the Marker API record.
- **`kind`** *(integer, required)*: Kind of the Marker API.
- **`operation`** *(integer, required)*: Operation of the Marker API.
- **`correlation_id`** *(object, required)*: Correlation ID information.
- **`internal`** *(integer, required)*: Internal correlation ID.
- **`external`** *(integer, required)*: External correlation ID.
- **`start_timestamp`** *(integer, required)*: Start timestamp.
- **`end_timestamp`** *(integer, required)*: End timestamp.
- **`thread_id`** *(integer, required)*: Thread ID.
- **`dst_agent_id`** *(object, required)*: Destination Agent ID.
- **`handle`** *(integer, required)*: Handle of the agent.
- **`src_agent_id`** *(object, required)*: Source Agent ID.
- **`handle`** *(integer, required)*: Handle of the agent.
- **`bytes`** *(integer, required)*: Bytes copied.
- **`memory_allocation`** *(array)*: Memory allocation records.
- **size** *(integer, required)*: Size of the Marker API record.
- **kind** *(integer, required)*: Kind of the Marker API.
- **operation** *(integer, required)*: Operation of the Marker API.
- **correlation_id** *(object, required)*: Correlation ID information.
- **internal** *(integer, required)*: Internal correlation ID.
- **external** *(integer, required)*: External correlation ID.
- **start_timestamp** *(integer, required)*: Start timestamp.
- **end_timestamp** *(integer, required)*: End timestamp.
- **thread_id** *(integer, required)*: Thread ID.
- **dst_agent_id** *(object, required)*: Destination Agent ID.
- **handle** *(integer, required)*: Handle of the agent.
- **src_agent_id** *(object, required)*: Source Agent ID.
- **handle** *(integer, required)*: Handle of the agent.
- **bytes** *(integer, required)*: Bytes copied.
- **memory_allocation** *(array)*: Memory allocation records.
- **Items** *(object)*
- **`size`** *(integer, required)*: Size of the Marker API record.
- **`kind`** *(integer, required)*: Kind of the Marker API.
- **`operation`** *(integer, required)*: Operation of the Marker API.
- **`correlation_id`** *(object, required)*: Correlation ID information.
- **`internal`** *(integer, required)*: Internal correlation ID.
- **`external`** *(integer, required)*: External correlation ID.
- **`start_timestamp`** *(integer, required)*: Start timestamp.
- **`end_timestamp`** *(integer, required)*: End timestamp.
- **`thread_id`** *(integer, required)*: Thread ID.
- **`agent_id`** *(object, required)*: Agent ID.
- **`handle`** *(integer, required)*: Handle of the agent.
- **`address`** *(string, required)*: Starting address of allocation.
- **`allocation_size`** *(integer, required)*: Size of allocation.
- **`rocDecode_api`** *(array)*: rocDecode API records.
- **size** *(integer, required)*: Size of the Marker API record.
- **kind** *(integer, required)*: Kind of the Marker API.
- **operation** *(integer, required)*: Operation of the Marker API.
- **correlation_id** *(object, required)*: Correlation ID information.
- **internal** *(integer, required)*: Internal correlation ID.
- **external** *(integer, required)*: External correlation ID.
- **start_timestamp** *(integer, required)*: Start timestamp.
- **end_timestamp** *(integer, required)*: End timestamp.
- **thread_id** *(integer, required)*: Thread ID.
- **agent_id** *(object, required)*: Agent ID.
- **handle** *(integer, required)*: Handle of the agent.
- **address** *(string, required)*: Starting address of allocation.
- **allocation_size** *(integer, required)*: Size of allocation.
- **rocDecode_api** *(array)*: rocDecode API records.
- **Items** *(object)*
- **`size`** *(integer, required)*: Size of the rocDecode API record.
- **`kind`** *(integer, required)*: Kind of the rocDecode API.
- **`operation`** *(integer, required)*: Operation of the rocDecode API.
- **`correlation_id`** *(object, required)*: Correlation ID information.
- **`internal`** *(integer, required)*: Internal correlation ID.
- **`external`** *(integer, required)*: External correlation ID.
- **`start_timestamp`** *(integer, required)*: Start timestamp.
- **`end_timestamp`** *(integer, required)*: End timestamp.
- **`thread_id`** *(integer, required)*: Thread ID.
- **size** *(integer, required)*: Size of the rocDecode API record.
- **kind** *(integer, required)*: Kind of the rocDecode API.
- **operation** *(integer, required)*: Operation of the rocDecode API.
- **correlation_id** *(object, required)*: Correlation ID information.
- **internal** *(integer, required)*: Internal correlation ID.
- **external** *(integer, required)*: External correlation ID.
- **start_timestamp** *(integer, required)*: Start timestamp.
- **end_timestamp** *(integer, required)*: End timestamp.
- **thread_id** *(integer, required)*: Thread ID.