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

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

rocprofiler: /home/docs/checkouts/readthedocs.org/user_builds/advanced-micro-devices-rocprofiler-docs/checkouts/docs-6.1.1/include/rocprofiler/v2/rocprofiler.h Source File
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 
265 
274 
277 // TODO(aelwazir): Fix them to use the new Error codes
288 typedef enum {
448 
459 
466 // TODO(aelwazir): More clear description, (think about nested!!??)
467 
477 
487 
497 typedef struct {
502  uint64_t handle;
504 
520 typedef struct {
521  uint64_t value;
523 
535 
540 typedef struct {
544 
554 typedef struct {
558  uint64_t handle;
560 
564 typedef enum {
591 
595 typedef struct {
605 
616 typedef struct {
621  uint64_t handle; // Topology folder serial number
623 
629 typedef enum {
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 {
655 
675  size_t* data_size) ROCPROFILER_VERSION_9_0;
676 
696  const char** name) ROCPROFILER_VERSION_9_0;
697 
710 typedef struct {
714  uint64_t handle;
716 
717 // TODO(aelwazir): Check if there is anymore Queue Information needed
721 typedef enum {
727 
748  size_t* data_size) ROCPROFILER_VERSION_9_0;
749 
769  const char** name) ROCPROFILER_VERSION_9_0;
770 
781 typedef struct {
785  uint64_t handle;
787 
791 typedef enum {
797 
819  size_t* data_size) ROCPROFILER_VERSION_9_0;
820 
840  const char** data) ROCPROFILER_VERSION_9_0;
841 
847 typedef struct {
851  uint32_t value;
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;
881 
883  const char* gpu_name,
884  uint32_t gpu_index) ROCPROFILER_VERSION_9_0;
885 
888 
893 typedef struct {
897  uint64_t handle;
899 
903 typedef enum {
918 
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 
963  rocprofiler_counter_id_t counter_id, const char** data) ROCPROFILER_VERSION_9_0;
964 
965 typedef struct {
969  uint64_t value;
971 
972 // TODO(aelwazir): add more types to the values should we use unions??!!
976 typedef struct {
980  double value;
982 
988 typedef struct {
998 
1004 typedef struct {
1008  uint64_t value;
1010 
1016 typedef struct {
1020  uint64_t grid_size;
1024  uint64_t workgroup_size;
1028  uint64_t lds_size;
1032  uint64_t scratch_size;
1044  uint64_t sgpr_count;
1048  uint64_t wave_size;
1052  uint64_t signal_handle;
1053 
1055 
1059 typedef struct {
1060  uint64_t value;
1062 
1070 typedef struct {
1123 
1124 typedef struct {
1125  uint32_t value;
1126 
1128 
1129 typedef struct {
1130  uint16_t value; // Counter Value
1131 
1133 
1138 typedef struct {
1140 
1142 
1143 
1150 typedef struct {
1156 
1164  rocprofiler_record_se_spm_data_t shader_engine_data[4];
1165 
1167 
1171 typedef struct {
1172  void* buffer_ptr;
1173  uint32_t buffer_size;
1175 
1179 typedef struct {
1183  const char* filepath;
1187  uint64_t base_address;
1191  const char* data;
1195  uint64_t size;
1206 
1210 typedef enum {
1225 
1229 typedef struct {
1237  uint64_t count;
1242  uint64_t userdata;
1244 
1252 typedef struct {
1289  uint64_t writer_id;
1303 
1304 
1314 typedef enum {
1343  // TODO(aelwazir): Used in kernel Info, memcpy, ..etc, refer to hsa_support
1344  // TODO(aelwazir): Move HSA Events to hsa_support
1351 
1355 typedef struct {
1356  uint32_t id;
1358 
1362 typedef struct {
1366  uint64_t value;
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  };
1379 
1394  const char** name);
1395 
1406  rocprofiler_tracer_operation_id_t* operation_id);
1407 
1411 typedef struct {
1412  uint64_t id;
1414 
1415 typedef enum {
1429 
1437 typedef struct {
1488  const char* name;
1490 
1494 typedef struct {
1495  uint64_t value;
1497 
1501 typedef struct {
1507  union {
1515  uint64_t cycle;
1516  };
1520  uint64_t pc;
1524  uint32_t se;
1530 
1535 typedef struct {
1546 
1559 typedef enum {
1564  // Periodic Flush
1565  // Size
1566  // Think of using the kind as an end of the array!!??
1568 
1569 typedef struct {
1571  uint64_t value;
1573 
1574 typedef struct {
1575  uint64_t value;
1577 
1578 typedef struct {
1579  uint64_t value;
1581 
1598  const rocprofiler_record_header_t* end,
1599  rocprofiler_session_id_t session_id,
1600  rocprofiler_buffer_id_t buffer_id);
1601 
1618 
1639  const rocprofiler_record_header_t* record, const rocprofiler_record_header_t** next,
1641 
1651 typedef enum {
1658 
1692 
1710 
1716 typedef enum {
1746 
1751 typedef enum {
1764  // TODO(aelwazir): Add more clear description on how to use?
1778 
1779 // TODO(aelwazir): Another way to define this as needed
1782 
1786 typedef enum {
1832 
1838 
1839 
1840 // att tracing parameters object
1841 typedef struct {
1843  union {
1844  uint32_t value;
1845  const char* counter_name;
1846  };
1848 
1854 typedef struct {
1859  // TODO(aelwazir): get HIP or HSA or counters as enums
1863  union {
1864  const char** name_regex;
1867  uint32_t range[2];
1868  uint64_t* dispatch_ids;
1869  };
1873  uint64_t data_count;
1875 
1876 typedef struct {
1880  const char** counters_names;
1888  uint32_t sampling_rate;
1893 
1895 
1896 typedef enum {
1900 
1901 typedef struct {
1902  char* name;
1905 
1906 typedef struct {
1910 
1911 typedef struct {
1923  uint32_t sampling_rate;
1931  uint32_t initial_delay;
1937 
1938 typedef struct {
1957  uint32_t num_counters;
1959 
1963 typedef union {
1971  const char** counters_names;
1985 
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,
2013 
2032  rocprofiler_session_id_t session_id, rocprofiler_filter_id_t filter_id,
2034 
2044  rocprofiler_session_id_t session_id);
2045 
2068  rocprofiler_session_id_t session_id, rocprofiler_filter_id_t filter_id,
2070 
2087 
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 
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 
2164 
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,
2219 
2220 // TODO(aelwazir): Multiple sessions activate for different set of filters
2242 
2259 
2266 typedef struct {
2267  double value;
2269 
2270 typedef struct {
2271  char metric_name[64];
2274 
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 
2306 
2320  rocprofiler_session_id_t session_id,
2322 
2333 
2343 
2357  uint64_t userdata
2358 );
2359 
2371 
2380 
2389 
2399 
2402 #ifdef __cplusplus
2403 } // extern "C" block
2404 #endif // __cplusplus
2405 
2406 #endif // INC_ROCPROFILER_H_
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_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_API rocprofiler_status_t rocprofiler_codeobj_capture_free(rocprofiler_record_id_t id)
API to delete a record.
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_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_API rocprofiler_status_t rocprofiler_codeobj_capture_stop(rocprofiler_record_id_t id)
Stops recording of future codeobjs, until start() is called again.
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_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_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_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
Record kind.
Definition: rocprofiler.h:564
@ ROCPROFILER_PC_SAMPLING_RECORD
Represents a PC sampling record.
Definition: rocprofiler.h:581
@ ROCPROFILER_TRACER_RECORD
Represents records that have tracing data (ex.
Definition: rocprofiler.h:573
@ ROCPROFILER_COUNTERS_SAMPLER_RECORD
Represents Counters sampler records.
Definition: rocprofiler.h:589
@ ROCPROFILER_PROFILER_RECORD
Represents records that have profiling data (ex.
Definition: rocprofiler.h:569
@ ROCPROFILER_SPM_RECORD
Represents SPM records.
Definition: rocprofiler.h:585
@ ROCPROFILER_ATT_TRACER_RECORD
Represents a ATT tracing record (Not available yet)
Definition: rocprofiler.h:577
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_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
Buffer Property Options.
Definition: rocprofiler.h:1559
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
Flush interval.
Definition: rocprofiler.h:1563
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_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
Counter Information Types, can be used by rocprofiler_query_counter_info.
Definition: rocprofiler.h:903
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
Enum defines how code object is captured for ATT and PC Sampling.
Definition: rocprofiler.h:1210
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
Can be used to get the counter name.
Definition: rocprofiler.h:907
@ ROCPROFILER_COUNTER_BLOCK_ID
Can be used to get the block id of a counter.
Definition: rocprofiler.h:911
@ 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
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
Capture file and memory paths for the loaded code object.
Definition: rocprofiler.h:1214
@ ROCPROFILER_CAPTURE_COPY_FILE_AND_MEMORY
Capture symbols and all kernel code for file:// and memory:// type objects.
Definition: rocprofiler.h:1223
const char ** counters_names
Counters to profile.
Definition: rocprofiler.h:1880
int counters_count
Counters count.
Definition: rocprofiler.h:1884
rocprofiler_filter_property_kind_t kind
Filter Property kind.
Definition: rocprofiler.h:1858
uint64_t workgroup_size
workgroup size
Definition: rocprofiler.h:1024
uint64_t lds_size
lds_size
Definition: rocprofiler.h:1028
uint64_t userdata
Userdata space for custom capture.
Definition: rocprofiler.h:1242
uint32_t initial_delay
Initial delay (ms)
Definition: rocprofiler.h:1931
const struct hsa_api_data_s * hsa
Definition: rocprofiler.h:1375
rocprofiler_counters_sampler_counter_output_t * counters
Counters, including identifiers to get counter information and Counters values.
Definition: rocprofiler.h:1953
rocprofiler_timestamp_t timestamp
Host timestamp.
Definition: rocprofiler.h:1511
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
uint32_t se
Sampled shader element.
Definition: rocprofiler.h:1524
uint64_t value
Definition: rocprofiler.h:1579
const rocprofiler_intercepted_codeobj_t * symbols
List of symbols.
Definition: rocprofiler.h:1233
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
uint64_t shader_engine_data_count
The count of the shader engine ATT data.
Definition: rocprofiler.h:1297
rocprofiler_thread_id_t thread_id
Thread id.
Definition: rocprofiler.h:1281
rocprofiler_tracer_api_data_t api_data
API Data.
Definition: rocprofiler.h:1458
uint64_t handle
Kernel object identifier.
Definition: rocprofiler.h:785
uint64_t cycle
GPU clock counter (not currently used)
Definition: rocprofiler.h:1515
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_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_kernel_properties_t kernel_properties
kernel properties, including the grid size, work group size, registers count, wave size and completio...
Definition: rocprofiler.h:1109
uint32_t sampling_duration
Total sampling duration (ms); time between sampling start/stop.
Definition: rocprofiler.h:1927
uint64_t value
Correlation ID Value.
Definition: rocprofiler.h:1366
uint64_t size
If a copy of the codeobj is made, contains the size of the data.
Definition: rocprofiler.h:1195
uint32_t num_counters
Number of counter values.
Definition: rocprofiler.h:1957
uint32_t instances_count
Definition: rocprofiler.h:877
rocprofiler_api_tracing_phase_t phase
API Tracing phase (Enter/Exit/None(Activity Records/Asynchronous Output Records))
Definition: rocprofiler.h:1484
rocprofiler_correlation_id_t correlation_id
Correlation id.
Definition: rocprofiler.h:1121
const char * data
If a copy of the codeobj is made, contains the data.
Definition: rocprofiler.h:1191
uint32_t value
Definition: rocprofiler.h:1844
rocprofiler_tracer_operation_id_t operation_id
Tracing Operation ID for HIP/HSA.
Definition: rocprofiler.h:1454
rocprofiler_record_counter_value_t value
Definition: rocprofiler.h:1908
uint32_t sampling_rate
Sampling rate.
Definition: rocprofiler.h:1888
uint64_t handle
Record ID handle.
Definition: rocprofiler.h:558
rocprofiler_counter_id_t counter_handler
Counter Instance Identifier.
Definition: rocprofiler.h:992
rocprofiler_queue_index_t queue_idx
Queue Index - packet index in the queue.
Definition: rocprofiler.h:1285
uint64_t value
Definition: rocprofiler.h:1575
double value
Counter value.
Definition: rocprofiler.h:980
uint64_t accum_vgpr_count
accum vgpr count
Definition: rocprofiler.h:1040
const char * description
Definition: rocprofiler.h:875
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
uint64_t base_address
Addr where codeobj is loaded.
Definition: rocprofiler.h:1187
rocprofiler_codeobj_symbols_t intercept_list
Filepaths for the intercepted code objects at the time of kernel dispatch.
Definition: rocprofiler.h:1301
rocprofiler_record_kind_t kind
Represents the kind of the record using rocprofiler_record_kind_t.
Definition: rocprofiler.h:599
uint64_t signal_handle
Dispatch completion signal handle.
Definition: rocprofiler.h:1052
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_pc_sample_t pc_sample
PC sample data.
Definition: rocprofiler.h:1544
rocprofiler_thread_id_t thread_id
Thread id.
Definition: rocprofiler.h:1113
rocprofiler_timestamp_t begin
Definition: rocprofiler.h:541
uint32_t value
Thread ID.
Definition: rocprofiler.h:851
rocprofiler_hip_function_name_t * hip_functions_names
Definition: rocprofiler.h:1865
uint64_t value
queue index value
Definition: rocprofiler.h:969
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_header_t header
ROCProfiler General Record base header to identify the id and kind of every record.
Definition: rocprofiler.h:1257
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_type_t type
Definition: rocprofiler.h:1903
rocprofiler_timestamp_t clock_end
Timestamp for the time point this codeobj was unloaded.
Definition: rocprofiler.h:1204
uint64_t pc
Sampled program counter.
Definition: rocprofiler.h:1520
uint64_t * dispatch_ids
Definition: rocprofiler.h:1868
uint64_t sgpr_count
sgpr_count
Definition: rocprofiler.h:1044
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_header_t header
ROCProfiler General Record base header to identify the id and kind of every record.
Definition: rocprofiler.h:1075
rocprofiler_record_header_t header
ROCProfiler General Record base header to identify the id and kind of every record.
Definition: rocprofiler.h:1540
const char ** name_regex
Definition: rocprofiler.h:1864
uint64_t value
Definition: rocprofiler.h:521
rocprofiler_record_counter_value_t value
Counter Instance Value.
Definition: rocprofiler.h:996
uint64_t scratch_size
scratch_size
Definition: rocprofiler.h:1032
rocprofiler_record_header_timestamp_t timestamps
Timestamps, start and end timestamps of the record data (ex.
Definition: rocprofiler.h:1095
uint32_t value
Definition: rocprofiler.h:1125
rocprofiler_timestamp_t end
Definition: rocprofiler.h:542
uint64_t arch_vgpr_count
arch vgpr count
Definition: rocprofiler.h:1036
uint32_t id
Definition: rocprofiler.h:1356
const char * counter_name
Definition: rocprofiler.h:1845
rocprofiler_agent_id_t gpu_id
Sampled GPU agent.
Definition: rocprofiler.h:1528
rocprofiler_hsa_function_name_t * hsa_functions_names
Definition: rocprofiler.h:1866
int counters_num
Counters count.
Definition: rocprofiler.h:1919
uint64_t value
Counters Instances Count for every record.
Definition: rocprofiler.h:1008
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_counters_instances_count_t counters_count
The count of the counters that were collected by the profiler.
Definition: rocprofiler.h:1104
uint64_t handle
Unique Id for every queue for one agent for one system.
Definition: rocprofiler.h:714
const char * name
Definition: rocprofiler.h:874
uint64_t id
Definition: rocprofiler.h:1412
uint64_t grid_size
Grid Size.
Definition: rocprofiler.h:1020
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_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
double value
Definition: rocprofiler.h:2267
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_tracer_external_id_t external_id
Tracing external ID, and ROCTX ID if domain is ACTIVITY_DOMAIN_ROCTX.
Definition: rocprofiler.h:1446
const struct roctx_api_data_s * roctx
Definition: rocprofiler.h:1376
const char * expression
Definition: rocprofiler.h:876
const struct hip_api_data_s * hip
Definition: rocprofiler.h:1374
rocprofiler_record_se_att_data_t * shader_engine_data
ATT data output from each shader engine.
Definition: rocprofiler.h:1293
int gpu_agent_index
Preferred agents to collect counters from.
Definition: rocprofiler.h:1935
uint16_t value
Definition: rocprofiler.h:1130
rocprofiler_att_parameter_name_t parameter_name
Definition: rocprofiler.h:1842
rocprofiler_record_header_timestamp_t timestamps
Timestamps.
Definition: rocprofiler.h:1466
rocprofiler_counters_sampler_counter_input_t * counters
Counters to profile.
Definition: rocprofiler.h:1915
const char * name
Kernel Name for HIP API calls that launches kernels or ROCTx message for ROCTx api calls.
Definition: rocprofiler.h:1488
rocprofiler_counters_sampler_parameters_t counters_sampler_parameters
sampled counters parameters
Definition: rocprofiler.h:1983
char * name
Definition: rocprofiler.h:1902
rocprofiler_agent_id_t agent_id
Agent identifier that can be used as a handler in rocprofiler_query_agent_info.
Definition: rocprofiler.h:1471
uint32_t sampling_rate
Sampling rate (ms)
Definition: rocprofiler.h:1923
uint32_t buffer_size
Definition: rocprofiler.h:1173
rocprofiler_record_id_t id
Represents the id of the record.
Definition: rocprofiler.h:603
uint64_t value
Definition: rocprofiler.h:1495
const char * filepath
File path (file://, memory://) of the code object.
Definition: rocprofiler.h:1183
rocprofiler_counters_sampler_counter_type_t type
Definition: rocprofiler.h:1907
const char * block_name
Definition: rocprofiler.h:878
rocprofiler_kernel_dispatch_id_t dispatch_id
Kernel dispatch ID.
Definition: rocprofiler.h:1506
const char ** counters_names
Counters to profile.
Definition: rocprofiler.h:1971
uint64_t count
Number of symbols.
Definition: rocprofiler.h:1237
rocprofiler_record_header_timestamp_t timestamps
Timestamps at which the counters were sampled.
Definition: rocprofiler.h:1160
uint64_t wave_size
wave size
Definition: rocprofiler.h:1048
rocprofiler_buffer_property_kind_t kind
Definition: rocprofiler.h:1570
void * buffer_ptr
Definition: rocprofiler.h:1172
rocprofiler_att_parameter_t * att_parameters
att parameters
Definition: rocprofiler.h:1975
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
uint64_t data_count
Data array count.
Definition: rocprofiler.h:1873
uint64_t value
Definition: rocprofiler.h:1060
uint64_t handle
A unique id generated for every counter requested by the user.
Definition: rocprofiler.h:897
rocprofiler_counter_value_t value
Definition: rocprofiler.h:2272
const rocprofiler_record_counter_instance_t * counters
Counters, including identifiers to get counter information and Counters values.
Definition: rocprofiler.h:1100
rocprofiler_tracer_activity_correlation_id_t correlation_id
Activity correlation ID.
Definition: rocprofiler.h:1462
uint32_t block_counters
Definition: rocprofiler.h:879
uint64_t writer_id
Writer ID for counting how many kernels.
Definition: rocprofiler.h:1289
rocprofiler_spm_parameter_t * spm_parameters
spm counters parameters
Definition: rocprofiler.h:1979
rocprofiler_tracer_activity_domain_t * trace_apis
APIs to trace.
Definition: rocprofiler.h:1967
rocprofiler_thread_id_t thread_id
Thread id.
Definition: rocprofiler.h:1480
rocprofiler_timestamp_t clock_start
Timestamp for the time point this codeobj was loaded.
Definition: rocprofiler.h:1199
rocprofiler_agent_id_t * gpu_agent_id
Preferred agents to collect SPM on.
Definition: rocprofiler.h:1892
rocprofiler_record_header_t header
ROCProfiler General Record base header to identify the id and kind of every record.
Definition: rocprofiler.h:1943
uint64_t value
Definition: rocprofiler.h:1571
rocprofiler_queue_index_t queue_idx
Queue Index - packet index in the queue.
Definition: rocprofiler.h:1117
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_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
Types of information that can be requested about the Agents.
Definition: rocprofiler.h:645
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
GPU Agent Type.
Definition: rocprofiler.h:653
@ ROCPROFILER_AGENT_NAME
GPU Agent Name.
Definition: rocprofiler.h:649
@ ROCPROFILER_CPU_AGENT
CPU Agent.
Definition: rocprofiler.h:633
@ ROCPROFILER_GPU_AGENT
GPU Agent.
Definition: rocprofiler.h:637
rocprofiler_kernel_info_kind_t
Kernel Information Types, can be used by rocprofiler_query_kernel_info.
Definition: rocprofiler.h:791
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_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
Kernel Name Information Type.
Definition: rocprofiler.h:795
rocprofiler_queue_info_kind_t
Types of information that can be requested about the Queues.
Definition: rocprofiler.h:721
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_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
AMD HSA Queue Size.
Definition: rocprofiler.h:725
ROCPROFILER_API rocprofiler_status_t rocprofiler_finalize() ROCPROFILER_VERSION_9_0
Finalize the API Tools.
ROCPROFILER_API rocprofiler_status_t rocprofiler_initialize() ROCPROFILER_VERSION_9_0
Initialize the API Tools.
rocprofiler_filter_kind_t
Definition: rocprofiler.h:1716
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
Definition: rocprofiler.h:1896
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...
const char * rocprofiler_hip_function_name_t
Definition: rocprofiler.h:1780
const char * rocprofiler_hsa_function_name_t
Definition: rocprofiler.h:1781
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_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.
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_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_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_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
ATT parameters to be used by for collection.
Definition: rocprofiler.h:1786
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
Kernel Dispatch Timestamp collection.
Definition: rocprofiler.h:1720
@ ROCPROFILER_ATT_TRACE_COLLECTION
ATT Tracing.
Definition: rocprofiler.h:1732
@ ROCPROFILER_COUNTERS_COLLECTION
GPU Application counter collection.
Definition: rocprofiler.h:1724
@ ROCPROFILER_SPM_COLLECTION
SPM collection.
Definition: rocprofiler.h:1736
@ ROCPROFILER_API_TRACE
HIP/HSA/ROCTX/SYS Trace.
Definition: rocprofiler.h:1740
@ ROCPROFILER_PC_SAMPLING_COLLECTION
PC Sampling collection.
Definition: rocprofiler.h:1728
@ ROCPROFILER_COUNTERS_SAMPLER
Sampled Counters.
Definition: rocprofiler.h:1744
@ ROCPROFILER_COUNTERS_SAMPLER_XGMI_COUNTERS
Definition: rocprofiler.h:1898
@ ROCPROFILER_COUNTERS_SAMPLER_PCIE_COUNTERS
Definition: rocprofiler.h:1897
@ ROCPROFILER_ATT_CAPTURE_MODE
Set ISA capture during ATT collection (rocprofiler_codeobj_capture_mode_t)
Definition: rocprofiler.h:1814
@ ROCPROFILER_ATT_VMID_MASK
VMID Mask.
Definition: rocprofiler.h:1794
@ ROCPROFILER_ATT_SIMD_SELECT
Set SIMD Mask (GFX9) or SIMD ID for collection (Navi)
Definition: rocprofiler.h:1802
@ ROCPROFILER_ATT_COMPUTE_UNIT
Select the target compute unit (wgp) for profiling.
Definition: rocprofiler.h:1790
@ ROCPROFILER_ATT_TOKEN_MASK
Deprecated.
Definition: rocprofiler.h:1834
@ ROCPROFILER_ATT_PERF_CTRL
Select collection period for perfcounters.
Definition: rocprofiler.h:1822
@ ROCPROFILER_ATT_MAXVALUE
Definition: rocprofiler.h:1831
@ ROCPROFILER_ATT_TOKEN_MASK2
Deprecated.
Definition: rocprofiler.h:1835
@ ROCPROFILER_ATT_PERFCOUNTER_NAME
Select perfcounter name (SQ block) for collection.
Definition: rocprofiler.h:1830
@ ROCPROFILER_ATT_PERFCOUNTER
Select perfcounter ID (SQ block) for collection.
Definition: rocprofiler.h:1826
@ ROCPROFILER_ATT_OCCUPANCY
Set true for occupancy collection only.
Definition: rocprofiler.h:1806
@ ROCPROFILER_ATT_MASK
Definition: rocprofiler.h:1833
@ ROCPROFILER_ATT_SAMPLE_RATE
Deprecated.
Definition: rocprofiler.h:1836
@ ROCPROFILER_ATT_BUFFER_SIZE
ATT collection max data size, in MB.
Definition: rocprofiler.h:1810
@ ROCPROFILER_ATT_SE_MASK
Shader engine mask for selection.
Definition: rocprofiler.h:1798
@ ROCPROFILER_ATT_PERF_MASK
Mask of which compute units to generate perfcounters.
Definition: rocprofiler.h:1818
@ 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
Add HIP API calls that will be only traced (ex.
Definition: rocprofiler.h:1759
@ ROCPROFILER_FILTER_HSA_TRACER_API_FUNCTIONS
Add HSA API calls that will be only traced (ex.
Definition: rocprofiler.h:1755
@ ROCPROFILER_FILTER_KERNEL_NAMES
Add Kernel names that will be profiled or traced.
Definition: rocprofiler.h:1772
@ ROCPROFILER_FILTER_DISPATCH_IDS
Add Kernel correlation ids that will be profiled or traced for ATT.
Definition: rocprofiler.h:1776
@ ROCPROFILER_FILTER_GPU_NAME
Add GPU names that will be only profiled or traced.
Definition: rocprofiler.h:1763
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_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_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_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
Replay Profiling Modes.
Definition: rocprofiler.h:1651
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
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_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 API status codes.
Definition: rocprofiler.h:288
@ 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
The requested information for the tracing API Data is missing.
Definition: rocprofiler.h:352
@ 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
The requested Counter information for the given kernel is missing.
Definition: rocprofiler.h:344
@ ROCPROFILER_STATUS_ERROR_SESSION_MISSING_FILTER
Missing Filter for a session.
Definition: rocprofiler.h:377
@ ROCPROFILER_STATUS_ERROR_SESSION_MISSING_BUFFER
Missing Buffer for a session.
Definition: rocprofiler.h:308
@ 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
Kernel is not found with given identifier.
Definition: rocprofiler.h:332
@ ROCPROFILER_STATUS_ERROR_FILTER_DATA_CORRUPTED
The given filter data is corrupted.
Definition: rocprofiler.h:393
@ 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
Counter is not found with the given identifier.
Definition: rocprofiler.h:340
@ ROCPROFILER_STATUS_ERROR_CORRUPTED_LABEL_DATA
The given label is corrupted.
Definition: rocprofiler.h:397
@ ROCPROFILER_STATUS_ERROR_INCORRECT_REPLAY_MODE
Incorrect Replay mode.
Definition: rocprofiler.h:373
@ ROCPROFILER_STATUS_ERROR_NOT_IMPLEMENTED
The feature requested is not implemented.
Definition: rocprofiler.h:442
@ ROCPROFILER_STATUS_ERROR_QUEUE_NOT_FOUND
Queue is not found for the given identifier.
Definition: rocprofiler.h:324
@ ROCPROFILER_STATUS_ERROR_INVALID_OPERATION_ID
The given operation id is not valid.
Definition: rocprofiler.h:434
@ ROCPROFILER_STATUS_ERROR_INVALID_DOMAIN_ID
The given domain id is not valid.
Definition: rocprofiler.h:438
@ ROCPROFILER_STATUS_ERROR_INCORRECT_FLUSH_INTERVAL
Incorrect Flush interval.
Definition: rocprofiler.h:385
@ 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
The requested Session given the session identifier is not found.
Definition: rocprofiler.h:360
@ 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
The session filter can't accept the given data.
Definition: rocprofiler.h:389
@ ROCPROFILER_STATUS_ERROR_INCORRECT_DOMAIN
The given Domain is incorrect.
Definition: rocprofiler.h:356
@ ROCPROFILER_STATUS_ERROR_INVALID_ARGUMENTS
Invalid Arguments were given to the function.
Definition: rocprofiler.h:430
@ ROCPROFILER_STATUS_ERROR_AGENT_NOT_FOUND
Agent is not found with given identifier.
Definition: rocprofiler.h:316
@ ROCPROFILER_STATUS_ERROR_SESSION_NOT_ACTIVE
Can't terminate a non active session.
Definition: rocprofiler.h:414
@ ROCPROFILER_STATUS_ERROR
A generic error has occurred.
Definition: rocprofiler.h:296
@ 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
There is no label in the labels stack to be popped.
Definition: rocprofiler.h:401
@ ROCPROFILER_STATUS_ERROR_TIMESTAMP_NOT_APPLICABLE
Timestamps can't be collected.
Definition: rocprofiler.h:312
@ 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
The size given for the buffer is not applicable.
Definition: rocprofiler.h:381
@ 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 is already initialized.
Definition: rocprofiler.h:300
@ ROCPROFILER_STATUS_SUCCESS
The function has executed successfully.
Definition: rocprofiler.h:292
@ ROCPROFILER_STATUS_ERROR_PASS_NOT_STARTED
There is no pass that started.
Definition: rocprofiler.h:405
@ ROCPROFILER_STATUS_ERROR_FILTER_NOT_SUPPORTED
The required Filter is not supported.
Definition: rocprofiler.h:426
@ ROCPROFILER_STATUS_ERROR_AGENT_INFORMATION_MISSING
Agent information is missing for the given identifier.
Definition: rocprofiler.h:320
@ ROCPROFILER_STATUS_ERROR_NOT_INITIALIZED
ROCProfiler is not initialized.
Definition: rocprofiler.h:304
#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_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
Traced API domains.
Definition: rocprofiler.h:1314
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
Definition: rocprofiler.h:1415
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
ROCTX domain.
Definition: rocprofiler.h:1342
@ ACTIVITY_DOMAIN_EXT_API
External ID domain.
Definition: rocprofiler.h:1338
@ ACTIVITY_DOMAIN_HSA_EVT
HSA events (Device Activity)
Definition: rocprofiler.h:1348
@ ACTIVITY_DOMAIN_HSA_OPS
HSA async activity domain.
Definition: rocprofiler.h:1322
@ ACTIVITY_DOMAIN_HIP_API
HIP API domain.
Definition: rocprofiler.h:1330
@ ACTIVITY_DOMAIN_NUMBER
Definition: rocprofiler.h:1349
@ ACTIVITY_DOMAIN_HSA_API
HSA API domain.
Definition: rocprofiler.h:1318
@ ACTIVITY_DOMAIN_HIP_OPS
HIP async activity domain.
Definition: rocprofiler.h:1326
@ ACTIVITY_DOMAIN_KFD_API
KFD API domain.
Definition: rocprofiler.h:1334
@ ROCPROFILER_PHASE_NONE
No phase, it is an activity record or asynchronous output data.
Definition: rocprofiler.h:1419
@ ROCPROFILER_PHASE_ENTER
Enter phase for API calls.
Definition: rocprofiler.h:1423
@ ROCPROFILER_PHASE_EXIT
Exit phase for API calls.
Definition: rocprofiler.h:1427
uint32_t rocprofiler_version_minor()
uint32_t rocprofiler_version_major()
Agent ID handle, which represents a unique id to the agent reported as it can be used to retrieve Age...
Definition: rocprofiler.h:616
Definition: rocprofiler.h:1841
Definition: rocprofiler.h:1574
Definition: rocprofiler.h:1569
struct to store the filepaths and their addresses for intercepted code objects
Definition: rocprofiler.h:1229
Correlation ID.
Definition: rocprofiler.h:1059
Counter ID to be used to query counter information using rocprofiler_query_counter_info.
Definition: rocprofiler.h:893
Definition: rocprofiler.h:873
Definition: rocprofiler.h:2266
Definition: rocprofiler.h:1901
Definition: rocprofiler.h:1906
Definition: rocprofiler.h:1911
Definition: rocprofiler.h:2270
Definition: rocprofiler.h:1124
Definition: rocprofiler.h:1578
Filter Data Type filter data will be used to report required and optional filters for the sessions us...
Definition: rocprofiler.h:1854
struct to store the filepaths and their addresses for intercepted code objects
Definition: rocprofiler.h:1179
Kernel dispatch correlation ID, unique across all dispatches.
Definition: rocprofiler.h:1494
Kernel identifier that represent a unique id for every kernel.
Definition: rocprofiler.h:781
Kernel properties, this will represent the kernel properties such as its grid size,...
Definition: rocprofiler.h:1016
An individual PC sample.
Definition: rocprofiler.h:1501
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
Definition: rocprofiler.h:965
ATT tracing record structure.
Definition: rocprofiler.h:1252
Counter Instance Structure, it will represent every counter reported in the array of counters reporte...
Definition: rocprofiler.h:988
Counter Value Structure.
Definition: rocprofiler.h:976
Counters Instances Count Structure, every profiling record has this structure included to report the ...
Definition: rocprofiler.h:1004
Definition: rocprofiler.h:1938
Generic ROCProfiler record header.
Definition: rocprofiler.h:595
Timestamps (start & end), it will be used for kernel dispatch tracing as well as API Tracing.
Definition: rocprofiler.h:540
A unique identifier for every record.
Definition: rocprofiler.h:554
PC sample record: contains the program counter/instruction pointer observed during periodic sampling ...
Definition: rocprofiler.h:1535
Profiling record, this will represent all the information reported by the profiler regarding kernel d...
Definition: rocprofiler.h:1070
struct to store the trace data from a shader engine.
Definition: rocprofiler.h:1171
Counters, including identifiers to get counter information and Counters values.
Definition: rocprofiler.h:1138
SPM record, this will represent all the information reported by the SPM regarding counters and their ...
Definition: rocprofiler.h:1150
Tracing record, this will represent all the information reported by the tracer regarding APIs and the...
Definition: rocprofiler.h:1437
Session Identifier.
Definition: rocprofiler.h:497
Definition: rocprofiler.h:1876
Holds the thread id.
Definition: rocprofiler.h:847
ROCProfiling Timestamp Type.
Definition: rocprofiler.h:520
Correlation identifier.
Definition: rocprofiler.h:1362
Tracer API Calls Data Handler.
Definition: rocprofiler.h:1372
Tracing external ID.
Definition: rocprofiler.h:1411
Tracing Operation ID for HIP/HSA.
Definition: rocprofiler.h:1355
Filter Kind Data.
Definition: rocprofiler.h:1963
#define ROCPROFILER_API
Definition: rocprofiler.h:198