/home/docs/checkouts/readthedocs.org/user_builds/advanced-micro-devices-rocprofiler-docs/checkouts/latest/include/rocprofiler/v2/rocprofiler.h Source File

• include
• rocprofiler
• v2

rocprofiler.h

Go to the documentation of this file.

1 /******************************************************************************

2 Copyright (c) 2018 Advanced Micro Devices, Inc. All rights reserved.

3 

4 Permission is hereby granted, free of charge, to any person obtaining a copy

5 of this software and associated documentation files (the "Software"), to deal

6 in the Software without restriction, including without limitation the rights

7 to use, copy, modify, merge, publish, distribute, sublicense, and/or sell

8 copies of the Software, and to permit persons to whom the Software is

9 furnished to do so, subject to the following conditions:

10 

11 The above copyright notice and this permission notice shall be included in

12 all copies or substantial portions of the Software.

13 

14 THE SOFTWARE IS PROVIDED "AS IS", WITHOUT WARRANTY OF ANY KIND, EXPRESS OR

15 IMPLIED, INCLUDING BUT NOT LIMITED TO THE WARRANTIES OF MERCHANTABILITY,

16 FITNESS FOR A PARTICULAR PURPOSE AND NONINFRINGEMENT. IN NO EVENT SHALL THE

17 AUTHORS OR COPYRIGHT HOLDERS BE LIABLE FOR ANY CLAIM, DAMAGES OR OTHER

18 LIABILITY, WHETHER IN AN ACTION OF CONTRACT, TORT OR OTHERWISE, ARISING FROM,

19 OUT OF OR IN CONNECTION WITH THE SOFTWARE OR THE USE OR OTHER DEALINGS IN

20 THE SOFTWARE.

21 *******************************************************************************/

22 

24 //

25 // ROC Profiler API

26 //

27 // The goal of the implementation is to provide a HW specific low-level

28 // performance analysis interface for profiling of GPU compute applications.

29 // The profiling includes HW performance counters (PMC) with complex

30 // performance metrics and traces.

31 //

32 // The library can be used by a tool library loaded by HSA runtime or by

33 // higher level HW independent performance analysis API like PAPI.

34 //

35 // The library is written on C and will be based on AQLprofile AMD specific

36 // HSA extension. The library implementation requires HSA API intercepting and

37 // a profiling queue supporting a submit callback interface.

38 //

39 //

160 //

165 

167 #ifndef INC_ROCPROFILER_H_

168 #define INC_ROCPROFILER_H_

169 

170 /* Placeholder for calling convention and import/export macros */

171 #if !defined(ROCPROFILER_CALL)

172 #define ROCPROFILER_CALL

173 #endif /* !defined (ROCPROFILER_CALL) */

174 

175 #if !defined(ROCPROFILER_EXPORT_DECORATOR)

176 #if defined(__GNUC__)

177 #define ROCPROFILER_EXPORT_DECORATOR __attribute__((visibility("default")))

178 #elif defined(_MSC_VER)

179 #define ROCPROFILER_EXPORT_DECORATOR __declspec(dllexport)

180 #endif /* defined (_MSC_VER) */

181 #endif /* !defined (ROCPROFILER_EXPORT_DECORATOR) */

182 

183 #if !defined(ROCPROFILER_IMPORT_DECORATOR)

184 #if defined(__GNUC__)

185 #define ROCPROFILER_IMPORT_DECORATOR

186 #elif defined(_MSC_VER)

187 #define ROCPROFILER_IMPORT_DECORATOR __declspec(dllimport)

188 #endif /* defined (_MSC_VER) */

189 #endif /* !defined (ROCPROFILER_IMPORT_DECORATOR) */

190 

191 #define ROCPROFILER_EXPORT ROCPROFILER_EXPORT_DECORATOR ROCPROFILER_CALL

192 #define ROCPROFILER_IMPORT ROCPROFILER_IMPORT_DECORATOR ROCPROFILER_CALL

193 

194 #if !defined(ROCPROFILER)

195 #if defined(ROCPROFILER_EXPORTS)

196 #define ROCPROFILER_API ROCPROFILER_EXPORT

197 #else /* !defined (ROCPROFILER_EXPORTS) */

198 #define ROCPROFILER_API ROCPROFILER_IMPORT

199 #endif /* !defined (ROCPROFILER_EXPORTS) */

200 #endif /* !defined (ROCPROFILER) */

201 

202 #include <stddef.h>

203 #include <stdint.h>

204 

205 #ifdef __cplusplus

206 extern "C" {

207 #endif /* __cplusplus */

208 

228 #define ROCPROFILER_VERSION_9_0

229 

249 #define ROCPROFILER_VERSION_MAJOR 9

250 

255 #define ROCPROFILER_VERSION_MINOR 0

256 

264 ROCPROFILER_API uint32_t rocprofiler_version_major();

265 

273 ROCPROFILER_API uint32_t rocprofiler_version_minor();

274 

277 // TODO(aelwazir): Fix them to use the new Error codes

288 typedef enum {

292  ROCPROFILER_STATUS_SUCCESS = 0,

296  ROCPROFILER_STATUS_ERROR = -1,

300  ROCPROFILER_STATUS_ERROR_ALREADY_INITIALIZED = -2,

304  ROCPROFILER_STATUS_ERROR_NOT_INITIALIZED = -3,

308  ROCPROFILER_STATUS_ERROR_SESSION_MISSING_BUFFER = -4,

312  ROCPROFILER_STATUS_ERROR_TIMESTAMP_NOT_APPLICABLE = -5,

316  ROCPROFILER_STATUS_ERROR_AGENT_NOT_FOUND = -6,

320  ROCPROFILER_STATUS_ERROR_AGENT_INFORMATION_MISSING = -7,

324  ROCPROFILER_STATUS_ERROR_QUEUE_NOT_FOUND = -8,

328  ROCPROFILER_STATUS_ERROR_QUEUE_INFORMATION_MISSING = -9,

332  ROCPROFILER_STATUS_ERROR_KERNEL_NOT_FOUND = -10,

336  ROCPROFILER_STATUS_ERROR_KERNEL_INFORMATION_MISSING = -11,

340  ROCPROFILER_STATUS_ERROR_COUNTER_NOT_FOUND = -12,

344  ROCPROFILER_STATUS_ERROR_COUNTER_INFORMATION_MISSING = -13,

348  ROCPROFILER_STATUS_ERROR_TRACER_API_DATA_NOT_FOUND = -14,

352  ROCPROFILER_STATUS_ERROR_TRACER_API_DATA_INFORMATION_MISSING = -15,

356  ROCPROFILER_STATUS_ERROR_INCORRECT_DOMAIN = -16,

360  ROCPROFILER_STATUS_ERROR_SESSION_NOT_FOUND = -17,

365  ROCPROFILER_STATUS_ERROR_CORRUPTED_SESSION_BUFFER = -18,

369  ROCPROFILER_STATUS_ERROR_RECORD_CORRUPTED = -19,

373  ROCPROFILER_STATUS_ERROR_INCORRECT_REPLAY_MODE = -20,

377  ROCPROFILER_STATUS_ERROR_SESSION_MISSING_FILTER = -21,

381  ROCPROFILER_STATUS_ERROR_INCORRECT_SIZE = -22,

385  ROCPROFILER_STATUS_ERROR_INCORRECT_FLUSH_INTERVAL = -23,

389  ROCPROFILER_STATUS_ERROR_SESSION_FILTER_DATA_MISMATCH = -24,

393  ROCPROFILER_STATUS_ERROR_FILTER_DATA_CORRUPTED = -25,

397  ROCPROFILER_STATUS_ERROR_CORRUPTED_LABEL_DATA = -26,

401  ROCPROFILER_STATUS_ERROR_RANGE_STACK_IS_EMPTY = -27,

405  ROCPROFILER_STATUS_ERROR_PASS_NOT_STARTED = -28,

410  ROCPROFILER_STATUS_ERROR_HAS_ACTIVE_SESSION = -29,

414  ROCPROFILER_STATUS_ERROR_SESSION_NOT_ACTIVE = -30,

418  ROCPROFILER_STATUS_ERROR_FILTER_NOT_FOUND = -31,

422  ROCPROFILER_STATUS_ERROR_BUFFER_NOT_FOUND = -32,

426  ROCPROFILER_STATUS_ERROR_FILTER_NOT_SUPPORTED = -33,

430  ROCPROFILER_STATUS_ERROR_INVALID_ARGUMENTS = -34,

434  ROCPROFILER_STATUS_ERROR_INVALID_OPERATION_ID = -35,

438  ROCPROFILER_STATUS_ERROR_INVALID_DOMAIN_ID = -36,

442  ROCPROFILER_STATUS_ERROR_NOT_IMPLEMENTED = -37,

446  ROCPROFILER_STATUS_ERROR_MISMATCHED_EXTERNAL_CORRELATION_ID = -38,

447 } rocprofiler_status_t;

448 

457 ROCPROFILER_API const char* rocprofiler_error_str(rocprofiler_status_t status)

458  ROCPROFILER_VERSION_9_0;

459 

466 // TODO(aelwazir): More clear description, (think about nested!!??)

467 

476 ROCPROFILER_API rocprofiler_status_t rocprofiler_initialize() ROCPROFILER_VERSION_9_0;

477 

486 ROCPROFILER_API rocprofiler_status_t rocprofiler_finalize() ROCPROFILER_VERSION_9_0;

487 

497 typedef struct {

502  uint64_t handle;

503 } rocprofiler_session_id_t;

504 

520 typedef struct {

521  uint64_t value;

522 } rocprofiler_timestamp_t;

523 

533 ROCPROFILER_API rocprofiler_status_t rocprofiler_get_timestamp(rocprofiler_timestamp_t* timestamp)

534  ROCPROFILER_VERSION_9_0;

535 

540 typedef struct {

541  rocprofiler_timestamp_t begin;

542  rocprofiler_timestamp_t end;

543 } rocprofiler_record_header_timestamp_t;

544 

554 typedef struct {

558  uint64_t handle;

559 } rocprofiler_record_id_t;

560 

564 typedef enum {

569  ROCPROFILER_PROFILER_RECORD = 0,

573  ROCPROFILER_TRACER_RECORD = 1,

577  ROCPROFILER_ATT_TRACER_RECORD = 2,

581  ROCPROFILER_PC_SAMPLING_RECORD = 3,

585  ROCPROFILER_SPM_RECORD = 4,

589  ROCPROFILER_COUNTERS_SAMPLER_RECORD = 5

590 } rocprofiler_record_kind_t;

591 

595 typedef struct {

599  rocprofiler_record_kind_t kind;

603  rocprofiler_record_id_t id;

604 } rocprofiler_record_header_t;

605 

616 typedef struct {

621  uint64_t handle; // Topology folder serial number

622 } rocprofiler_agent_id_t;

623 

629 typedef enum {

633  ROCPROFILER_CPU_AGENT = 0,

637  ROCPROFILER_GPU_AGENT = 1

638 } rocprofiler_agent_type_t;

639 

640 // TODO(aelwazir): check if we need to report the family name as well!!?? OR

641 // return the agent itself so that they can use HSA API

645 typedef enum {

649  ROCPROFILER_AGENT_NAME = 0,

653  ROCPROFILER_AGENT_TYPE = 1

654 } rocprofiler_agent_info_kind_t;

655 

673 ROCPROFILER_API rocprofiler_status_t rocprofiler_query_agent_info_size(

674  rocprofiler_agent_info_kind_t kind, rocprofiler_agent_id_t agent_id,

675  size_t* data_size) ROCPROFILER_VERSION_9_0;

676 

694 ROCPROFILER_API rocprofiler_status_t

695 rocprofiler_query_agent_info(rocprofiler_agent_info_kind_t kind, rocprofiler_agent_id_t descriptor,

696  const char** name) ROCPROFILER_VERSION_9_0;

697 

710 typedef struct {

714  uint64_t handle;

715 } rocprofiler_queue_id_t;

716 

717 // TODO(aelwazir): Check if there is anymore Queue Information needed

721 typedef enum {

725  ROCPROFILER_QUEUE_SIZE = 0

726 } rocprofiler_queue_info_kind_t;

727 

746 ROCPROFILER_API rocprofiler_status_t rocprofiler_query_queue_info_size(

747  rocprofiler_queue_info_kind_t kind, rocprofiler_queue_id_t agent_id,

748  size_t* data_size) ROCPROFILER_VERSION_9_0;

749 

767 ROCPROFILER_API rocprofiler_status_t

768 rocprofiler_query_queue_info(rocprofiler_queue_info_kind_t kind, rocprofiler_queue_id_t descriptor,

769  const char** name) ROCPROFILER_VERSION_9_0;

770 

781 typedef struct {

785  uint64_t handle;

786 } rocprofiler_kernel_id_t;

787 

791 typedef enum {

795  ROCPROFILER_KERNEL_NAME = 0

796 } rocprofiler_kernel_info_kind_t;

797 

817 ROCPROFILER_API rocprofiler_status_t rocprofiler_query_kernel_info_size(

818  rocprofiler_kernel_info_kind_t kind, rocprofiler_kernel_id_t kernel_id,

819  size_t* data_size) ROCPROFILER_VERSION_9_0;

820 

838 ROCPROFILER_API rocprofiler_status_t rocprofiler_query_kernel_info(

839  rocprofiler_kernel_info_kind_t kind, rocprofiler_kernel_id_t kernel_id,

840  const char** data) ROCPROFILER_VERSION_9_0;

841 

847 typedef struct {

851  uint32_t value;

852 } rocprofiler_thread_id_t;

853 

873 typedef struct {

874  const char* name;

875  const char* description;

876  const char* expression;

877  uint32_t instances_count;

878  const char* block_name;

879  uint32_t block_counters;

880 } rocprofiler_counter_info_t;

881 

882 typedef int (*rocprofiler_counters_info_callback_t)(rocprofiler_counter_info_t counter,

883  const char* gpu_name,

884  uint32_t gpu_index) ROCPROFILER_VERSION_9_0;

885 

886 ROCPROFILER_API rocprofiler_status_t rocprofiler_iterate_counters(

887  rocprofiler_counters_info_callback_t counters_info_callback) ROCPROFILER_VERSION_9_0;

888 

893 typedef struct {

897  uint64_t handle;

898 } rocprofiler_counter_id_t;

899 

903 typedef enum {

907  ROCPROFILER_COUNTER_NAME = 0,

911  ROCPROFILER_COUNTER_BLOCK_ID = 2,

916  ROCPROFILER_COUNTER_HIERARCHY_LEVEL = 3

917 } rocprofiler_counter_info_kind_t;

918 

939 ROCPROFILER_API rocprofiler_status_t rocprofiler_query_counter_info_size(

940  rocprofiler_session_id_t session_id, rocprofiler_counter_info_kind_t counter_info_type,

941  rocprofiler_counter_id_t counter_id, size_t* data_size) ROCPROFILER_VERSION_9_0;

942 

961 ROCPROFILER_API rocprofiler_status_t rocprofiler_query_counter_info(

962  rocprofiler_session_id_t session_id, rocprofiler_counter_info_kind_t kind,

963  rocprofiler_counter_id_t counter_id, const char** data) ROCPROFILER_VERSION_9_0;

964 

965 typedef struct {

969  uint64_t value;

970 } rocprofiler_queue_index_t;

971 

972 // TODO(aelwazir): add more types to the values should we use unions??!!

976 typedef struct {

980  double value;

981 } rocprofiler_record_counter_value_t;

982 

988 typedef struct {

992  rocprofiler_counter_id_t counter_handler; // Counter Handler

996  rocprofiler_record_counter_value_t value; // Counter Value

997 } rocprofiler_record_counter_instance_t;

998 

1004 typedef struct {

1008  uint64_t value;

1009 } rocprofiler_record_counters_instances_count_t;

1010 

1016 typedef struct {

1020  uint64_t grid_size;

1024  uint64_t workgroup_size;

1028  uint64_t lds_size;

1032  uint64_t scratch_size;

1036  uint64_t arch_vgpr_count;

1040  uint64_t accum_vgpr_count;

1044  uint64_t sgpr_count;

1048  uint64_t wave_size;

1052  uint64_t signal_handle;

1053 

1054 } rocprofiler_kernel_properties_t;

1055 

1059 typedef struct {

1060  uint64_t value;

1061 } rocprofiler_correlation_id_t;

1062 

1070 typedef struct {

1075  rocprofiler_record_header_t header;

1080  rocprofiler_kernel_id_t kernel_id;

1085  rocprofiler_agent_id_t gpu_id;

1090  rocprofiler_queue_id_t queue_id;

1095  rocprofiler_record_header_timestamp_t timestamps;

1100  const rocprofiler_record_counter_instance_t* counters;

1104  rocprofiler_record_counters_instances_count_t counters_count; /* Counters Count */

1109  rocprofiler_kernel_properties_t kernel_properties;

1113  rocprofiler_thread_id_t thread_id;

1117  rocprofiler_queue_index_t queue_idx;

1121  rocprofiler_correlation_id_t correlation_id;

1122 } rocprofiler_record_profiler_t;

1123 

1124 typedef struct {

1125  uint32_t value;

1126 

1127 } rocprofiler_event_id_t;

1128 

1129 typedef struct {

1130  uint16_t value; // Counter Value

1131 

1132 } rocprofiler_record_spm_counters_instances_count_t;

1133 

1138 typedef struct {

1139  rocprofiler_record_spm_counters_instances_count_t counters_data[32];

1140 

1141 } rocprofiler_record_se_spm_data_t;

1142 

1143 

1150 typedef struct {

1155  rocprofiler_record_header_t header;

1156 

1160  rocprofiler_record_header_timestamp_t timestamps;

1164  rocprofiler_record_se_spm_data_t shader_engine_data[4];

1165 

1166 } rocprofiler_record_spm_t;

1167 

1171 typedef struct {

1172  void* buffer_ptr;

1173  uint32_t buffer_size;

1174 } rocprofiler_record_se_att_data_t;

1175 

1179 typedef struct {

1183  const char* filepath;

1187  uint64_t base_address;

1191  const char* data;

1195  uint64_t size;

1199  rocprofiler_timestamp_t clock_start;

1204  rocprofiler_timestamp_t clock_end;

1205 } rocprofiler_intercepted_codeobj_t;

1206 

1210 typedef enum {

1214  ROCPROFILER_CAPTURE_SYMBOLS_ONLY = 0,

1219  ROCPROFILER_CAPTURE_COPY_MEMORY = 1,

1223  ROCPROFILER_CAPTURE_COPY_FILE_AND_MEMORY = 2

1224 } rocprofiler_codeobj_capture_mode_t;

1225 

1229 typedef struct {

1233  const rocprofiler_intercepted_codeobj_t* symbols;

1237  uint64_t count;

1242  uint64_t userdata;

1243 } rocprofiler_codeobj_symbols_t;

1244 

1252 typedef struct {

1257  rocprofiler_record_header_t header;

1262  rocprofiler_kernel_id_t kernel_id;

1267  rocprofiler_agent_id_t gpu_id;

1272  rocprofiler_queue_id_t queue_id;

1277  rocprofiler_kernel_properties_t kernel_properties;

1281  rocprofiler_thread_id_t thread_id;

1285  rocprofiler_queue_index_t queue_idx;

1289  uint64_t writer_id;

1293  rocprofiler_record_se_att_data_t* shader_engine_data;

1297  uint64_t shader_engine_data_count;

1301  rocprofiler_codeobj_symbols_t intercept_list;

1302 } rocprofiler_record_att_tracer_t;

1303 

1304 

1314 typedef enum {

1318  ACTIVITY_DOMAIN_HSA_API = 0,

1322  ACTIVITY_DOMAIN_HSA_OPS = 1,

1326  ACTIVITY_DOMAIN_HIP_OPS = 2,

1330  ACTIVITY_DOMAIN_HIP_API = 3,

1334  ACTIVITY_DOMAIN_KFD_API = 4,

1338  ACTIVITY_DOMAIN_EXT_API = 5,

1342  ACTIVITY_DOMAIN_ROCTX = 6,

1343  // TODO(aelwazir): Used in kernel Info, memcpy, ..etc, refer to hsa_support

1344  // TODO(aelwazir): Move HSA Events to hsa_support

1348  ACTIVITY_DOMAIN_HSA_EVT = 7,

1349  ACTIVITY_DOMAIN_NUMBER

1350 } rocprofiler_tracer_activity_domain_t;

1351 

1355 typedef struct {

1356  uint32_t id;

1357 } rocprofiler_tracer_operation_id_t;

1358 

1362 typedef struct {

1366  uint64_t value;

1367 } rocprofiler_tracer_activity_correlation_id_t;

1368 

1372 typedef struct {

1373  union {

1374  const struct hip_api_data_s* hip;

1375  const struct hsa_api_data_s* hsa;

1376  const struct roctx_api_data_s* roctx;

1377  };

1378 } rocprofiler_tracer_api_data_t;

1379 

1392 ROCPROFILER_API rocprofiler_status_t rocprofiler_query_tracer_operation_name(

1393  rocprofiler_tracer_activity_domain_t domain, rocprofiler_tracer_operation_id_t operation_id,

1394  const char** name);

1395 

1404 ROCPROFILER_API rocprofiler_status_t

1405 rocprofiler_tracer_operation_id(rocprofiler_tracer_activity_domain_t domain, const char* name,

1406  rocprofiler_tracer_operation_id_t* operation_id);

1407 

1411 typedef struct {

1412  uint64_t id;

1413 } rocprofiler_tracer_external_id_t;

1414 

1415 typedef enum {

1419  ROCPROFILER_PHASE_NONE = 0,

1423  ROCPROFILER_PHASE_ENTER = 1,

1427  ROCPROFILER_PHASE_EXIT = 2

1428 } rocprofiler_api_tracing_phase_t;

1429 

1437 typedef struct {

1442  rocprofiler_record_header_t header;

1446  rocprofiler_tracer_external_id_t external_id;

1450  rocprofiler_tracer_activity_domain_t domain;

1454  rocprofiler_tracer_operation_id_t operation_id;

1458  rocprofiler_tracer_api_data_t api_data;

1462  rocprofiler_tracer_activity_correlation_id_t correlation_id;

1466  rocprofiler_record_header_timestamp_t timestamps;

1471  rocprofiler_agent_id_t agent_id;

1476  rocprofiler_queue_id_t queue_id;

1480  rocprofiler_thread_id_t thread_id;

1484  rocprofiler_api_tracing_phase_t phase;

1488  const char* name;

1489 } rocprofiler_record_tracer_t;

1490 

1494 typedef struct {

1495  uint64_t value;

1496 } rocprofiler_kernel_dispatch_id_t;

1497 

1501 typedef struct {

1506  rocprofiler_kernel_dispatch_id_t dispatch_id;

1507  union {

1511  rocprofiler_timestamp_t timestamp;

1515  uint64_t cycle;

1516  };

1520  uint64_t pc;

1524  uint32_t se;

1528  rocprofiler_agent_id_t gpu_id;

1529 } rocprofiler_pc_sample_t;

1530 

1535 typedef struct {

1540  rocprofiler_record_header_t header;

1544  rocprofiler_pc_sample_t pc_sample;

1545 } rocprofiler_record_pc_sample_t;

1546 

1559 typedef enum {

1563  ROCPROFILER_BUFFER_PROPERTY_KIND_INTERVAL_FLUSH = 0,

1564  // Periodic Flush

1565  // Size

1566  // Think of using the kind as an end of the array!!??

1567 } rocprofiler_buffer_property_kind_t;

1568 

1569 typedef struct {

1570  rocprofiler_buffer_property_kind_t kind;

1571  uint64_t value;

1572 } rocprofiler_buffer_property_t;

1573 

1574 typedef struct {

1575  uint64_t value;

1576 } rocprofiler_buffer_id_t;

1577 

1578 typedef struct {

1579  uint64_t value;

1580 } rocprofiler_filter_id_t;

1581 

1597 typedef void (*rocprofiler_buffer_callback_t)(const rocprofiler_record_header_t* begin,

1598  const rocprofiler_record_header_t* end,

1599  rocprofiler_session_id_t session_id,

1600  rocprofiler_buffer_id_t buffer_id);

1601 

1616 ROCPROFILER_API rocprofiler_status_t rocprofiler_flush_data(

1617  rocprofiler_session_id_t session_id, rocprofiler_buffer_id_t buffer_id) ROCPROFILER_VERSION_9_0;

1618 

1638 ROCPROFILER_API rocprofiler_status_t rocprofiler_next_record(

1639  const rocprofiler_record_header_t* record, const rocprofiler_record_header_t** next,

1640  rocprofiler_session_id_t session_id, rocprofiler_buffer_id_t buffer_id) ROCPROFILER_VERSION_9_0;

1641 

1651 typedef enum {

1656  ROCPROFILER_NONE_REPLAY_MODE = -1,

1657 } rocprofiler_replay_mode_t;

1658 

1689 ROCPROFILER_API rocprofiler_status_t

1690 rocprofiler_create_session(rocprofiler_replay_mode_t replay_mode,

1691  rocprofiler_session_id_t* session_id) ROCPROFILER_VERSION_9_0;

1692 

1708 ROCPROFILER_API rocprofiler_status_t

1709 rocprofiler_destroy_session(rocprofiler_session_id_t session_id) ROCPROFILER_VERSION_9_0;

1710 

1716 typedef enum {

1720  ROCPROFILER_DISPATCH_TIMESTAMPS_COLLECTION = 1,

1724  ROCPROFILER_COUNTERS_COLLECTION = 2,

1728  ROCPROFILER_PC_SAMPLING_COLLECTION = 3,

1732  ROCPROFILER_ATT_TRACE_COLLECTION = 4,

1736  ROCPROFILER_SPM_COLLECTION = 5,

1740  ROCPROFILER_API_TRACE = 6,

1744  ROCPROFILER_COUNTERS_SAMPLER = 7

1745 } rocprofiler_filter_kind_t;

1746 

1751 typedef enum {

1755  ROCPROFILER_FILTER_HSA_TRACER_API_FUNCTIONS = 1,

1759  ROCPROFILER_FILTER_HIP_TRACER_API_FUNCTIONS = 2,

1763  ROCPROFILER_FILTER_GPU_NAME = 3,

1764  // TODO(aelwazir): Add more clear description on how to use?

1768  ROCPROFILER_FILTER_RANGE = 4,

1772  ROCPROFILER_FILTER_KERNEL_NAMES = 5,

1776  ROCPROFILER_FILTER_DISPATCH_IDS = 6

1777 } rocprofiler_filter_property_kind_t;

1778 

1779 // TODO(aelwazir): Another way to define this as needed

1780 typedef const char* rocprofiler_hip_function_name_t;

1781 typedef const char* rocprofiler_hsa_function_name_t;

1782 

1786 typedef enum {

1790  ROCPROFILER_ATT_COMPUTE_UNIT = 0,

1794  ROCPROFILER_ATT_VMID_MASK = 1,

1798  ROCPROFILER_ATT_SE_MASK = 5,

1802  ROCPROFILER_ATT_SIMD_SELECT = 8,

1806  ROCPROFILER_ATT_OCCUPANCY = 9,

1810  ROCPROFILER_ATT_BUFFER_SIZE = 10,

1814  ROCPROFILER_ATT_CAPTURE_MODE = 11,

1818  ROCPROFILER_ATT_PERF_MASK = 240,

1822  ROCPROFILER_ATT_PERF_CTRL = 241,

1826  ROCPROFILER_ATT_PERFCOUNTER = 242,

1830  ROCPROFILER_ATT_PERFCOUNTER_NAME = 243,

1831  ROCPROFILER_ATT_MAXVALUE,

1832 

1833  ROCPROFILER_ATT_MASK = 2,

1834  ROCPROFILER_ATT_TOKEN_MASK = 3,

1835  ROCPROFILER_ATT_TOKEN_MASK2 = 4,

1836  ROCPROFILER_ATT_SAMPLE_RATE = 6

1837 } rocprofiler_att_parameter_name_t;

1838 

1839 

1840 // att tracing parameters object

1841 typedef struct {

1842  rocprofiler_att_parameter_name_t parameter_name;

1843  union {

1844  uint32_t value;

1845  const char* counter_name;

1846  };

1847 } rocprofiler_att_parameter_t;

1848 

1854 typedef struct {

1858  rocprofiler_filter_property_kind_t kind;

1859  // TODO(aelwazir): get HIP or HSA or counters as enums

1863  union {

1864  const char** name_regex;

1865  rocprofiler_hip_function_name_t* hip_functions_names;

1866  rocprofiler_hsa_function_name_t* hsa_functions_names;

1867  uint32_t range[2];

1868  uint64_t* dispatch_ids;

1869  };

1873  uint64_t data_count;

1874 } rocprofiler_filter_property_t;

1875 

1876 typedef struct {

1880  const char** counters_names;

1884  int counters_count;

1888  uint32_t sampling_rate;

1892  rocprofiler_agent_id_t* gpu_agent_id;

1893 

1894 } rocprofiler_spm_parameter_t;

1895 

1896 typedef enum {

1897  ROCPROFILER_COUNTERS_SAMPLER_PCIE_COUNTERS = 0,

1898  ROCPROFILER_COUNTERS_SAMPLER_XGMI_COUNTERS = 1

1899 } rocprofiler_counters_sampler_counter_type_t;

1900 

1901 typedef struct {

1902  char* name;

1903  rocprofiler_counters_sampler_counter_type_t type;

1904 } rocprofiler_counters_sampler_counter_input_t;

1905 

1906 typedef struct {

1907  rocprofiler_counters_sampler_counter_type_t type;

1908  rocprofiler_record_counter_value_t value;

1909 } rocprofiler_counters_sampler_counter_output_t;

1910 

1911 typedef struct {

1915  rocprofiler_counters_sampler_counter_input_t* counters;

1919  int counters_num;

1923  uint32_t sampling_rate;

1927  uint32_t sampling_duration;

1931  uint32_t initial_delay;

1935  int gpu_agent_index;

1936 } rocprofiler_counters_sampler_parameters_t;

1937 

1938 typedef struct {

1943  rocprofiler_record_header_t header;

1948  rocprofiler_agent_id_t gpu_id;

1953  rocprofiler_counters_sampler_counter_output_t* counters;

1957  uint32_t num_counters;

1958 } rocprofiler_record_counters_sampler_t;

1959 

1963 typedef union {

1967  rocprofiler_tracer_activity_domain_t* trace_apis;

1971  const char** counters_names;

1975  rocprofiler_att_parameter_t* att_parameters;

1979  rocprofiler_spm_parameter_t* spm_parameters;

1983  rocprofiler_counters_sampler_parameters_t counters_sampler_parameters;

1984 } rocprofiler_filter_data_t;

1985 

2009 ROCPROFILER_API rocprofiler_status_t rocprofiler_create_filter(

2010  rocprofiler_session_id_t session_id, rocprofiler_filter_kind_t filter_kind,

2011  rocprofiler_filter_data_t data, uint64_t data_count, rocprofiler_filter_id_t* filter_id,

2012  rocprofiler_filter_property_t property) ROCPROFILER_VERSION_9_0;

2013 

2031 ROCPROFILER_API rocprofiler_status_t rocprofiler_set_filter_buffer(

2032  rocprofiler_session_id_t session_id, rocprofiler_filter_id_t filter_id,

2033  rocprofiler_buffer_id_t buffer_id) ROCPROFILER_VERSION_9_0;

2034 

2043 typedef void (*rocprofiler_sync_callback_t)(rocprofiler_record_tracer_t record,

2044  rocprofiler_session_id_t session_id);

2045 

2067 ROCPROFILER_API rocprofiler_status_t rocprofiler_set_api_trace_sync_callback(

2068  rocprofiler_session_id_t session_id, rocprofiler_filter_id_t filter_id,

2069  rocprofiler_sync_callback_t callback) ROCPROFILER_VERSION_9_0;

2070 

2085 ROCPROFILER_API rocprofiler_status_t rocprofiler_destroy_filter(

2086  rocprofiler_session_id_t session_id, rocprofiler_filter_id_t filter_id) ROCPROFILER_VERSION_9_0;

2087 

2111 ROCPROFILER_API rocprofiler_status_t rocprofiler_create_buffer(

2112  rocprofiler_session_id_t session_id, rocprofiler_buffer_callback_t buffer_callback,

2113  size_t buffer_size, rocprofiler_buffer_id_t* buffer_id) ROCPROFILER_VERSION_9_0;

2114 

2138 ROCPROFILER_API rocprofiler_status_t rocprofiler_set_buffer_properties(

2139  rocprofiler_session_id_t session_id, rocprofiler_buffer_id_t buffer_id,

2140  rocprofiler_buffer_property_t* buffer_properties,

2141  uint32_t buffer_properties_count) ROCPROFILER_VERSION_9_0;

2142 

2162 ROCPROFILER_API rocprofiler_status_t rocprofiler_destroy_buffer(

2163  rocprofiler_session_id_t session_id, rocprofiler_buffer_id_t buffer_id) ROCPROFILER_VERSION_9_0;

2164 

2213 ROCPROFILER_API rocprofiler_status_t rocprofiler_create_ready_session(

2214  rocprofiler_replay_mode_t replay_mode, rocprofiler_filter_kind_t filter_kind,

2215  rocprofiler_filter_data_t data, uint64_t data_count, size_t buffer_size,

2216  rocprofiler_buffer_callback_t buffer_callback, rocprofiler_session_id_t* session_id,

2217  rocprofiler_filter_property_t property,

2218  rocprofiler_sync_callback_t callback) ROCPROFILER_VERSION_9_0;

2219 

2220 // TODO(aelwazir): Multiple sessions activate for different set of filters

2240 ROCPROFILER_API rocprofiler_status_t rocprofiler_start_session(rocprofiler_session_id_t session_id)

2241  ROCPROFILER_VERSION_9_0;

2242 

2257 ROCPROFILER_API rocprofiler_status_t

2258 rocprofiler_terminate_session(rocprofiler_session_id_t session_id) ROCPROFILER_VERSION_9_0;

2259 

2266 typedef struct {

2267  double value;

2268 } rocprofiler_counter_value_t;

2269 

2270 typedef struct {

2271  char metric_name[64];

2272  rocprofiler_counter_value_t value;

2273 } rocprofiler_device_profile_metric_t;

2274 

2292 ROCPROFILER_API rocprofiler_status_t rocprofiler_device_profiling_session_create(

2293  const char** counter_names, uint64_t num_counters, rocprofiler_session_id_t* session_id,

2294  int cpu_index, int gpu_index) ROCPROFILER_VERSION_9_0;

2295 

2304 ROCPROFILER_API rocprofiler_status_t rocprofiler_device_profiling_session_start(

2305  rocprofiler_session_id_t session_id) ROCPROFILER_VERSION_9_0;

2306 

2319 ROCPROFILER_API rocprofiler_status_t rocprofiler_device_profiling_session_poll(

2320  rocprofiler_session_id_t session_id,

2321  rocprofiler_device_profile_metric_t* data) ROCPROFILER_VERSION_9_0;

2322 

2331 ROCPROFILER_API rocprofiler_status_t rocprofiler_device_profiling_session_stop(

2332  rocprofiler_session_id_t session_id) ROCPROFILER_VERSION_9_0;

2333 

2341 ROCPROFILER_API rocprofiler_status_t rocprofiler_device_profiling_session_destroy(

2342  rocprofiler_session_id_t session_id) ROCPROFILER_VERSION_9_0;

2343 

2353 ROCPROFILER_API rocprofiler_status_t

2354 rocprofiler_codeobj_capture_create(

2355  rocprofiler_record_id_t* id,

2356  rocprofiler_codeobj_capture_mode_t mode,

2357  uint64_t userdata

2358 );

2359 

2368 ROCPROFILER_API rocprofiler_status_t

2369 rocprofiler_codeobj_capture_get(rocprofiler_record_id_t id,

2370  rocprofiler_codeobj_symbols_t* capture);

2371 

2378 ROCPROFILER_API rocprofiler_status_t

2379 rocprofiler_codeobj_capture_free(rocprofiler_record_id_t id);

2380 

2387 ROCPROFILER_API rocprofiler_status_t

2388 rocprofiler_codeobj_capture_start(rocprofiler_record_id_t id);

2389 

2397 ROCPROFILER_API rocprofiler_status_t

2398 rocprofiler_codeobj_capture_stop(rocprofiler_record_id_t id);

2399 

2402 #ifdef __cplusplus

2403 } // extern "C" block

2404 #endif // __cplusplus

2405 

2406 #endif // INC_ROCPROFILER_H_

rocprofiler_codeobj_capture_start

ROCPROFILER_API rocprofiler_status_t rocprofiler_codeobj_capture_start(rocprofiler_record_id_t id)

Records the current loaded codeobjs and any following loads until stop() is called.

rocprofiler_device_profiling_session_destroy

ROCPROFILER_API rocprofiler_status_t rocprofiler_device_profiling_session_destroy(rocprofiler_session_id_t session_id) ROCPROFILER_VERSION_9_0

Destroy the device profiling session that was created previously.

rocprofiler_codeobj_capture_free

ROCPROFILER_API rocprofiler_status_t rocprofiler_codeobj_capture_free(rocprofiler_record_id_t id)

API to delete a record.

rocprofiler_device_profiling_session_stop

ROCPROFILER_API rocprofiler_status_t rocprofiler_device_profiling_session_stop(rocprofiler_session_id_t session_id) ROCPROFILER_VERSION_9_0

Stop the device profiling session that was created previously.

rocprofiler_device_profiling_session_create

ROCPROFILER_API rocprofiler_status_t rocprofiler_device_profiling_session_create(const char **counter_names, uint64_t num_counters, rocprofiler_session_id_t *session_id, int cpu_index, int gpu_index) ROCPROFILER_VERSION_9_0

Create a device profiling session.

rocprofiler_codeobj_capture_stop

ROCPROFILER_API rocprofiler_status_t rocprofiler_codeobj_capture_stop(rocprofiler_record_id_t id)

Stops recording of future codeobjs, until start() is called again.

rocprofiler_device_profiling_session_poll

ROCPROFILER_API rocprofiler_status_t rocprofiler_device_profiling_session_poll(rocprofiler_session_id_t session_id, rocprofiler_device_profile_metric_t *data) ROCPROFILER_VERSION_9_0

Poll the device profiling session to read counters from the GPU device.

rocprofiler_codeobj_capture_get

ROCPROFILER_API rocprofiler_status_t rocprofiler_codeobj_capture_get(rocprofiler_record_id_t id, rocprofiler_codeobj_symbols_t *capture)

API to get the captured codeobj.

rocprofiler_codeobj_capture_create

ROCPROFILER_API rocprofiler_status_t rocprofiler_codeobj_capture_create(rocprofiler_record_id_t *id, rocprofiler_codeobj_capture_mode_t mode, uint64_t userdata)

Creates a codeobj capture record, returned in ID.

rocprofiler_device_profiling_session_start

ROCPROFILER_API rocprofiler_status_t rocprofiler_device_profiling_session_start(rocprofiler_session_id_t session_id) ROCPROFILER_VERSION_9_0

Start the device profiling session that was created previously.

rocprofiler_record_kind_t

rocprofiler_record_kind_t

Record kind.

Definition: rocprofiler.h:564

ROCPROFILER_PC_SAMPLING_RECORD

@ ROCPROFILER_PC_SAMPLING_RECORD

Represents a PC sampling record.

Definition: rocprofiler.h:581

ROCPROFILER_TRACER_RECORD

@ ROCPROFILER_TRACER_RECORD

Represents records that have tracing data (ex.

Definition: rocprofiler.h:573

ROCPROFILER_COUNTERS_SAMPLER_RECORD

@ ROCPROFILER_COUNTERS_SAMPLER_RECORD

Represents Counters sampler records.

Definition: rocprofiler.h:589

ROCPROFILER_PROFILER_RECORD

@ ROCPROFILER_PROFILER_RECORD

Represents records that have profiling data (ex.

Definition: rocprofiler.h:569

ROCPROFILER_SPM_RECORD

@ ROCPROFILER_SPM_RECORD

Represents SPM records.

Definition: rocprofiler.h:585

ROCPROFILER_ATT_TRACER_RECORD

@ ROCPROFILER_ATT_TRACER_RECORD

Represents a ATT tracing record (Not available yet)

Definition: rocprofiler.h:577

rocprofiler_buffer_callback_t

void(* rocprofiler_buffer_callback_t)(const rocprofiler_record_header_t *begin, const rocprofiler_record_header_t *end, rocprofiler_session_id_t session_id, rocprofiler_buffer_id_t buffer_id)

Memory pool buffer callback.

Definition: rocprofiler.h:1597

rocprofiler_next_record

ROCPROFILER_API rocprofiler_status_t rocprofiler_next_record(const rocprofiler_record_header_t *record, const rocprofiler_record_header_t **next, rocprofiler_session_id_t session_id, rocprofiler_buffer_id_t buffer_id) ROCPROFILER_VERSION_9_0

Get a pointer to the next profiling record.

rocprofiler_buffer_property_kind_t

rocprofiler_buffer_property_kind_t

Buffer Property Options.

Definition: rocprofiler.h:1559

rocprofiler_flush_data

ROCPROFILER_API rocprofiler_status_t rocprofiler_flush_data(rocprofiler_session_id_t session_id, rocprofiler_buffer_id_t buffer_id) ROCPROFILER_VERSION_9_0

Flush specific Buffer.

ROCPROFILER_BUFFER_PROPERTY_KIND_INTERVAL_FLUSH

@ ROCPROFILER_BUFFER_PROPERTY_KIND_INTERVAL_FLUSH

Flush interval.

Definition: rocprofiler.h:1563

rocprofiler_query_counter_info_size

ROCPROFILER_API rocprofiler_status_t rocprofiler_query_counter_info_size(rocprofiler_session_id_t session_id, rocprofiler_counter_info_kind_t counter_info_type, rocprofiler_counter_id_t counter_id, size_t *data_size) ROCPROFILER_VERSION_9_0

Query Counter Information Data size to allow the user to allocate the right size for the information ...

rocprofiler_query_counter_info

ROCPROFILER_API rocprofiler_status_t rocprofiler_query_counter_info(rocprofiler_session_id_t session_id, rocprofiler_counter_info_kind_t kind, rocprofiler_counter_id_t counter_id, const char **data) ROCPROFILER_VERSION_9_0

Query Counter Information Data using an allocated data pointer by the user, user can get the size of ...

rocprofiler_counter_info_kind_t

rocprofiler_counter_info_kind_t

Counter Information Types, can be used by rocprofiler_query_counter_info.

Definition: rocprofiler.h:903

rocprofiler_iterate_counters

ROCPROFILER_API rocprofiler_status_t rocprofiler_iterate_counters(rocprofiler_counters_info_callback_t counters_info_callback) ROCPROFILER_VERSION_9_0

rocprofiler_codeobj_capture_mode_t

rocprofiler_codeobj_capture_mode_t

Enum defines how code object is captured for ATT and PC Sampling.

Definition: rocprofiler.h:1210

rocprofiler_counters_info_callback_t

int(* rocprofiler_counters_info_callback_t)(rocprofiler_counter_info_t counter, const char *gpu_name, uint32_t gpu_index) ROCPROFILER_VERSION_9_0

Definition: rocprofiler.h:882

ROCPROFILER_COUNTER_NAME

@ ROCPROFILER_COUNTER_NAME

Can be used to get the counter name.

Definition: rocprofiler.h:907

ROCPROFILER_COUNTER_BLOCK_ID

@ ROCPROFILER_COUNTER_BLOCK_ID

Can be used to get the block id of a counter.

Definition: rocprofiler.h:911

ROCPROFILER_COUNTER_HIERARCHY_LEVEL

@ ROCPROFILER_COUNTER_HIERARCHY_LEVEL

This is the level of hierarchy from the GFX_IP where the counter value should be collected.

Definition: rocprofiler.h:916

ROCPROFILER_CAPTURE_COPY_MEMORY

@ ROCPROFILER_CAPTURE_COPY_MEMORY

Capture symbols for file:// and memory:// type objects, and generate a copy of all kernel code for ob...

Definition: rocprofiler.h:1219

ROCPROFILER_CAPTURE_SYMBOLS_ONLY

@ ROCPROFILER_CAPTURE_SYMBOLS_ONLY

Capture file and memory paths for the loaded code object.

Definition: rocprofiler.h:1214

ROCPROFILER_CAPTURE_COPY_FILE_AND_MEMORY

@ ROCPROFILER_CAPTURE_COPY_FILE_AND_MEMORY

Capture symbols and all kernel code for file:// and memory:// type objects.

Definition: rocprofiler.h:1223

rocprofiler_spm_parameter_t::counters_names

const char ** counters_names

Counters to profile.

Definition: rocprofiler.h:1880

rocprofiler_spm_parameter_t::counters_count

int counters_count

Counters count.

Definition: rocprofiler.h:1884

rocprofiler_filter_property_t::kind

rocprofiler_filter_property_kind_t kind

Filter Property kind.

Definition: rocprofiler.h:1858

rocprofiler_kernel_properties_t::workgroup_size

uint64_t workgroup_size

workgroup size

Definition: rocprofiler.h:1024

rocprofiler_kernel_properties_t::lds_size

uint64_t lds_size

lds_size

Definition: rocprofiler.h:1028

rocprofiler_codeobj_symbols_t::userdata

uint64_t userdata

Userdata space for custom capture.

Definition: rocprofiler.h:1242

rocprofiler_counters_sampler_parameters_t::initial_delay

uint32_t initial_delay

Initial delay (ms)

Definition: rocprofiler.h:1931

rocprofiler_tracer_api_data_t::hsa

const struct hsa_api_data_s * hsa

Definition: rocprofiler.h:1375

rocprofiler_record_counters_sampler_t::counters

rocprofiler_counters_sampler_counter_output_t * counters

Counters, including identifiers to get counter information and Counters values.

Definition: rocprofiler.h:1953

rocprofiler_pc_sample_t::timestamp

rocprofiler_timestamp_t timestamp

Host timestamp.

Definition: rocprofiler.h:1511

rocprofiler_session_id_t::handle

uint64_t handle

Session Identifier to get the session or to be used to call any API that needs to deal with a specifi...

Definition: rocprofiler.h:502

rocprofiler_pc_sample_t::se

uint32_t se

Sampled shader element.

Definition: rocprofiler.h:1524

rocprofiler_filter_id_t::value

uint64_t value

Definition: rocprofiler.h:1579

rocprofiler_codeobj_symbols_t::symbols

const rocprofiler_intercepted_codeobj_t * symbols

List of symbols.

Definition: rocprofiler.h:1233

rocprofiler_record_att_tracer_t::kernel_properties

rocprofiler_kernel_properties_t kernel_properties

kernel properties, including the grid size, work group size, registers count, wave size and completio...

Definition: rocprofiler.h:1277

rocprofiler_record_att_tracer_t::shader_engine_data_count

uint64_t shader_engine_data_count

The count of the shader engine ATT data.

Definition: rocprofiler.h:1297

rocprofiler_record_att_tracer_t::thread_id

rocprofiler_thread_id_t thread_id

Thread id.

Definition: rocprofiler.h:1281

rocprofiler_record_tracer_t::api_data

rocprofiler_tracer_api_data_t api_data

API Data.

Definition: rocprofiler.h:1458

rocprofiler_kernel_id_t::handle

uint64_t handle

Kernel object identifier.

Definition: rocprofiler.h:785

rocprofiler_pc_sample_t::cycle

uint64_t cycle

GPU clock counter (not currently used)

Definition: rocprofiler.h:1515

rocprofiler_record_att_tracer_t::kernel_id

rocprofiler_kernel_id_t kernel_id

Kernel Identifier to be used by the user to get the kernel info using rocprofiler_query_kernel_info.

Definition: rocprofiler.h:1262

rocprofiler_record_profiler_t::gpu_id

rocprofiler_agent_id_t gpu_id

Agent Identifier to be used by the user to get the Agent Information using rocprofiler_query_agent_in...

Definition: rocprofiler.h:1085

rocprofiler_record_profiler_t::kernel_properties

rocprofiler_kernel_properties_t kernel_properties

kernel properties, including the grid size, work group size, registers count, wave size and completio...

Definition: rocprofiler.h:1109

rocprofiler_counters_sampler_parameters_t::sampling_duration

uint32_t sampling_duration

Total sampling duration (ms); time between sampling start/stop.

Definition: rocprofiler.h:1927

rocprofiler_tracer_activity_correlation_id_t::value

uint64_t value

Correlation ID Value.

Definition: rocprofiler.h:1366

rocprofiler_intercepted_codeobj_t::size

uint64_t size

If a copy of the codeobj is made, contains the size of the data.

Definition: rocprofiler.h:1195

rocprofiler_record_counters_sampler_t::num_counters

uint32_t num_counters

Number of counter values.

Definition: rocprofiler.h:1957

rocprofiler_counter_info_t::instances_count

uint32_t instances_count

Definition: rocprofiler.h:877

rocprofiler_record_tracer_t::phase

rocprofiler_api_tracing_phase_t phase

API Tracing phase (Enter/Exit/None(Activity Records/Asynchronous Output Records))

Definition: rocprofiler.h:1484

rocprofiler_record_profiler_t::correlation_id

rocprofiler_correlation_id_t correlation_id

Correlation id.

Definition: rocprofiler.h:1121

rocprofiler_intercepted_codeobj_t::data

const char * data

If a copy of the codeobj is made, contains the data.

Definition: rocprofiler.h:1191

rocprofiler_att_parameter_t::value

uint32_t value

Definition: rocprofiler.h:1844

rocprofiler_record_tracer_t::operation_id

rocprofiler_tracer_operation_id_t operation_id

Tracing Operation ID for HIP/HSA.

Definition: rocprofiler.h:1454

rocprofiler_counters_sampler_counter_output_t::value

rocprofiler_record_counter_value_t value

Definition: rocprofiler.h:1908

rocprofiler_spm_parameter_t::sampling_rate

uint32_t sampling_rate

Sampling rate.

Definition: rocprofiler.h:1888

rocprofiler_record_id_t::handle

uint64_t handle

Record ID handle.

Definition: rocprofiler.h:558

rocprofiler_record_counter_instance_t::counter_handler

rocprofiler_counter_id_t counter_handler

Counter Instance Identifier.

Definition: rocprofiler.h:992

rocprofiler_record_att_tracer_t::queue_idx

rocprofiler_queue_index_t queue_idx

Queue Index - packet index in the queue.

Definition: rocprofiler.h:1285

rocprofiler_buffer_id_t::value

uint64_t value

Definition: rocprofiler.h:1575

rocprofiler_record_counter_value_t::value

double value

Counter value.

Definition: rocprofiler.h:980

rocprofiler_kernel_properties_t::accum_vgpr_count

uint64_t accum_vgpr_count

accum vgpr count

Definition: rocprofiler.h:1040

rocprofiler_counter_info_t::description

const char * description

Definition: rocprofiler.h:875

rocprofiler_record_profiler_t::kernel_id

rocprofiler_kernel_id_t kernel_id

Kernel Identifier to be used by the user to get the kernel info using rocprofiler_query_kernel_info.

Definition: rocprofiler.h:1080

rocprofiler_intercepted_codeobj_t::base_address

uint64_t base_address

Addr where codeobj is loaded.

Definition: rocprofiler.h:1187

rocprofiler_record_att_tracer_t::intercept_list

rocprofiler_codeobj_symbols_t intercept_list

Filepaths for the intercepted code objects at the time of kernel dispatch.

Definition: rocprofiler.h:1301

rocprofiler_record_header_t::kind

rocprofiler_record_kind_t kind

Represents the kind of the record using rocprofiler_record_kind_t.

Definition: rocprofiler.h:599

rocprofiler_kernel_properties_t::signal_handle

uint64_t signal_handle

Dispatch completion signal handle.

Definition: rocprofiler.h:1052

rocprofiler_record_profiler_t::queue_id

rocprofiler_queue_id_t queue_id

Queue Identifier to be used by the user to get the Queue Information using rocprofiler_query_agent_in...

Definition: rocprofiler.h:1090

rocprofiler_record_pc_sample_t::pc_sample

rocprofiler_pc_sample_t pc_sample

PC sample data.

Definition: rocprofiler.h:1544

rocprofiler_record_profiler_t::thread_id

rocprofiler_thread_id_t thread_id

Thread id.

Definition: rocprofiler.h:1113

rocprofiler_record_header_timestamp_t::begin

rocprofiler_timestamp_t begin

Definition: rocprofiler.h:541

rocprofiler_thread_id_t::value

uint32_t value

Thread ID.

Definition: rocprofiler.h:851

rocprofiler_filter_property_t::hip_functions_names

rocprofiler_hip_function_name_t * hip_functions_names

Definition: rocprofiler.h:1865

rocprofiler_queue_index_t::value

uint64_t value

queue index value

Definition: rocprofiler.h:969

rocprofiler_agent_id_t::handle

uint64_t handle

a unique id to represent every agent on the system, this handle should be unique across all nodes in ...

Definition: rocprofiler.h:621

rocprofiler_record_att_tracer_t::header

rocprofiler_record_header_t header

ROCProfiler General Record base header to identify the id and kind of every record.

Definition: rocprofiler.h:1257

rocprofiler_record_tracer_t::header

rocprofiler_record_header_t header

ROCProfiler General Record base header to identify the id and kind of every record.

Definition: rocprofiler.h:1442

rocprofiler_counters_sampler_counter_input_t::type

rocprofiler_counters_sampler_counter_type_t type

Definition: rocprofiler.h:1903

rocprofiler_intercepted_codeobj_t::clock_end

rocprofiler_timestamp_t clock_end

Timestamp for the time point this codeobj was unloaded.

Definition: rocprofiler.h:1204

rocprofiler_pc_sample_t::pc

uint64_t pc

Sampled program counter.

Definition: rocprofiler.h:1520

rocprofiler_filter_property_t::dispatch_ids

uint64_t * dispatch_ids

Definition: rocprofiler.h:1868

rocprofiler_kernel_properties_t::sgpr_count

uint64_t sgpr_count

sgpr_count

Definition: rocprofiler.h:1044

rocprofiler_record_tracer_t::domain

rocprofiler_tracer_activity_domain_t domain

Activity domain id, represents the type of the APIs that are being traced.

Definition: rocprofiler.h:1450

rocprofiler_record_profiler_t::header

rocprofiler_record_header_t header

ROCProfiler General Record base header to identify the id and kind of every record.

Definition: rocprofiler.h:1075

rocprofiler_record_pc_sample_t::header

rocprofiler_record_header_t header

ROCProfiler General Record base header to identify the id and kind of every record.

Definition: rocprofiler.h:1540

rocprofiler_filter_property_t::name_regex

const char ** name_regex

Definition: rocprofiler.h:1864

rocprofiler_timestamp_t::value

uint64_t value

Definition: rocprofiler.h:521

rocprofiler_record_counter_instance_t::value

rocprofiler_record_counter_value_t value

Counter Instance Value.

Definition: rocprofiler.h:996

rocprofiler_kernel_properties_t::scratch_size

uint64_t scratch_size

scratch_size

Definition: rocprofiler.h:1032

rocprofiler_record_profiler_t::timestamps

rocprofiler_record_header_timestamp_t timestamps

Timestamps, start and end timestamps of the record data (ex.

Definition: rocprofiler.h:1095

rocprofiler_event_id_t::value

uint32_t value

Definition: rocprofiler.h:1125

rocprofiler_record_header_timestamp_t::end

rocprofiler_timestamp_t end

Definition: rocprofiler.h:542

rocprofiler_kernel_properties_t::arch_vgpr_count

uint64_t arch_vgpr_count

arch vgpr count

Definition: rocprofiler.h:1036

rocprofiler_tracer_operation_id_t::id

uint32_t id

Definition: rocprofiler.h:1356

rocprofiler_att_parameter_t::counter_name

const char * counter_name

Definition: rocprofiler.h:1845

rocprofiler_pc_sample_t::gpu_id

rocprofiler_agent_id_t gpu_id

Sampled GPU agent.

Definition: rocprofiler.h:1528

rocprofiler_filter_property_t::hsa_functions_names

rocprofiler_hsa_function_name_t * hsa_functions_names

Definition: rocprofiler.h:1866

rocprofiler_counters_sampler_parameters_t::counters_num

int counters_num

Counters count.

Definition: rocprofiler.h:1919

rocprofiler_record_counters_instances_count_t::value

uint64_t value

Counters Instances Count for every record.

Definition: rocprofiler.h:1008

rocprofiler_record_spm_t::header

rocprofiler_record_header_t header

ROCProfiler General Record base header to identify the id and kind of every record.

Definition: rocprofiler.h:1155

rocprofiler_record_profiler_t::counters_count

rocprofiler_record_counters_instances_count_t counters_count

The count of the counters that were collected by the profiler.

Definition: rocprofiler.h:1104

rocprofiler_queue_id_t::handle

uint64_t handle

Unique Id for every queue for one agent for one system.

Definition: rocprofiler.h:714

rocprofiler_counter_info_t::name

const char * name

Definition: rocprofiler.h:874

rocprofiler_tracer_external_id_t::id

uint64_t id

Definition: rocprofiler.h:1412

rocprofiler_kernel_properties_t::grid_size

uint64_t grid_size

Grid Size.

Definition: rocprofiler.h:1020

rocprofiler_record_att_tracer_t::gpu_id

rocprofiler_agent_id_t gpu_id

Agent Identifier to be used by the user to get the Agent Information using rocprofiler_query_agent_in...

Definition: rocprofiler.h:1267

rocprofiler_record_att_tracer_t::queue_id

rocprofiler_queue_id_t queue_id

Queue Identifier to be used by the user to get the Queue Information using rocprofiler_query_agent_in...

Definition: rocprofiler.h:1272

rocprofiler_counter_value_t::value

double value

Definition: rocprofiler.h:2267

rocprofiler_record_tracer_t::queue_id

rocprofiler_queue_id_t queue_id

Queue identifier that can be used as a handler in rocprofiler_query_queue_info.

Definition: rocprofiler.h:1476

rocprofiler_record_tracer_t::external_id

rocprofiler_tracer_external_id_t external_id

Tracing external ID, and ROCTX ID if domain is ACTIVITY_DOMAIN_ROCTX.

Definition: rocprofiler.h:1446

rocprofiler_tracer_api_data_t::roctx

const struct roctx_api_data_s * roctx

Definition: rocprofiler.h:1376

rocprofiler_counter_info_t::expression

const char * expression

Definition: rocprofiler.h:876

rocprofiler_tracer_api_data_t::hip

const struct hip_api_data_s * hip

Definition: rocprofiler.h:1374

rocprofiler_record_att_tracer_t::shader_engine_data

rocprofiler_record_se_att_data_t * shader_engine_data

ATT data output from each shader engine.

Definition: rocprofiler.h:1293

rocprofiler_counters_sampler_parameters_t::gpu_agent_index

int gpu_agent_index

Preferred agents to collect counters from.

Definition: rocprofiler.h:1935

rocprofiler_record_spm_counters_instances_count_t::value

uint16_t value

Definition: rocprofiler.h:1130

rocprofiler_att_parameter_t::parameter_name

rocprofiler_att_parameter_name_t parameter_name

Definition: rocprofiler.h:1842

rocprofiler_record_tracer_t::timestamps

rocprofiler_record_header_timestamp_t timestamps

Timestamps.

Definition: rocprofiler.h:1466

rocprofiler_counters_sampler_parameters_t::counters

rocprofiler_counters_sampler_counter_input_t * counters

Counters to profile.

Definition: rocprofiler.h:1915

rocprofiler_record_tracer_t::name

const char * name

Kernel Name for HIP API calls that launches kernels or ROCTx message for ROCTx api calls.

Definition: rocprofiler.h:1488

rocprofiler_filter_data_t::counters_sampler_parameters

rocprofiler_counters_sampler_parameters_t counters_sampler_parameters

sampled counters parameters

Definition: rocprofiler.h:1983

rocprofiler_counters_sampler_counter_input_t::name

char * name

Definition: rocprofiler.h:1902

rocprofiler_record_tracer_t::agent_id

rocprofiler_agent_id_t agent_id

Agent identifier that can be used as a handler in rocprofiler_query_agent_info.

Definition: rocprofiler.h:1471

rocprofiler_counters_sampler_parameters_t::sampling_rate

uint32_t sampling_rate

Sampling rate (ms)

Definition: rocprofiler.h:1923

rocprofiler_record_se_att_data_t::buffer_size

uint32_t buffer_size

Definition: rocprofiler.h:1173

rocprofiler_record_header_t::id

rocprofiler_record_id_t id

Represents the id of the record.

Definition: rocprofiler.h:603

rocprofiler_kernel_dispatch_id_t::value

uint64_t value

Definition: rocprofiler.h:1495

rocprofiler_intercepted_codeobj_t::filepath

const char * filepath

File path (file://, memory://) of the code object.

Definition: rocprofiler.h:1183

rocprofiler_counters_sampler_counter_output_t::type

rocprofiler_counters_sampler_counter_type_t type

Definition: rocprofiler.h:1907

rocprofiler_counter_info_t::block_name

const char * block_name

Definition: rocprofiler.h:878

rocprofiler_pc_sample_t::dispatch_id

rocprofiler_kernel_dispatch_id_t dispatch_id

Kernel dispatch ID.

Definition: rocprofiler.h:1506

rocprofiler_filter_data_t::counters_names

const char ** counters_names

Counters to profile.

Definition: rocprofiler.h:1971

rocprofiler_codeobj_symbols_t::count

uint64_t count

Number of symbols.

Definition: rocprofiler.h:1237

rocprofiler_record_spm_t::timestamps

rocprofiler_record_header_timestamp_t timestamps

Timestamps at which the counters were sampled.

Definition: rocprofiler.h:1160

rocprofiler_kernel_properties_t::wave_size

uint64_t wave_size

wave size

Definition: rocprofiler.h:1048

rocprofiler_buffer_property_t::kind

rocprofiler_buffer_property_kind_t kind

Definition: rocprofiler.h:1570

rocprofiler_record_se_att_data_t::buffer_ptr

void * buffer_ptr

Definition: rocprofiler.h:1172

rocprofiler_filter_data_t::att_parameters

rocprofiler_att_parameter_t * att_parameters

att parameters

Definition: rocprofiler.h:1975

rocprofiler_record_counters_sampler_t::gpu_id

rocprofiler_agent_id_t gpu_id

Agent Identifier to be used by the user to get the Agent Information using rocprofiler_query_agent_in...

Definition: rocprofiler.h:1948

rocprofiler_filter_property_t::data_count

uint64_t data_count

Data array count.

Definition: rocprofiler.h:1873

rocprofiler_correlation_id_t::value

uint64_t value

Definition: rocprofiler.h:1060

rocprofiler_counter_id_t::handle

uint64_t handle

A unique id generated for every counter requested by the user.

Definition: rocprofiler.h:897

rocprofiler_device_profile_metric_t::value

rocprofiler_counter_value_t value

Definition: rocprofiler.h:2272

rocprofiler_record_profiler_t::counters

const rocprofiler_record_counter_instance_t * counters

Counters, including identifiers to get counter information and Counters values.

Definition: rocprofiler.h:1100

rocprofiler_record_tracer_t::correlation_id

rocprofiler_tracer_activity_correlation_id_t correlation_id

Activity correlation ID.

Definition: rocprofiler.h:1462

rocprofiler_counter_info_t::block_counters

uint32_t block_counters

Definition: rocprofiler.h:879

rocprofiler_record_att_tracer_t::writer_id

uint64_t writer_id

Writer ID for counting how many kernels.

Definition: rocprofiler.h:1289

rocprofiler_filter_data_t::spm_parameters

rocprofiler_spm_parameter_t * spm_parameters

spm counters parameters

Definition: rocprofiler.h:1979

rocprofiler_filter_data_t::trace_apis

rocprofiler_tracer_activity_domain_t * trace_apis

APIs to trace.

Definition: rocprofiler.h:1967

rocprofiler_record_tracer_t::thread_id

rocprofiler_thread_id_t thread_id

Thread id.

Definition: rocprofiler.h:1480

rocprofiler_intercepted_codeobj_t::clock_start

rocprofiler_timestamp_t clock_start

Timestamp for the time point this codeobj was loaded.

Definition: rocprofiler.h:1199

rocprofiler_spm_parameter_t::gpu_agent_id

rocprofiler_agent_id_t * gpu_agent_id

Preferred agents to collect SPM on.

Definition: rocprofiler.h:1892

rocprofiler_record_counters_sampler_t::header

rocprofiler_record_header_t header

ROCProfiler General Record base header to identify the id and kind of every record.

Definition: rocprofiler.h:1943

rocprofiler_buffer_property_t::value

uint64_t value

Definition: rocprofiler.h:1571

rocprofiler_record_profiler_t::queue_idx

rocprofiler_queue_index_t queue_idx

Queue Index - packet index in the queue.

Definition: rocprofiler.h:1117

rocprofiler_query_agent_info

ROCPROFILER_API rocprofiler_status_t rocprofiler_query_agent_info(rocprofiler_agent_info_kind_t kind, rocprofiler_agent_id_t descriptor, const char **name) ROCPROFILER_VERSION_9_0

Query Agent Information Data using an allocated data pointer by the user, user can get the size of th...

rocprofiler_query_agent_info_size

ROCPROFILER_API rocprofiler_status_t rocprofiler_query_agent_info_size(rocprofiler_agent_info_kind_t kind, rocprofiler_agent_id_t agent_id, size_t *data_size) ROCPROFILER_VERSION_9_0

Query Agent Information size to allow the user to allocate the right size for the information data re...

rocprofiler_agent_info_kind_t

rocprofiler_agent_info_kind_t

Types of information that can be requested about the Agents.

Definition: rocprofiler.h:645

rocprofiler_agent_type_t

rocprofiler_agent_type_t

Using rocprofiler_query_agent_info, user can determine the type of the agent the following struct wil...

Definition: rocprofiler.h:629

ROCPROFILER_AGENT_TYPE

@ ROCPROFILER_AGENT_TYPE

GPU Agent Type.

Definition: rocprofiler.h:653

ROCPROFILER_AGENT_NAME

@ ROCPROFILER_AGENT_NAME

GPU Agent Name.

Definition: rocprofiler.h:649

ROCPROFILER_CPU_AGENT

@ ROCPROFILER_CPU_AGENT

CPU Agent.

Definition: rocprofiler.h:633

ROCPROFILER_GPU_AGENT

@ ROCPROFILER_GPU_AGENT

GPU Agent.

Definition: rocprofiler.h:637

rocprofiler_kernel_info_kind_t

rocprofiler_kernel_info_kind_t

Kernel Information Types, can be used by rocprofiler_query_kernel_info.

Definition: rocprofiler.h:791

rocprofiler_query_kernel_info

ROCPROFILER_API rocprofiler_status_t rocprofiler_query_kernel_info(rocprofiler_kernel_info_kind_t kind, rocprofiler_kernel_id_t kernel_id, const char **data) ROCPROFILER_VERSION_9_0

Query Kernel Information Data using an allocated data pointer by the user, user can get the size of t...

rocprofiler_query_kernel_info_size

ROCPROFILER_API rocprofiler_status_t rocprofiler_query_kernel_info_size(rocprofiler_kernel_info_kind_t kind, rocprofiler_kernel_id_t kernel_id, size_t *data_size) ROCPROFILER_VERSION_9_0

Query Kernel Information Data size to allow the user to allocate the right size for the information d...

ROCPROFILER_KERNEL_NAME

@ ROCPROFILER_KERNEL_NAME

Kernel Name Information Type.

Definition: rocprofiler.h:795

rocprofiler_queue_info_kind_t

rocprofiler_queue_info_kind_t

Types of information that can be requested about the Queues.

Definition: rocprofiler.h:721

rocprofiler_query_queue_info_size

ROCPROFILER_API rocprofiler_status_t rocprofiler_query_queue_info_size(rocprofiler_queue_info_kind_t kind, rocprofiler_queue_id_t agent_id, size_t *data_size) ROCPROFILER_VERSION_9_0

Query Queue Information size to allow the user to allocate the right size for the information data re...

rocprofiler_query_queue_info

ROCPROFILER_API rocprofiler_status_t rocprofiler_query_queue_info(rocprofiler_queue_info_kind_t kind, rocprofiler_queue_id_t descriptor, const char **name) ROCPROFILER_VERSION_9_0

Query Queue Information Data using an allocated data pointer by the user, user can get the size of th...

ROCPROFILER_QUEUE_SIZE

@ ROCPROFILER_QUEUE_SIZE

AMD HSA Queue Size.

Definition: rocprofiler.h:725

rocprofiler_finalize

ROCPROFILER_API rocprofiler_status_t rocprofiler_finalize() ROCPROFILER_VERSION_9_0

Finalize the API Tools.

rocprofiler_initialize

ROCPROFILER_API rocprofiler_status_t rocprofiler_initialize() ROCPROFILER_VERSION_9_0

Initialize the API Tools.

rocprofiler_filter_kind_t

rocprofiler_filter_kind_t

Definition: rocprofiler.h:1716

rocprofiler_set_filter_buffer

ROCPROFILER_API rocprofiler_status_t rocprofiler_set_filter_buffer(rocprofiler_session_id_t session_id, rocprofiler_filter_id_t filter_id, rocprofiler_buffer_id_t buffer_id) ROCPROFILER_VERSION_9_0

Set Session Filter Buffer This function will associate buffer to a specific filter.

rocprofiler_counters_sampler_counter_type_t

rocprofiler_counters_sampler_counter_type_t

Definition: rocprofiler.h:1896

rocprofiler_set_api_trace_sync_callback

ROCPROFILER_API rocprofiler_status_t rocprofiler_set_api_trace_sync_callback(rocprofiler_session_id_t session_id, rocprofiler_filter_id_t filter_id, rocprofiler_sync_callback_t callback) ROCPROFILER_VERSION_9_0

Set Session API Tracing Filter Synchronous Callback This function will associate buffer to a specific...

rocprofiler_hip_function_name_t

const char * rocprofiler_hip_function_name_t

Definition: rocprofiler.h:1780

rocprofiler_hsa_function_name_t

const char * rocprofiler_hsa_function_name_t

Definition: rocprofiler.h:1781

rocprofiler_destroy_filter

ROCPROFILER_API rocprofiler_status_t rocprofiler_destroy_filter(rocprofiler_session_id_t session_id, rocprofiler_filter_id_t filter_id) ROCPROFILER_VERSION_9_0

Destroy Session Filter This function will destroy a specific filter.

rocprofiler_set_buffer_properties

ROCPROFILER_API rocprofiler_status_t rocprofiler_set_buffer_properties(rocprofiler_session_id_t session_id, rocprofiler_buffer_id_t buffer_id, rocprofiler_buffer_property_t *buffer_properties, uint32_t buffer_properties_count) ROCPROFILER_VERSION_9_0

Setting Buffer Properties This function will set buffer properties.

rocprofiler_sync_callback_t

void(* rocprofiler_sync_callback_t)(rocprofiler_record_tracer_t record, rocprofiler_session_id_t session_id)

Synchronous Callback To be only used by rocprofiler_set_api_trace_sync_callback, please refer to rocp...

Definition: rocprofiler.h:2043

rocprofiler_create_filter

ROCPROFILER_API rocprofiler_status_t rocprofiler_create_filter(rocprofiler_session_id_t session_id, rocprofiler_filter_kind_t filter_kind, rocprofiler_filter_data_t data, uint64_t data_count, rocprofiler_filter_id_t *filter_id, rocprofiler_filter_property_t property) ROCPROFILER_VERSION_9_0

Create Session Filter This function will create filter and associate it with a specific session For e...

rocprofiler_create_buffer

ROCPROFILER_API rocprofiler_status_t rocprofiler_create_buffer(rocprofiler_session_id_t session_id, rocprofiler_buffer_callback_t buffer_callback, size_t buffer_size, rocprofiler_buffer_id_t *buffer_id) ROCPROFILER_VERSION_9_0

Create Buffer This function will create a buffer that can be associated with a filter.

rocprofiler_destroy_buffer

ROCPROFILER_API rocprofiler_status_t rocprofiler_destroy_buffer(rocprofiler_session_id_t session_id, rocprofiler_buffer_id_t buffer_id) ROCPROFILER_VERSION_9_0

Destroy Buffer This function will destroy a buffer given its id and session id.

rocprofiler_att_parameter_name_t

rocprofiler_att_parameter_name_t

ATT parameters to be used by for collection.

Definition: rocprofiler.h:1786

rocprofiler_filter_property_kind_t

rocprofiler_filter_property_kind_t

Data Filter Types to be used by ::rocprofiler_session_set_filter to add filters to a specific session...

Definition: rocprofiler.h:1751

ROCPROFILER_DISPATCH_TIMESTAMPS_COLLECTION

@ ROCPROFILER_DISPATCH_TIMESTAMPS_COLLECTION

Kernel Dispatch Timestamp collection.

Definition: rocprofiler.h:1720

ROCPROFILER_ATT_TRACE_COLLECTION

@ ROCPROFILER_ATT_TRACE_COLLECTION

ATT Tracing.

Definition: rocprofiler.h:1732

ROCPROFILER_COUNTERS_COLLECTION

@ ROCPROFILER_COUNTERS_COLLECTION

GPU Application counter collection.

Definition: rocprofiler.h:1724

ROCPROFILER_SPM_COLLECTION

@ ROCPROFILER_SPM_COLLECTION

SPM collection.

Definition: rocprofiler.h:1736

ROCPROFILER_API_TRACE

@ ROCPROFILER_API_TRACE

HIP/HSA/ROCTX/SYS Trace.

Definition: rocprofiler.h:1740

ROCPROFILER_PC_SAMPLING_COLLECTION

@ ROCPROFILER_PC_SAMPLING_COLLECTION

PC Sampling collection.

Definition: rocprofiler.h:1728

ROCPROFILER_COUNTERS_SAMPLER

@ ROCPROFILER_COUNTERS_SAMPLER

Sampled Counters.

Definition: rocprofiler.h:1744

ROCPROFILER_COUNTERS_SAMPLER_XGMI_COUNTERS

@ ROCPROFILER_COUNTERS_SAMPLER_XGMI_COUNTERS

Definition: rocprofiler.h:1898

ROCPROFILER_COUNTERS_SAMPLER_PCIE_COUNTERS

@ ROCPROFILER_COUNTERS_SAMPLER_PCIE_COUNTERS

Definition: rocprofiler.h:1897

ROCPROFILER_ATT_CAPTURE_MODE

@ ROCPROFILER_ATT_CAPTURE_MODE

Set ISA capture during ATT collection (rocprofiler_codeobj_capture_mode_t)

Definition: rocprofiler.h:1814

ROCPROFILER_ATT_VMID_MASK

@ ROCPROFILER_ATT_VMID_MASK

VMID Mask.

Definition: rocprofiler.h:1794

ROCPROFILER_ATT_SIMD_SELECT

@ ROCPROFILER_ATT_SIMD_SELECT

Set SIMD Mask (GFX9) or SIMD ID for collection (Navi)

Definition: rocprofiler.h:1802

ROCPROFILER_ATT_COMPUTE_UNIT

@ ROCPROFILER_ATT_COMPUTE_UNIT

Select the target compute unit (wgp) for profiling.

Definition: rocprofiler.h:1790

ROCPROFILER_ATT_TOKEN_MASK

@ ROCPROFILER_ATT_TOKEN_MASK

Deprecated.

Definition: rocprofiler.h:1834

ROCPROFILER_ATT_PERF_CTRL

@ ROCPROFILER_ATT_PERF_CTRL

Select collection period for perfcounters.

Definition: rocprofiler.h:1822

ROCPROFILER_ATT_MAXVALUE

@ ROCPROFILER_ATT_MAXVALUE

Definition: rocprofiler.h:1831

ROCPROFILER_ATT_TOKEN_MASK2

@ ROCPROFILER_ATT_TOKEN_MASK2

Deprecated.

Definition: rocprofiler.h:1835

ROCPROFILER_ATT_PERFCOUNTER_NAME

@ ROCPROFILER_ATT_PERFCOUNTER_NAME

Select perfcounter name (SQ block) for collection.

Definition: rocprofiler.h:1830

ROCPROFILER_ATT_PERFCOUNTER

@ ROCPROFILER_ATT_PERFCOUNTER

Select perfcounter ID (SQ block) for collection.

Definition: rocprofiler.h:1826

ROCPROFILER_ATT_OCCUPANCY

@ ROCPROFILER_ATT_OCCUPANCY

Set true for occupancy collection only.

Definition: rocprofiler.h:1806

ROCPROFILER_ATT_MASK

@ ROCPROFILER_ATT_MASK

Definition: rocprofiler.h:1833

ROCPROFILER_ATT_SAMPLE_RATE

@ ROCPROFILER_ATT_SAMPLE_RATE

Deprecated.

Definition: rocprofiler.h:1836

ROCPROFILER_ATT_BUFFER_SIZE

@ ROCPROFILER_ATT_BUFFER_SIZE

ATT collection max data size, in MB.

Definition: rocprofiler.h:1810

ROCPROFILER_ATT_SE_MASK

@ ROCPROFILER_ATT_SE_MASK

Shader engine mask for selection.

Definition: rocprofiler.h:1798

ROCPROFILER_ATT_PERF_MASK

@ ROCPROFILER_ATT_PERF_MASK

Mask of which compute units to generate perfcounters.

Definition: rocprofiler.h:1818

ROCPROFILER_FILTER_RANGE

@ ROCPROFILER_FILTER_RANGE

Add Range of calls to be traced or kernels to be profiled.

Definition: rocprofiler.h:1768

ROCPROFILER_FILTER_HIP_TRACER_API_FUNCTIONS

@ ROCPROFILER_FILTER_HIP_TRACER_API_FUNCTIONS

Add HIP API calls that will be only traced (ex.

Definition: rocprofiler.h:1759

ROCPROFILER_FILTER_HSA_TRACER_API_FUNCTIONS

@ ROCPROFILER_FILTER_HSA_TRACER_API_FUNCTIONS

Add HSA API calls that will be only traced (ex.

Definition: rocprofiler.h:1755

ROCPROFILER_FILTER_KERNEL_NAMES

@ ROCPROFILER_FILTER_KERNEL_NAMES

Add Kernel names that will be profiled or traced.

Definition: rocprofiler.h:1772

ROCPROFILER_FILTER_DISPATCH_IDS

@ ROCPROFILER_FILTER_DISPATCH_IDS

Add Kernel correlation ids that will be profiled or traced for ATT.

Definition: rocprofiler.h:1776

ROCPROFILER_FILTER_GPU_NAME

@ ROCPROFILER_FILTER_GPU_NAME

Add GPU names that will be only profiled or traced.

Definition: rocprofiler.h:1763

rocprofiler_destroy_session

ROCPROFILER_API rocprofiler_status_t rocprofiler_destroy_session(rocprofiler_session_id_t session_id) ROCPROFILER_VERSION_9_0

Destroy Session Destroy session created by rocprofiler_create_session, please refer to the samples fo...

rocprofiler_terminate_session

ROCPROFILER_API rocprofiler_status_t rocprofiler_terminate_session(rocprofiler_session_id_t session_id) ROCPROFILER_VERSION_9_0

Deactivate Session Deactivate session created by rocprofiler_create_session, please refer to the samp...

rocprofiler_create_ready_session

ROCPROFILER_API rocprofiler_status_t rocprofiler_create_ready_session(rocprofiler_replay_mode_t replay_mode, rocprofiler_filter_kind_t filter_kind, rocprofiler_filter_data_t data, uint64_t data_count, size_t buffer_size, rocprofiler_buffer_callback_t buffer_callback, rocprofiler_session_id_t *session_id, rocprofiler_filter_property_t property, rocprofiler_sync_callback_t callback) ROCPROFILER_VERSION_9_0

Create Ready Session A one call to create a ready profiling or tracing session, so that the session w...

rocprofiler_create_session

ROCPROFILER_API rocprofiler_status_t rocprofiler_create_session(rocprofiler_replay_mode_t replay_mode, rocprofiler_session_id_t *session_id) ROCPROFILER_VERSION_9_0

Create Session A ROCProfiler Session is having enough information about what needs to be collected or...

rocprofiler_replay_mode_t

rocprofiler_replay_mode_t

Replay Profiling Modes.

Definition: rocprofiler.h:1651

rocprofiler_start_session

ROCPROFILER_API rocprofiler_status_t rocprofiler_start_session(rocprofiler_session_id_t session_id) ROCPROFILER_VERSION_9_0

Activate Session Activating session created by rocprofiler_create_session, please refer to the sample...

ROCPROFILER_NONE_REPLAY_MODE

@ ROCPROFILER_NONE_REPLAY_MODE

No Replay to be done, Mostly for tracing tool or if the user wants to make sure that no replays will ...

Definition: rocprofiler.h:1656

rocprofiler_error_str

ROCPROFILER_API const char * rocprofiler_error_str(rocprofiler_status_t status) ROCPROFILER_VERSION_9_0

Query the textual description of the given error for the current thread.

rocprofiler_status_t

rocprofiler_status_t

ROCProfiler API status codes.

Definition: rocprofiler.h:288

ROCPROFILER_STATUS_ERROR_CORRUPTED_SESSION_BUFFER

@ ROCPROFILER_STATUS_ERROR_CORRUPTED_SESSION_BUFFER

The requested Session Buffer given the session identifier is corrupted or deleted.

Definition: rocprofiler.h:365

ROCPROFILER_STATUS_ERROR_TRACER_API_DATA_INFORMATION_MISSING

@ ROCPROFILER_STATUS_ERROR_TRACER_API_DATA_INFORMATION_MISSING

The requested information for the tracing API Data is missing.

Definition: rocprofiler.h:352

ROCPROFILER_STATUS_ERROR_QUEUE_INFORMATION_MISSING

@ ROCPROFILER_STATUS_ERROR_QUEUE_INFORMATION_MISSING

The requested information about the queue is not found.

Definition: rocprofiler.h:328

ROCPROFILER_STATUS_ERROR_COUNTER_INFORMATION_MISSING

@ ROCPROFILER_STATUS_ERROR_COUNTER_INFORMATION_MISSING

The requested Counter information for the given kernel is missing.

Definition: rocprofiler.h:344

ROCPROFILER_STATUS_ERROR_SESSION_MISSING_FILTER

@ ROCPROFILER_STATUS_ERROR_SESSION_MISSING_FILTER

Missing Filter for a session.

Definition: rocprofiler.h:377

ROCPROFILER_STATUS_ERROR_SESSION_MISSING_BUFFER

@ ROCPROFILER_STATUS_ERROR_SESSION_MISSING_BUFFER

Missing Buffer for a session.

Definition: rocprofiler.h:308

ROCPROFILER_STATUS_ERROR_HAS_ACTIVE_SESSION

@ ROCPROFILER_STATUS_ERROR_HAS_ACTIVE_SESSION

There is already Active session, Can't activate two session at the same time.

Definition: rocprofiler.h:410

ROCPROFILER_STATUS_ERROR_KERNEL_NOT_FOUND

@ ROCPROFILER_STATUS_ERROR_KERNEL_NOT_FOUND

Kernel is not found with given identifier.

Definition: rocprofiler.h:332

ROCPROFILER_STATUS_ERROR_FILTER_DATA_CORRUPTED

@ ROCPROFILER_STATUS_ERROR_FILTER_DATA_CORRUPTED

The given filter data is corrupted.

Definition: rocprofiler.h:393

ROCPROFILER_STATUS_ERROR_BUFFER_NOT_FOUND

@ ROCPROFILER_STATUS_ERROR_BUFFER_NOT_FOUND

The required buffer is not found for the given session.

Definition: rocprofiler.h:422

ROCPROFILER_STATUS_ERROR_COUNTER_NOT_FOUND

@ ROCPROFILER_STATUS_ERROR_COUNTER_NOT_FOUND

Counter is not found with the given identifier.

Definition: rocprofiler.h:340

ROCPROFILER_STATUS_ERROR_CORRUPTED_LABEL_DATA

@ ROCPROFILER_STATUS_ERROR_CORRUPTED_LABEL_DATA

The given label is corrupted.

Definition: rocprofiler.h:397

ROCPROFILER_STATUS_ERROR_INCORRECT_REPLAY_MODE

@ ROCPROFILER_STATUS_ERROR_INCORRECT_REPLAY_MODE

Incorrect Replay mode.

Definition: rocprofiler.h:373

ROCPROFILER_STATUS_ERROR_NOT_IMPLEMENTED

@ ROCPROFILER_STATUS_ERROR_NOT_IMPLEMENTED

The feature requested is not implemented.

Definition: rocprofiler.h:442

ROCPROFILER_STATUS_ERROR_QUEUE_NOT_FOUND

@ ROCPROFILER_STATUS_ERROR_QUEUE_NOT_FOUND

Queue is not found for the given identifier.

Definition: rocprofiler.h:324

ROCPROFILER_STATUS_ERROR_INVALID_OPERATION_ID

@ ROCPROFILER_STATUS_ERROR_INVALID_OPERATION_ID

The given operation id is not valid.

Definition: rocprofiler.h:434

ROCPROFILER_STATUS_ERROR_INVALID_DOMAIN_ID

@ ROCPROFILER_STATUS_ERROR_INVALID_DOMAIN_ID

The given domain id is not valid.

Definition: rocprofiler.h:438

ROCPROFILER_STATUS_ERROR_INCORRECT_FLUSH_INTERVAL

@ ROCPROFILER_STATUS_ERROR_INCORRECT_FLUSH_INTERVAL

Incorrect Flush interval.

Definition: rocprofiler.h:385

ROCPROFILER_STATUS_ERROR_TRACER_API_DATA_NOT_FOUND

@ ROCPROFILER_STATUS_ERROR_TRACER_API_DATA_NOT_FOUND

The requested Tracing API Data for the given data identifier is missing.

Definition: rocprofiler.h:348

ROCPROFILER_STATUS_ERROR_SESSION_NOT_FOUND

@ ROCPROFILER_STATUS_ERROR_SESSION_NOT_FOUND

The requested Session given the session identifier is not found.

Definition: rocprofiler.h:360

ROCPROFILER_STATUS_ERROR_MISMATCHED_EXTERNAL_CORRELATION_ID

@ ROCPROFILER_STATUS_ERROR_MISMATCHED_EXTERNAL_CORRELATION_ID

External Correlation id pop called without matching push.

Definition: rocprofiler.h:446

ROCPROFILER_STATUS_ERROR_SESSION_FILTER_DATA_MISMATCH

@ ROCPROFILER_STATUS_ERROR_SESSION_FILTER_DATA_MISMATCH

The session filter can't accept the given data.

Definition: rocprofiler.h:389

ROCPROFILER_STATUS_ERROR_INCORRECT_DOMAIN

@ ROCPROFILER_STATUS_ERROR_INCORRECT_DOMAIN

The given Domain is incorrect.

Definition: rocprofiler.h:356

ROCPROFILER_STATUS_ERROR_INVALID_ARGUMENTS

@ ROCPROFILER_STATUS_ERROR_INVALID_ARGUMENTS

Invalid Arguments were given to the function.

Definition: rocprofiler.h:430

ROCPROFILER_STATUS_ERROR_AGENT_NOT_FOUND

@ ROCPROFILER_STATUS_ERROR_AGENT_NOT_FOUND

Agent is not found with given identifier.

Definition: rocprofiler.h:316

ROCPROFILER_STATUS_ERROR_SESSION_NOT_ACTIVE

@ ROCPROFILER_STATUS_ERROR_SESSION_NOT_ACTIVE

Can't terminate a non active session.

Definition: rocprofiler.h:414

ROCPROFILER_STATUS_ERROR

@ ROCPROFILER_STATUS_ERROR

A generic error has occurred.

Definition: rocprofiler.h:296

ROCPROFILER_STATUS_ERROR_KERNEL_INFORMATION_MISSING

@ ROCPROFILER_STATUS_ERROR_KERNEL_INFORMATION_MISSING

The requested information about the kernel is not found.

Definition: rocprofiler.h:336

ROCPROFILER_STATUS_ERROR_RANGE_STACK_IS_EMPTY

@ ROCPROFILER_STATUS_ERROR_RANGE_STACK_IS_EMPTY

There is no label in the labels stack to be popped.

Definition: rocprofiler.h:401

ROCPROFILER_STATUS_ERROR_TIMESTAMP_NOT_APPLICABLE

@ ROCPROFILER_STATUS_ERROR_TIMESTAMP_NOT_APPLICABLE

Timestamps can't be collected.

Definition: rocprofiler.h:312

ROCPROFILER_STATUS_ERROR_FILTER_NOT_FOUND

@ ROCPROFILER_STATUS_ERROR_FILTER_NOT_FOUND

The required filter is not found for the given session.

Definition: rocprofiler.h:418

ROCPROFILER_STATUS_ERROR_INCORRECT_SIZE

@ ROCPROFILER_STATUS_ERROR_INCORRECT_SIZE

The size given for the buffer is not applicable.

Definition: rocprofiler.h:381

ROCPROFILER_STATUS_ERROR_RECORD_CORRUPTED

@ ROCPROFILER_STATUS_ERROR_RECORD_CORRUPTED

The requested record given the record identifier is corrupted or deleted.

Definition: rocprofiler.h:369

ROCPROFILER_STATUS_ERROR_ALREADY_INITIALIZED

@ ROCPROFILER_STATUS_ERROR_ALREADY_INITIALIZED

ROCProfiler is already initialized.

Definition: rocprofiler.h:300

ROCPROFILER_STATUS_SUCCESS

@ ROCPROFILER_STATUS_SUCCESS

The function has executed successfully.

Definition: rocprofiler.h:292

ROCPROFILER_STATUS_ERROR_PASS_NOT_STARTED

@ ROCPROFILER_STATUS_ERROR_PASS_NOT_STARTED

There is no pass that started.

Definition: rocprofiler.h:405

ROCPROFILER_STATUS_ERROR_FILTER_NOT_SUPPORTED

@ ROCPROFILER_STATUS_ERROR_FILTER_NOT_SUPPORTED

The required Filter is not supported.

Definition: rocprofiler.h:426

ROCPROFILER_STATUS_ERROR_AGENT_INFORMATION_MISSING

@ ROCPROFILER_STATUS_ERROR_AGENT_INFORMATION_MISSING

Agent information is missing for the given identifier.

Definition: rocprofiler.h:320

ROCPROFILER_STATUS_ERROR_NOT_INITIALIZED

@ ROCPROFILER_STATUS_ERROR_NOT_INITIALIZED

ROCProfiler is not initialized.

Definition: rocprofiler.h:304

ROCPROFILER_VERSION_9_0

#define ROCPROFILER_VERSION_9_0

The function was introduced in version 9.0 of the interface and has the symbol version string of "ROC...

Definition: rocprofiler.h:228

rocprofiler_get_timestamp

ROCPROFILER_API rocprofiler_status_t rocprofiler_get_timestamp(rocprofiler_timestamp_t *timestamp) ROCPROFILER_VERSION_9_0

Get the system clock timestamp.

rocprofiler_tracer_activity_domain_t

rocprofiler_tracer_activity_domain_t

Traced API domains.

Definition: rocprofiler.h:1314

rocprofiler_tracer_operation_id

ROCPROFILER_API rocprofiler_status_t rocprofiler_tracer_operation_id(rocprofiler_tracer_activity_domain_t domain, const char *name, rocprofiler_tracer_operation_id_t *operation_id)

Get Tracer API Operation ID.

rocprofiler_api_tracing_phase_t

rocprofiler_api_tracing_phase_t

Definition: rocprofiler.h:1415

rocprofiler_query_tracer_operation_name

ROCPROFILER_API rocprofiler_status_t rocprofiler_query_tracer_operation_name(rocprofiler_tracer_activity_domain_t domain, rocprofiler_tracer_operation_id_t operation_id, const char **name)

Get Tracer API Function Name.

ACTIVITY_DOMAIN_ROCTX

@ ACTIVITY_DOMAIN_ROCTX

ROCTX domain.

Definition: rocprofiler.h:1342

ACTIVITY_DOMAIN_EXT_API

@ ACTIVITY_DOMAIN_EXT_API

External ID domain.

Definition: rocprofiler.h:1338

ACTIVITY_DOMAIN_HSA_EVT

@ ACTIVITY_DOMAIN_HSA_EVT

HSA events (Device Activity)

Definition: rocprofiler.h:1348

ACTIVITY_DOMAIN_HSA_OPS

@ ACTIVITY_DOMAIN_HSA_OPS

HSA async activity domain.

Definition: rocprofiler.h:1322

ACTIVITY_DOMAIN_HIP_API

@ ACTIVITY_DOMAIN_HIP_API

HIP API domain.

Definition: rocprofiler.h:1330

ACTIVITY_DOMAIN_NUMBER

@ ACTIVITY_DOMAIN_NUMBER

Definition: rocprofiler.h:1349

ACTIVITY_DOMAIN_HSA_API

@ ACTIVITY_DOMAIN_HSA_API

HSA API domain.

Definition: rocprofiler.h:1318

ACTIVITY_DOMAIN_HIP_OPS

@ ACTIVITY_DOMAIN_HIP_OPS

HIP async activity domain.

Definition: rocprofiler.h:1326

ACTIVITY_DOMAIN_KFD_API

@ ACTIVITY_DOMAIN_KFD_API

KFD API domain.

Definition: rocprofiler.h:1334

ROCPROFILER_PHASE_NONE

@ ROCPROFILER_PHASE_NONE

No phase, it is an activity record or asynchronous output data.

Definition: rocprofiler.h:1419

ROCPROFILER_PHASE_ENTER

@ ROCPROFILER_PHASE_ENTER

Enter phase for API calls.

Definition: rocprofiler.h:1423

ROCPROFILER_PHASE_EXIT

@ ROCPROFILER_PHASE_EXIT

Exit phase for API calls.

Definition: rocprofiler.h:1427

rocprofiler_version_minor

uint32_t rocprofiler_version_minor()

rocprofiler_version_major

uint32_t rocprofiler_version_major()

rocprofiler_agent_id_t

Agent ID handle, which represents a unique id to the agent reported as it can be used to retrieve Age...

Definition: rocprofiler.h:616

rocprofiler_att_parameter_t

Definition: rocprofiler.h:1841

rocprofiler_buffer_id_t

Definition: rocprofiler.h:1574

rocprofiler_buffer_property_t

Definition: rocprofiler.h:1569

rocprofiler_codeobj_symbols_t

struct to store the filepaths and their addresses for intercepted code objects

Definition: rocprofiler.h:1229

rocprofiler_correlation_id_t

Correlation ID.

Definition: rocprofiler.h:1059

rocprofiler_counter_id_t

Counter ID to be used to query counter information using rocprofiler_query_counter_info.

Definition: rocprofiler.h:893

rocprofiler_counter_info_t

Definition: rocprofiler.h:873

rocprofiler_counter_value_t

Definition: rocprofiler.h:2266

rocprofiler_counters_sampler_counter_input_t

Definition: rocprofiler.h:1901

rocprofiler_counters_sampler_counter_output_t

Definition: rocprofiler.h:1906

rocprofiler_counters_sampler_parameters_t

Definition: rocprofiler.h:1911

rocprofiler_device_profile_metric_t

Definition: rocprofiler.h:2270

rocprofiler_event_id_t

Definition: rocprofiler.h:1124

rocprofiler_filter_id_t

Definition: rocprofiler.h:1578

rocprofiler_filter_property_t

Filter Data Type filter data will be used to report required and optional filters for the sessions us...

Definition: rocprofiler.h:1854

rocprofiler_intercepted_codeobj_t

struct to store the filepaths and their addresses for intercepted code objects

Definition: rocprofiler.h:1179

rocprofiler_kernel_dispatch_id_t

Kernel dispatch correlation ID, unique across all dispatches.

Definition: rocprofiler.h:1494

rocprofiler_kernel_id_t

Kernel identifier that represent a unique id for every kernel.

Definition: rocprofiler.h:781

rocprofiler_kernel_properties_t

Kernel properties, this will represent the kernel properties such as its grid size,...

Definition: rocprofiler.h:1016

rocprofiler_pc_sample_t

An individual PC sample.

Definition: rocprofiler.h:1501

rocprofiler_queue_id_t

Unique ID handle to represent an HSA Queue of type hsa_queue_t, this id can be used by the user to ge...

Definition: rocprofiler.h:710

rocprofiler_queue_index_t

Definition: rocprofiler.h:965

rocprofiler_record_att_tracer_t

ATT tracing record structure.

Definition: rocprofiler.h:1252

rocprofiler_record_counter_instance_t

Counter Instance Structure, it will represent every counter reported in the array of counters reporte...

Definition: rocprofiler.h:988

rocprofiler_record_counter_value_t

Counter Value Structure.

Definition: rocprofiler.h:976

rocprofiler_record_counters_instances_count_t

Counters Instances Count Structure, every profiling record has this structure included to report the ...

Definition: rocprofiler.h:1004

rocprofiler_record_counters_sampler_t

Definition: rocprofiler.h:1938

rocprofiler_record_header_t

Generic ROCProfiler record header.

Definition: rocprofiler.h:595

rocprofiler_record_header_timestamp_t

Timestamps (start & end), it will be used for kernel dispatch tracing as well as API Tracing.

Definition: rocprofiler.h:540

rocprofiler_record_id_t

A unique identifier for every record.

Definition: rocprofiler.h:554

rocprofiler_record_pc_sample_t

PC sample record: contains the program counter/instruction pointer observed during periodic sampling ...

Definition: rocprofiler.h:1535

rocprofiler_record_profiler_t

Profiling record, this will represent all the information reported by the profiler regarding kernel d...

Definition: rocprofiler.h:1070

rocprofiler_record_se_att_data_t

struct to store the trace data from a shader engine.

Definition: rocprofiler.h:1171

rocprofiler_record_se_spm_data_t

Counters, including identifiers to get counter information and Counters values.

Definition: rocprofiler.h:1138

rocprofiler_record_spm_counters_instances_count_t

Definition: rocprofiler.h:1129

rocprofiler_record_spm_t

SPM record, this will represent all the information reported by the SPM regarding counters and their ...

Definition: rocprofiler.h:1150

rocprofiler_record_tracer_t

Tracing record, this will represent all the information reported by the tracer regarding APIs and the...

Definition: rocprofiler.h:1437

rocprofiler_session_id_t

Session Identifier.

Definition: rocprofiler.h:497

rocprofiler_spm_parameter_t

Definition: rocprofiler.h:1876

rocprofiler_thread_id_t

Holds the thread id.

Definition: rocprofiler.h:847

rocprofiler_timestamp_t

ROCProfiling Timestamp Type.

Definition: rocprofiler.h:520

rocprofiler_tracer_activity_correlation_id_t

Correlation identifier.

Definition: rocprofiler.h:1362

rocprofiler_tracer_api_data_t

Tracer API Calls Data Handler.

Definition: rocprofiler.h:1372

rocprofiler_tracer_external_id_t

Tracing external ID.

Definition: rocprofiler.h:1411

rocprofiler_tracer_operation_id_t

Tracing Operation ID for HIP/HSA.

Definition: rocprofiler.h:1355

rocprofiler_filter_data_t

Filter Kind Data.

Definition: rocprofiler.h:1963

ROCPROFILER_API

#define ROCPROFILER_API

Definition: rocprofiler.h:198