The profiling records are asynchronously logged to the pool and can be associated with the respective GPU kernels. More...

Modules
	Counter Collection Handling
	records
	Tracer Part Handling
	Memory Storage Buffer
	Sessions.
	ROCProfiler Sessions
	ROCProfiler Session Modes.
	Device Profiling API

Data Structures
struct	rocprofiler_settings_t
struct	rocprofiler_data_t
struct	rocprofiler_feature_t
struct	rocprofiler_group_t
struct	rocprofiler_properties_t
struct	rocprofiler_dispatch_record_t
struct	rocprofiler_callback_data_t
struct	rocprofiler_queue_callbacks_t
union	rocprofiler_info_query_t
struct	rocprofiler_info_data_t
struct	rocprofiler_pool_entry_t
struct	rocprofiler_pool_properties_t
struct	rocprofiler_hsa_callback_data_t
struct	rocprofiler_hsa_callbacks_t

Typedefs
typedef hsa_ven_amd_aqlprofile_parameter_t	rocprofiler_parameter_t
typedef void	rocprofiler_feature_set_t
typedef void	rocprofiler_t
typedef bool(*	rocprofiler_handler_t) (rocprofiler_group_t group, void *arg)
typedef hsa_status_t(*	rocprofiler_callback_t) (const rocprofiler_callback_data_t *callback_data, void *user_data, rocprofiler_group_t *group)
typedef hsa_ven_amd_aqlprofile_data_callback_t	rocprofiler_trace_data_callback_t
typedef void	rocprofiler_pool_t
typedef bool(*	rocprofiler_pool_handler_t) (const rocprofiler_pool_entry_t *entry, void *arg)
typedef hsa_status_t(*	rocprofiler_hsa_callback_fun_t) (rocprofiler_hsa_cb_id_t id, const rocprofiler_hsa_callback_data_t *data, void *arg)

Enumerations
enum	rocprofiler_feature_kind_t { ROCPROFILER_FEATURE_KIND_METRIC = 0 , ROCPROFILER_FEATURE_KIND_TRACE = 1 , ROCPROFILER_FEATURE_KIND_SPM_MOD = 2 , ROCPROFILER_FEATURE_KIND_PCSMP_MOD = 4 }
enum	rocprofiler_data_kind_t {   ROCPROFILER_DATA_KIND_UNINIT = 0 , ROCPROFILER_DATA_KIND_INT32 = 1 , ROCPROFILER_DATA_KIND_INT64 = 2 , ROCPROFILER_DATA_KIND_FLOAT = 3 ,   ROCPROFILER_DATA_KIND_DOUBLE = 4 , ROCPROFILER_DATA_KIND_BYTES = 5 }
enum	rocprofiler_mode_t { ROCPROFILER_MODE_STANDALONE = 1 , ROCPROFILER_MODE_CREATEQUEUE = 2 , ROCPROFILER_MODE_SINGLEGROUP = 4 }
enum	rocprofiler_time_id_t {   ROCPROFILER_TIME_ID_CLOCK_REALTIME = 0 , ROCPROFILER_TIME_ID_CLOCK_REALTIME_COARSE = 1 , ROCPROFILER_TIME_ID_CLOCK_MONOTONIC = 2 , ROCPROFILER_TIME_ID_CLOCK_MONOTONIC_COARSE = 3 ,   ROCPROFILER_TIME_ID_CLOCK_MONOTONIC_RAW = 4 }
enum	rocprofiler_info_kind_t {   ROCPROFILER_INFO_KIND_METRIC = 0 , ROCPROFILER_INFO_KIND_METRIC_COUNT = 1 , ROCPROFILER_INFO_KIND_TRACE = 2 , ROCPROFILER_INFO_KIND_TRACE_COUNT = 3 ,   ROCPROFILER_INFO_KIND_TRACE_PARAMETER = 4 , ROCPROFILER_INFO_KIND_TRACE_PARAMETER_COUNT = 5 }
enum	rocprofiler_hsa_cb_id_t {   ROCPROFILER_HSA_CB_ID_ALLOCATE = 0 , ROCPROFILER_HSA_CB_ID_DEVICE = 1 , ROCPROFILER_HSA_CB_ID_MEMCOPY = 2 , ROCPROFILER_HSA_CB_ID_SUBMIT = 3 ,   ROCPROFILER_HSA_CB_ID_KSYMBOL = 4 , ROCPROFILER_HSA_CB_ID_CODEOBJ = 5 }

Functions
hsa_status_t	rocprofiler_error_string (const char **str)
hsa_status_t	rocprofiler_open (hsa_agent_t agent, rocprofiler_feature_t *features, uint32_t feature_count, rocprofiler_t **context, uint32_t mode, rocprofiler_properties_t *properties)
hsa_status_t	rocprofiler_add_feature (const rocprofiler_feature_t *feature, rocprofiler_feature_set_t *features_set)
hsa_status_t	rocprofiler_features_set_open (hsa_agent_t agent, rocprofiler_feature_set_t *features_set, rocprofiler_t **context, uint32_t mode, rocprofiler_properties_t *properties)
hsa_status_t	rocprofiler_close (rocprofiler_t *context)
hsa_status_t	rocprofiler_reset (rocprofiler_t *context, uint32_t group_index)
hsa_status_t	rocprofiler_get_agent (rocprofiler_t *context, hsa_agent_t *agent)
hsa_status_t	rocprofiler_get_time (rocprofiler_time_id_t time_id, uint64_t timestamp, uint64_t *value_ns, uint64_t *error_ns)
hsa_status_t	rocprofiler_set_queue_callbacks (rocprofiler_queue_callbacks_t callbacks, void *data)
hsa_status_t	rocprofiler_remove_queue_callbacks ()
hsa_status_t	rocprofiler_start_queue_callbacks ()
hsa_status_t	rocprofiler_stop_queue_callbacks ()
hsa_status_t	rocprofiler_start (rocprofiler_t *context, uint32_t group_index)
hsa_status_t	rocprofiler_stop (rocprofiler_t *context, uint32_t group_index)
hsa_status_t	rocprofiler_read (rocprofiler_t *context, uint32_t group_index)
hsa_status_t	rocprofiler_get_data (rocprofiler_t *context, uint32_t group_index)
hsa_status_t	rocprofiler_group_count (const rocprofiler_t *context, uint32_t *group_count)
hsa_status_t	rocprofiler_get_group (rocprofiler_t *context, uint32_t group_index, rocprofiler_group_t *group)
hsa_status_t	rocprofiler_group_start (rocprofiler_group_t *group)
hsa_status_t	rocprofiler_group_stop (rocprofiler_group_t *group)
hsa_status_t	rocprofiler_group_read (rocprofiler_group_t *group)
hsa_status_t	rocprofiler_group_get_data (rocprofiler_group_t *group)
hsa_status_t	rocprofiler_get_metrics (const rocprofiler_t *context)
hsa_status_t	rocprofiler_iterate_trace_data (rocprofiler_t *context, rocprofiler_trace_data_callback_t callback, void *data)
hsa_status_t	rocprofiler_get_info (const hsa_agent_t *agent, rocprofiler_info_kind_t kind, void *data)
hsa_status_t	rocprofiler_iterate_info (const hsa_agent_t *agent, rocprofiler_info_kind_t kind, hsa_status_t(*callback)(const rocprofiler_info_data_t info, void *data), void *data)
hsa_status_t	rocprofiler_query_info (const hsa_agent_t *agent, rocprofiler_info_query_t query, hsa_status_t(*callback)(const rocprofiler_info_data_t info, void *data), void *data)
hsa_status_t	rocprofiler_queue_create_profiled (hsa_agent_t agent_handle, uint32_t size, hsa_queue_type32_t type, void(*callback)(hsa_status_t status, hsa_queue_t *source, void *data), void *data, uint32_t private_segment_size, uint32_t group_segment_size, hsa_queue_t **queue)
hsa_status_t	rocprofiler_pool_open (hsa_agent_t agent, rocprofiler_feature_t *features, uint32_t feature_count, rocprofiler_pool_t **pool, uint32_t mode, rocprofiler_pool_properties_t *)
hsa_status_t	rocprofiler_pool_close (rocprofiler_pool_t *pool)
hsa_status_t	rocprofiler_pool_fetch (rocprofiler_pool_t *pool, rocprofiler_pool_entry_t *entry)
hsa_status_t	rocprofiler_pool_release (rocprofiler_pool_entry_t *entry)
hsa_status_t	rocprofiler_pool_iterate (rocprofiler_pool_t *pool, hsa_status_t(*callback)(rocprofiler_pool_entry_t *entry, void *data), void *data)
hsa_status_t	rocprofiler_pool_flush (rocprofiler_pool_t *pool)
hsa_status_t	rocprofiler_set_hsa_callbacks (const rocprofiler_hsa_callbacks_t callbacks, void *arg)

Variables
uint64_t	rocprofiler_session_id_t::handle
	Session Identifier to get the session or to be used to call any API that needs to deal with a specific session. More...
uint64_t	rocprofiler_timestamp_t::value
rocprofiler_timestamp_t	rocprofiler_record_header_timestamp_t::begin
rocprofiler_timestamp_t	rocprofiler_record_header_timestamp_t::end
uint64_t	rocprofiler_record_id_t::handle
	Record ID handle. More...
rocprofiler_record_kind_t	rocprofiler_record_header_t::kind
	Represents the kind of the record using rocprofiler_record_kind_t. More...
rocprofiler_record_id_t	rocprofiler_record_header_t::id
	Represents the id of the record. More...
uint64_t	rocprofiler_agent_id_t::handle
	a unique id to represent every agent on the system, this handle should be unique across all nodes in multi-node system More...
uint64_t	rocprofiler_queue_id_t::handle
	Unique Id for every queue for one agent for one system. More...
uint64_t	rocprofiler_kernel_id_t::handle
	Kernel object identifier. More...
uint32_t	rocprofiler_thread_id_t::value
	Thread ID. More...
const char *	rocprofiler_counter_info_t::name
const char *	rocprofiler_counter_info_t::description
const char *	rocprofiler_counter_info_t::expression
uint32_t	rocprofiler_counter_info_t::instances_count
const char *	rocprofiler_counter_info_t::block_name
uint32_t	rocprofiler_counter_info_t::block_counters
uint64_t	rocprofiler_counter_id_t::handle
	A unique id generated for every counter requested by the user. More...
uint64_t	rocprofiler_queue_index_t::value
	queue index value More...
double	rocprofiler_record_counter_value_t::value
	Counter value. More...
rocprofiler_counter_id_t	rocprofiler_record_counter_instance_t::counter_handler
	Counter Instance Identifier. More...
rocprofiler_record_counter_value_t	rocprofiler_record_counter_instance_t::value
	Counter Instance Value. More...
uint64_t	rocprofiler_record_counters_instances_count_t::value
	Counters Instances Count for every record. More...
uint64_t	rocprofiler_kernel_properties_t::grid_size
	Grid Size. More...
uint64_t	rocprofiler_kernel_properties_t::workgroup_size
	workgroup size More...
uint64_t	rocprofiler_kernel_properties_t::lds_size
	lds_size More...
uint64_t	rocprofiler_kernel_properties_t::scratch_size
	scratch_size More...
uint64_t	rocprofiler_kernel_properties_t::arch_vgpr_count
	arch vgpr count More...
uint64_t	rocprofiler_kernel_properties_t::accum_vgpr_count
	accum vgpr count More...
uint64_t	rocprofiler_kernel_properties_t::sgpr_count
	sgpr_count More...
uint64_t	rocprofiler_kernel_properties_t::wave_size
	wave size More...
uint64_t	rocprofiler_kernel_properties_t::signal_handle
	Dispatch completion signal handle. More...
rocprofiler_record_header_t	rocprofiler_record_profiler_t::header
	ROCProfiler General Record base header to identify the id and kind of every record. More...
rocprofiler_kernel_id_t	rocprofiler_record_profiler_t::kernel_id
	Kernel Identifier to be used by the user to get the kernel info using rocprofiler_query_kernel_info. More...
rocprofiler_agent_id_t	rocprofiler_record_profiler_t::gpu_id
	Agent Identifier to be used by the user to get the Agent Information using rocprofiler_query_agent_info. More...
rocprofiler_queue_id_t	rocprofiler_record_profiler_t::queue_id
	Queue Identifier to be used by the user to get the Queue Information using rocprofiler_query_agent_info. More...
rocprofiler_record_header_timestamp_t	rocprofiler_record_profiler_t::timestamps
	Timestamps, start and end timestamps of the record data (ex. More...
rocprofiler_record_counter_instance_t *	rocprofiler_record_profiler_t::counters
	Counters, including identifiers to get counter information and Counters values. More...
rocprofiler_kernel_properties_t	rocprofiler_record_profiler_t::kernel_properties
	kernel properties, including the grid size, work group size, registers count, wave size and completion signal More...
rocprofiler_thread_id_t	rocprofiler_record_profiler_t::thread_id
	Thread id. More...
rocprofiler_queue_index_t	rocprofiler_record_profiler_t::queue_idx
	Queue Index - packet index in the queue. More...
rocprofiler_record_counters_instances_count_t	rocprofiler_record_profiler_t::counters_count
	The count of the counters that were collected by the profiler. More...
uint32_t	rocprofiler_event_id_t::value
uint16_t	rocprofiler_record_spm_counters_instances_count_t::value
rocprofiler_record_spm_counters_instances_count_t	rocprofiler_record_se_spm_data_t::counters_data [32]
rocprofiler_record_header_t	rocprofiler_record_spm_t::header
	ROCProfiler General Record base header to identify the id and kind of every record. More...
rocprofiler_record_header_timestamp_t	rocprofiler_record_spm_t::timestamps
	Timestamps at which the counters were sampled. More...
rocprofiler_record_se_spm_data_t	rocprofiler_record_spm_t::shader_engine_data [4]
	Counter values per shader engine. More...
void *	rocprofiler_record_se_att_data_t::buffer_ptr
uint32_t	rocprofiler_record_se_att_data_t::buffer_size
rocprofiler_record_header_t	rocprofiler_record_att_tracer_t::header
	ROCProfiler General Record base header to identify the id and kind of every record. More...
rocprofiler_kernel_id_t	rocprofiler_record_att_tracer_t::kernel_id
	Kernel Identifier to be used by the user to get the kernel info using rocprofiler_query_kernel_info. More...
rocprofiler_agent_id_t	rocprofiler_record_att_tracer_t::gpu_id
	Agent Identifier to be used by the user to get the Agent Information using rocprofiler_query_agent_info. More...
rocprofiler_queue_id_t	rocprofiler_record_att_tracer_t::queue_id
	Queue Identifier to be used by the user to get the Queue Information using rocprofiler_query_agent_info. More...
rocprofiler_kernel_properties_t	rocprofiler_record_att_tracer_t::kernel_properties
	kernel properties, including the grid size, work group size, registers count, wave size and completion signal More...
rocprofiler_thread_id_t	rocprofiler_record_att_tracer_t::thread_id
	Thread id. More...
rocprofiler_queue_index_t	rocprofiler_record_att_tracer_t::queue_idx
	Queue Index - packet index in the queue. More...
rocprofiler_record_se_att_data_t *	rocprofiler_record_att_tracer_t::shader_engine_data
	ATT data output from each shader engine. More...
uint64_t	rocprofiler_record_att_tracer_t::shader_engine_data_count
	The count of the shader engine ATT data. More...
uint32_t	rocprofiler_tracer_operation_id_t::id
uint64_t	rocprofiler_tracer_activity_correlation_id_t::value
	Correlation ID Value. More...
const void *	rocprofiler_tracer_api_data_handle_t::handle
	Data Handler Identifier. More...
size_t	rocprofiler_tracer_api_data_handle_t::size
	API Data Size. More...
uint64_t	rocprofiler_tracer_external_id_t::id
rocprofiler_record_header_t	rocprofiler_record_tracer_t::header
	ROCProfiler General Record base header to identify the id and kind of every record. More...
rocprofiler_tracer_external_id_t	rocprofiler_record_tracer_t::external_id
	Tracing external ID. More...
rocprofiler_tracer_activity_domain_t	rocprofiler_record_tracer_t::domain
	Activity domain id, represents the type of the APIs that are being traced. More...
rocprofiler_tracer_operation_id_t	rocprofiler_record_tracer_t::operation_id
	Tracing Operation ID for HIP/HSA. More...
rocprofiler_tracer_api_data_handle_t	rocprofiler_record_tracer_t::api_data_handle
	API Data Handler to be used by rocprofiler_query_roctx_tracer_api_data_info or rocprofiler_query_hsa_tracer_api_data_info or rocprofiler_query_hip_tracer_api_data_info depending on the domain type. More...
rocprofiler_tracer_activity_correlation_id_t	rocprofiler_record_tracer_t::correlation_id
	Activity correlation ID. More...
rocprofiler_record_header_timestamp_t	rocprofiler_record_tracer_t::timestamps
	Timestamps. More...
rocprofiler_agent_id_t	rocprofiler_record_tracer_t::agent_id
	Agent identifier that can be used as a handler in rocprofiler_query_agent_info. More...
rocprofiler_queue_id_t	rocprofiler_record_tracer_t::queue_id
	Queue identifier that can be used as a handler in rocprofiler_query_queue_info. More...
rocprofiler_thread_id_t	rocprofiler_record_tracer_t::thread_id
	Thread id. More...
uint64_t	rocprofiler_kernel_dispatch_id_t::value
rocprofiler_kernel_dispatch_id_t	rocprofiler_pc_sample_t::dispatch_id
	Kernel dispatch ID. More...
rocprofiler_timestamp_t   rocprofiler_pc_sample_t::timestamp
	Host timestamp. More...
uint64_t   rocprofiler_pc_sample_t::cycle
	GPU clock counter (not currently used) More...
union {
rocprofiler_timestamp_t   rocprofiler_pc_sample_t::timestamp
	Host timestamp. More...
uint64_t   rocprofiler_pc_sample_t::cycle
	GPU clock counter (not currently used) More...
};
uint64_t	rocprofiler_pc_sample_t::pc
	Sampled program counter. More...
uint32_t	rocprofiler_pc_sample_t::se
	Sampled shader element. More...
rocprofiler_agent_id_t	rocprofiler_pc_sample_t::gpu_id
	Sampled GPU agent. More...
rocprofiler_record_header_t	rocprofiler_record_pc_sample_t::header
	ROCProfiler General Record base header to identify the id and kind of every record. More...
rocprofiler_pc_sample_t	rocprofiler_record_pc_sample_t::pc_sample
	PC sample data. More...
rocprofiler_buffer_property_kind_t	rocprofiler_buffer_property_t::kind
uint64_t	rocprofiler_buffer_property_t::value
uint64_t	rocprofiler_buffer_id_t::value
uint64_t	rocprofiler_filter_id_t::value
rocprofiler_att_parameter_name_t	rocprofiler_att_parameter_t::parameter_name
uint32_t   rocprofiler_att_parameter_t::value
const char *   rocprofiler_att_parameter_t::counter_name
union {
uint32_t   rocprofiler_att_parameter_t::value
const char *   rocprofiler_att_parameter_t::counter_name
};
rocprofiler_filter_property_kind_t	rocprofiler_filter_property_t::kind
	Filter Property kind. More...
const char **   rocprofiler_filter_property_t::name_regex
rocprofiler_hip_function_name_t *   rocprofiler_filter_property_t::hip_functions_names
rocprofiler_hsa_function_name_t *   rocprofiler_filter_property_t::hsa_functions_names
uint32_t   rocprofiler_filter_property_t::range [2]
union {
const char **   rocprofiler_filter_property_t::name_regex
rocprofiler_hip_function_name_t *   rocprofiler_filter_property_t::hip_functions_names
rocprofiler_hsa_function_name_t *   rocprofiler_filter_property_t::hsa_functions_names
uint32_t   rocprofiler_filter_property_t::range [2]
};
	Array of data required for the filter type chosen. More...
uint64_t	rocprofiler_filter_property_t::data_count
	Data array count. More...
const char **	rocprofiler_spm_parameter_t::counters_names
	Counters to profile. More...
int	rocprofiler_spm_parameter_t::counters_count
	Counters count. More...
uint32_t	rocprofiler_spm_parameter_t::sampling_rate
	Sampling rate. More...
rocprofiler_agent_id_t *	rocprofiler_spm_parameter_t::gpu_agent_id
	Preferred agents to collect SPM on. More...
rocprofiler_tracer_activity_domain_t *	rocprofiler_filter_data_t::trace_apis
	APIs to trace. More...
const char **	rocprofiler_filter_data_t::counters_names
	Counters to profile. More...
rocprofiler_att_parameter_t *	rocprofiler_filter_data_t::att_parameters
	att parameters More...
rocprofiler_spm_parameter_t *	rocprofiler_filter_data_t::spm_parameters
	spm counters parameters More...
double	rocprofiler_counter_value_t::value
char	rocprofiler_device_profile_metric_t::metric_name [64]
rocprofiler_counter_value_t	rocprofiler_device_profile_metric_t::value
uint32_t	rocprofiler_settings_t::intercept_mode
uint32_t	rocprofiler_settings_t::code_obj_tracking
uint32_t	rocprofiler_settings_t::memcopy_tracking
uint32_t	rocprofiler_settings_t::trace_size
uint32_t	rocprofiler_settings_t::trace_local
uint64_t	rocprofiler_settings_t::timeout
uint32_t	rocprofiler_settings_t::timestamp_on
uint32_t	rocprofiler_settings_t::hsa_intercepting
uint32_t	rocprofiler_settings_t::k_concurrent
uint32_t	rocprofiler_settings_t::opt_mode
uint32_t	rocprofiler_settings_t::obj_dumping
rocprofiler_data_kind_t	rocprofiler_data_t::kind
uint32_t   rocprofiler_data_t::result_int32
uint64_t   rocprofiler_data_t::result_int64
float   rocprofiler_data_t::result_float
double   rocprofiler_data_t::result_double
void *   rocprofiler_data_t::ptr
uint32_t   rocprofiler_data_t::size
uint32_t   rocprofiler_data_t::instance_count
bool   rocprofiler_data_t::copy
struct {
void *   rocprofiler_data_t::ptr
uint32_t   rocprofiler_data_t::size
uint32_t   rocprofiler_data_t::instance_count
bool   rocprofiler_data_t::copy
}   rocprofiler_data_t::result_bytes
union {
uint32_t   rocprofiler_data_t::result_int32
uint64_t   rocprofiler_data_t::result_int64
float   rocprofiler_data_t::result_float
double   rocprofiler_data_t::result_double
struct {
void *   rocprofiler_data_t::ptr
uint32_t   rocprofiler_data_t::size
uint32_t   rocprofiler_data_t::instance_count
bool   rocprofiler_data_t::copy
}   rocprofiler_data_t::result_bytes
};
rocprofiler_feature_kind_t	rocprofiler_feature_t::kind
const char *   rocprofiler_feature_t::name
const char *   rocprofiler_feature_t::block
uint32_t   rocprofiler_feature_t::event
struct {
const char *   rocprofiler_feature_t::block
uint32_t   rocprofiler_feature_t::event
}   rocprofiler_feature_t::counter
union {
const char *   rocprofiler_feature_t::name
struct {
const char *   rocprofiler_feature_t::block
uint32_t   rocprofiler_feature_t::event
}   rocprofiler_feature_t::counter
};
const rocprofiler_parameter_t *	rocprofiler_feature_t::parameters
uint32_t	rocprofiler_feature_t::parameter_count
rocprofiler_data_t	rocprofiler_feature_t::data
unsigned	rocprofiler_group_t::index
rocprofiler_feature_t **	rocprofiler_group_t::features
uint32_t	rocprofiler_group_t::feature_count
rocprofiler_t *	rocprofiler_group_t::context
hsa_queue_t *	rocprofiler_properties_t::queue
uint32_t	rocprofiler_properties_t::queue_depth
rocprofiler_handler_t	rocprofiler_properties_t::handler
void *	rocprofiler_properties_t::handler_arg
uint64_t	rocprofiler_dispatch_record_t::dispatch
uint64_t	rocprofiler_dispatch_record_t::begin
uint64_t	rocprofiler_dispatch_record_t::end
uint64_t	rocprofiler_dispatch_record_t::complete
hsa_agent_t	rocprofiler_callback_data_t::agent
uint32_t	rocprofiler_callback_data_t::agent_index
const hsa_queue_t *	rocprofiler_callback_data_t::queue
uint64_t	rocprofiler_callback_data_t::queue_index
uint32_t	rocprofiler_callback_data_t::queue_id
hsa_signal_t	rocprofiler_callback_data_t::completion_signal
const hsa_kernel_dispatch_packet_t *	rocprofiler_callback_data_t::packet
const char *	rocprofiler_callback_data_t::kernel_name
uint64_t	rocprofiler_callback_data_t::kernel_object
const amd_kernel_code_t *	rocprofiler_callback_data_t::kernel_code
uint32_t	rocprofiler_callback_data_t::thread_id
const rocprofiler_dispatch_record_t *	rocprofiler_callback_data_t::record
rocprofiler_callback_t	rocprofiler_queue_callbacks_t::dispatch
hsa_status_t(*	rocprofiler_queue_callbacks_t::create )(hsa_queue_t *queue, void *data)
hsa_status_t(*	rocprofiler_queue_callbacks_t::destroy )(hsa_queue_t *queue, void *data)
rocprofiler_info_kind_t	rocprofiler_info_query_t::info_kind
const char *   rocprofiler_info_query_t::trace_name
struct {
const char *   rocprofiler_info_query_t::trace_name
}	rocprofiler_info_query_t::trace_parameter
uint32_t	rocprofiler_info_data_t::agent_index
rocprofiler_info_kind_t	rocprofiler_info_data_t::kind
const char *   rocprofiler_info_data_t::name
uint32_t   rocprofiler_info_data_t::instances
const char *   rocprofiler_info_data_t::expr
const char *   rocprofiler_info_data_t::description
const char *   rocprofiler_info_data_t::block_name
uint32_t   rocprofiler_info_data_t::block_counters
struct {
const char *   rocprofiler_info_data_t::name
uint32_t   rocprofiler_info_data_t::instances
const char *   rocprofiler_info_data_t::expr
const char *   rocprofiler_info_data_t::description
const char *   rocprofiler_info_data_t::block_name
uint32_t   rocprofiler_info_data_t::block_counters
}   rocprofiler_info_data_t::metric
const char *   rocprofiler_info_data_t::name
const char *   rocprofiler_info_data_t::description
uint32_t   rocprofiler_info_data_t::parameter_count
struct {
const char *   rocprofiler_info_data_t::name
const char *   rocprofiler_info_data_t::description
uint32_t   rocprofiler_info_data_t::parameter_count
}   rocprofiler_info_data_t::trace
uint32_t   rocprofiler_info_data_t::code
const char *   rocprofiler_info_data_t::trace_name
const char *   rocprofiler_info_data_t::parameter_name
const char *   rocprofiler_info_data_t::description
struct {
uint32_t   rocprofiler_info_data_t::code
const char *   rocprofiler_info_data_t::trace_name
const char *   rocprofiler_info_data_t::parameter_name
const char *   rocprofiler_info_data_t::description
}   rocprofiler_info_data_t::trace_parameter
union {
struct {
const char *   rocprofiler_info_data_t::name
uint32_t   rocprofiler_info_data_t::instances
const char *   rocprofiler_info_data_t::expr
const char *   rocprofiler_info_data_t::description
const char *   rocprofiler_info_data_t::block_name
uint32_t   rocprofiler_info_data_t::block_counters
}   rocprofiler_info_data_t::metric
struct {
const char *   rocprofiler_info_data_t::name
const char *   rocprofiler_info_data_t::description
uint32_t   rocprofiler_info_data_t::parameter_count
}   rocprofiler_info_data_t::trace
struct {
uint32_t   rocprofiler_info_data_t::code
const char *   rocprofiler_info_data_t::trace_name
const char *   rocprofiler_info_data_t::parameter_name
const char *   rocprofiler_info_data_t::description
}   rocprofiler_info_data_t::trace_parameter
};
rocprofiler_t *	rocprofiler_pool_entry_t::context
void *	rocprofiler_pool_entry_t::payload
uint32_t	rocprofiler_pool_properties_t::num_entries
uint32_t	rocprofiler_pool_properties_t::payload_bytes
rocprofiler_pool_handler_t	rocprofiler_pool_properties_t::handler
void *	rocprofiler_pool_properties_t::handler_arg
const void *   rocprofiler_hsa_callback_data_t::ptr
size_t   rocprofiler_hsa_callback_data_t::size
hsa_amd_segment_t   rocprofiler_hsa_callback_data_t::segment
hsa_amd_memory_pool_global_flag_t   rocprofiler_hsa_callback_data_t::global_flag
int   rocprofiler_hsa_callback_data_t::is_code
struct {
const void *   rocprofiler_hsa_callback_data_t::ptr
size_t   rocprofiler_hsa_callback_data_t::size
hsa_amd_segment_t   rocprofiler_hsa_callback_data_t::segment
hsa_amd_memory_pool_global_flag_t   rocprofiler_hsa_callback_data_t::global_flag
int   rocprofiler_hsa_callback_data_t::is_code
}   rocprofiler_hsa_callback_data_t::allocate
hsa_device_type_t   rocprofiler_hsa_callback_data_t::type
uint32_t   rocprofiler_hsa_callback_data_t::id
hsa_agent_t   rocprofiler_hsa_callback_data_t::agent
const void *   rocprofiler_hsa_callback_data_t::ptr
struct {
hsa_device_type_t   rocprofiler_hsa_callback_data_t::type
uint32_t   rocprofiler_hsa_callback_data_t::id
hsa_agent_t   rocprofiler_hsa_callback_data_t::agent
const void *   rocprofiler_hsa_callback_data_t::ptr
}   rocprofiler_hsa_callback_data_t::device
const void *   rocprofiler_hsa_callback_data_t::dst
const void *   rocprofiler_hsa_callback_data_t::src
size_t   rocprofiler_hsa_callback_data_t::size
struct {
const void *   rocprofiler_hsa_callback_data_t::dst
const void *   rocprofiler_hsa_callback_data_t::src
size_t   rocprofiler_hsa_callback_data_t::size
}   rocprofiler_hsa_callback_data_t::memcopy
const void *   rocprofiler_hsa_callback_data_t::packet
const char *   rocprofiler_hsa_callback_data_t::kernel_name
hsa_queue_t *   rocprofiler_hsa_callback_data_t::queue
uint32_t   rocprofiler_hsa_callback_data_t::device_type
uint32_t   rocprofiler_hsa_callback_data_t::device_id
struct {
const void *   rocprofiler_hsa_callback_data_t::packet
const char *   rocprofiler_hsa_callback_data_t::kernel_name
hsa_queue_t *   rocprofiler_hsa_callback_data_t::queue
uint32_t   rocprofiler_hsa_callback_data_t::device_type
uint32_t   rocprofiler_hsa_callback_data_t::device_id
}   rocprofiler_hsa_callback_data_t::submit
uint64_t   rocprofiler_hsa_callback_data_t::object
const char *   rocprofiler_hsa_callback_data_t::name
uint32_t   rocprofiler_hsa_callback_data_t::name_length
int   rocprofiler_hsa_callback_data_t::unload
struct {
uint64_t   rocprofiler_hsa_callback_data_t::object
const char *   rocprofiler_hsa_callback_data_t::name
uint32_t   rocprofiler_hsa_callback_data_t::name_length
int   rocprofiler_hsa_callback_data_t::unload
}   rocprofiler_hsa_callback_data_t::ksymbol
uint32_t   rocprofiler_hsa_callback_data_t::storage_type
int   rocprofiler_hsa_callback_data_t::storage_file
uint64_t   rocprofiler_hsa_callback_data_t::memory_base
uint64_t   rocprofiler_hsa_callback_data_t::memory_size
uint64_t   rocprofiler_hsa_callback_data_t::load_base
uint64_t   rocprofiler_hsa_callback_data_t::load_size
uint64_t   rocprofiler_hsa_callback_data_t::load_delta
uint32_t   rocprofiler_hsa_callback_data_t::uri_length
char *   rocprofiler_hsa_callback_data_t::uri
int   rocprofiler_hsa_callback_data_t::unload
struct {
uint32_t   rocprofiler_hsa_callback_data_t::storage_type
int   rocprofiler_hsa_callback_data_t::storage_file
uint64_t   rocprofiler_hsa_callback_data_t::memory_base
uint64_t   rocprofiler_hsa_callback_data_t::memory_size
uint64_t   rocprofiler_hsa_callback_data_t::load_base
uint64_t   rocprofiler_hsa_callback_data_t::load_size
uint64_t   rocprofiler_hsa_callback_data_t::load_delta
uint32_t   rocprofiler_hsa_callback_data_t::uri_length
char *   rocprofiler_hsa_callback_data_t::uri
int   rocprofiler_hsa_callback_data_t::unload
}   rocprofiler_hsa_callback_data_t::codeobj
union {
struct {
const void *   rocprofiler_hsa_callback_data_t::ptr
size_t   rocprofiler_hsa_callback_data_t::size
hsa_amd_segment_t   rocprofiler_hsa_callback_data_t::segment
hsa_amd_memory_pool_global_flag_t   rocprofiler_hsa_callback_data_t::global_flag
int   rocprofiler_hsa_callback_data_t::is_code
}   rocprofiler_hsa_callback_data_t::allocate
struct {
hsa_device_type_t   rocprofiler_hsa_callback_data_t::type
uint32_t   rocprofiler_hsa_callback_data_t::id
hsa_agent_t   rocprofiler_hsa_callback_data_t::agent
const void *   rocprofiler_hsa_callback_data_t::ptr
}   rocprofiler_hsa_callback_data_t::device
struct {
const void *   rocprofiler_hsa_callback_data_t::dst
const void *   rocprofiler_hsa_callback_data_t::src
size_t   rocprofiler_hsa_callback_data_t::size
}   rocprofiler_hsa_callback_data_t::memcopy
struct {
const void *   rocprofiler_hsa_callback_data_t::packet
const char *   rocprofiler_hsa_callback_data_t::kernel_name
hsa_queue_t *   rocprofiler_hsa_callback_data_t::queue
uint32_t   rocprofiler_hsa_callback_data_t::device_type
uint32_t   rocprofiler_hsa_callback_data_t::device_id
}   rocprofiler_hsa_callback_data_t::submit
struct {
uint64_t   rocprofiler_hsa_callback_data_t::object
const char *   rocprofiler_hsa_callback_data_t::name
uint32_t   rocprofiler_hsa_callback_data_t::name_length
int   rocprofiler_hsa_callback_data_t::unload
}   rocprofiler_hsa_callback_data_t::ksymbol
struct {
uint32_t   rocprofiler_hsa_callback_data_t::storage_type
int   rocprofiler_hsa_callback_data_t::storage_file
uint64_t   rocprofiler_hsa_callback_data_t::memory_base
uint64_t   rocprofiler_hsa_callback_data_t::memory_size
uint64_t   rocprofiler_hsa_callback_data_t::load_base
uint64_t   rocprofiler_hsa_callback_data_t::load_size
uint64_t   rocprofiler_hsa_callback_data_t::load_delta
uint32_t   rocprofiler_hsa_callback_data_t::uri_length
char *   rocprofiler_hsa_callback_data_t::uri
int   rocprofiler_hsa_callback_data_t::unload
}   rocprofiler_hsa_callback_data_t::codeobj
};
rocprofiler_hsa_callback_fun_t	rocprofiler_hsa_callbacks_t::allocate
rocprofiler_hsa_callback_fun_t	rocprofiler_hsa_callbacks_t::device
rocprofiler_hsa_callback_fun_t	rocprofiler_hsa_callbacks_t::memcopy
rocprofiler_hsa_callback_fun_t	rocprofiler_hsa_callbacks_t::submit
rocprofiler_hsa_callback_fun_t	rocprofiler_hsa_callbacks_t::ksymbol
rocprofiler_hsa_callback_fun_t	rocprofiler_hsa_callbacks_t::codeobj

Detailed Description

The profiling records are asynchronously logged to the pool and can be associated with the respective GPU kernels.

Profiling API can be used to enable collecting of the records with or without timestamping data for the GPU Application in continuous mode or kernel mode.

Typedef Documentation

◆ rocprofiler_callback_t

◆ rocprofiler_feature_set_t

◆ rocprofiler_handler_t

◆ rocprofiler_hsa_callback_fun_t

◆ rocprofiler_parameter_t

◆ rocprofiler_pool_handler_t

◆ rocprofiler_pool_t

◆ rocprofiler_t

◆ rocprofiler_trace_data_callback_t

Enumeration Type Documentation

◆ rocprofiler_data_kind_t

◆ rocprofiler_feature_kind_t

◆ rocprofiler_hsa_cb_id_t

◆ rocprofiler_info_kind_t

◆ rocprofiler_mode_t

◆ rocprofiler_time_id_t

Function Documentation

◆ rocprofiler_add_feature()

◆ rocprofiler_close()

◆ rocprofiler_error_string()

◆ rocprofiler_features_set_open()

◆ rocprofiler_get_agent()

◆ rocprofiler_get_data()

◆ rocprofiler_get_group()

◆ rocprofiler_get_info()

◆ rocprofiler_get_metrics()

◆ rocprofiler_get_time()

◆ rocprofiler_group_count()

◆ rocprofiler_group_get_data()

◆ rocprofiler_group_read()

◆ rocprofiler_group_start()

◆ rocprofiler_group_stop()

◆ rocprofiler_iterate_info()

◆ rocprofiler_iterate_trace_data()

◆ rocprofiler_open()

◆ rocprofiler_pool_close()

◆ rocprofiler_pool_fetch()

◆ rocprofiler_pool_flush()

◆ rocprofiler_pool_iterate()

◆ rocprofiler_pool_open()

◆ rocprofiler_pool_release()

◆ rocprofiler_query_info()

◆ rocprofiler_queue_create_profiled()

◆ rocprofiler_read()

◆ rocprofiler_remove_queue_callbacks()

◆ rocprofiler_reset()

◆ rocprofiler_set_hsa_callbacks()

◆ rocprofiler_set_queue_callbacks()

◆ rocprofiler_start()

◆ rocprofiler_start_queue_callbacks()

◆ rocprofiler_stop()

◆ rocprofiler_stop_queue_callbacks()

Variable Documentation

◆ 

◆ 

◆ 

◆ 

◆ 

◆ 

◆ 

◆ accum_vgpr_count

◆ agent [1/3]

◆ agent [2/3]

◆  [3/3]

◆ agent_id

◆ agent_index [1/2]

◆ agent_index [2/2]

◆  [1/3]

◆  [2/3]

◆ allocate [3/3]

◆ api_data_handle

◆ arch_vgpr_count

◆ att_parameters

◆ begin [1/2]

◆ begin [2/2]

◆  [1/2]

◆ block [2/2]

◆ block_counters [1/3]

◆ block_counters [2/3]

◆  [3/3]

◆ block_name [1/3]

◆ block_name [2/3]

◆  [3/3]

◆ buffer_ptr

◆ buffer_size

◆ code [1/2]

◆  [2/2]

◆ code_obj_tracking

◆  [1/3]

◆  [2/3]

◆ codeobj [3/3]

◆ complete

◆ completion_signal

◆ context [1/2]

◆ context [2/2]

◆  [1/2]

◆ copy [2/2]

◆ correlation_id

◆  [1/2]

◆  [2/2]

◆ counter_handler

◆ counter_name [1/2]

◆  [2/2]

◆ counters

◆ counters_count [1/2]

◆ counters_count [2/2]

◆ counters_data

◆ counters_names [1/2]

◆ counters_names [2/2]

◆ create

◆ cycle [1/2]

◆  [2/2]

◆ data

◆ data_count

◆ description [1/5]

◆  [2/5]

◆ description [3/5]

◆  [4/5]

◆  [5/5]

◆ destroy

◆  [1/3]

◆  [2/3]

◆ device [3/3]

◆ device_id [1/2]

◆  [2/2]

◆ device_type [1/2]

◆  [2/2]

◆ dispatch [1/2]

◆ dispatch [2/2]

◆ dispatch_id

◆ domain

◆ dst [1/2]

◆  [2/2]

◆ end [1/2]

◆ end [2/2]

◆ event [1/2]

◆  [2/2]

◆ expr [1/2]

◆  [2/2]

◆ expression

◆ external_id

◆ feature_count

◆ features

◆ global_flag [1/2]

◆  [2/2]

◆ gpu_agent_id

◆ gpu_id [1/3]

◆ gpu_id [2/3]

◆ gpu_id [3/3]

◆ grid_size

◆ handle [1/7]

◆ handle [2/7]

◆ handle [3/7]

◆ handle [4/7]

◆ handle [5/7]

◆ handle [6/7]

◆ handle [7/7]

◆ handler [1/2]

◆ handler [2/2]

◆ handler_arg [1/2]

◆ handler_arg [2/2]

◆ header [1/5]

◆ header [2/5]

◆ header [3/5]

◆ header [4/5]

◆ header [5/5]

◆ hip_functions_names [1/2]

◆  [2/2]

◆ hsa_functions_names [1/2]

◆  [2/2]

◆ hsa_intercepting

◆ id [1/5]

◆ id [2/5]

◆ id [3/5]

◆ id [4/5]

◆  [5/5]

◆ index

◆ info_kind

◆ instance_count [1/2]

◆  [2/2]

◆ instances [1/2]

◆  [2/2]

◆ instances_count

◆ intercept_mode

◆  [1/2]

◆ is_code [2/2]

◆ k_concurrent

◆ kernel_code

◆ kernel_id [1/2]

◆ kernel_id [2/2]

◆ kernel_name [1/3]

◆ kernel_name [2/3]

◆  [3/3]

◆ kernel_object

◆ kernel_properties [1/2]

◆ kernel_properties [2/2]

◆ kind [1/6]

◆ kind [2/6]

◆ kind [3/6]

◆ kind [4/6]

◆ kind [5/6]

◆ kind [6/6]

◆  [1/3]

◆  [2/3]

◆ ksymbol [3/3]

◆ lds_size

◆  [1/2]

◆ load_base [2/2]

◆ load_delta [1/2]

◆  [2/2]

◆ load_size [1/2]

◆  [2/2]

◆  [1/3]

◆  [2/3]

◆ memcopy [3/3]

◆ memcopy_tracking

◆ memory_base [1/2]

◆  [2/2]

◆ memory_size [1/2]

◆  [2/2]

◆  [1/2]

◆  [2/2]

◆ metric_name

◆ name [1/8]

◆ name [2/8]

◆  [3/8]

◆ name [4/8]

◆  [5/8]

◆  [6/8]

◆ name [7/8]

◆  [8/8]

◆ name_length [1/2]

◆  [2/2]

◆  [1/2]

◆ name_regex [2/2]

◆ num_entries

◆ obj_dumping

◆  [1/2]

◆ object [2/2]

◆ operation_id

◆ opt_mode

◆ packet [1/3]

◆  [2/3]

◆ packet [3/3]

◆ parameter_count [1/3]

◆ parameter_count [2/3]

◆  [3/3]

◆ parameter_name [1/3]

◆ parameter_name [2/3]

◆  [3/3]

◆ parameters

◆ payload

◆ payload_bytes

◆ pc

◆ pc_sample

◆ ptr [1/5]

◆  [2/5]

◆  [3/5]

◆ ptr [4/5]

◆  [5/5]

◆ queue [1/4]

◆ queue [2/4]

◆  [3/4]

◆ queue [4/4]

◆ queue_depth

◆ queue_id [1/4]

◆ queue_id [2/4]

◆ queue_id [3/4]

◆ queue_id [4/4]

◆ queue_idx [1/2]

◆ queue_idx [2/2]

◆ queue_index

◆  [1/2]

◆ range [2/2]

◆ record

◆  [1/2]

◆  [2/2]

◆ result_double [1/2]

◆  [2/2]

◆ result_float [1/2]

◆  [2/2]

◆  [1/2]

◆ result_int32 [2/2]

◆  [1/2]

◆ result_int64 [2/2]

◆ sampling_rate

◆ scratch_size

◆ se

◆  [1/2]

◆ segment [2/2]

◆ sgpr_count

◆ shader_engine_data [1/2]

◆ shader_engine_data [2/2]

◆ shader_engine_data_count

◆ signal_handle

◆ size [1/6]

◆ size [2/6]

◆  [3/6]

◆ size [4/6]

◆  [5/6]

◆  [6/6]

◆ spm_parameters

◆  [1/2]

◆ src [2/2]

◆ storage_file [1/2]

◆  [2/2]

◆  [1/2]

◆ storage_type [2/2]

◆  [1/3]

◆  [2/3]

◆ submit [3/3]

◆ thread_id [1/4]

◆ thread_id [2/4]

◆ thread_id [3/4]

◆ thread_id [4/4]

◆ timeout

◆ timestamp [1/2]

◆  [2/2]

◆ timestamp_on

◆ timestamps [1/3]

◆ timestamps [2/3]

◆ timestamps [3/3]

◆  [1/2]

◆  [2/2]

◆ trace_apis

◆ trace_local

◆ trace_name [1/4]

◆  [2/4]

◆ trace_name [3/4]

◆  [4/4]

◆  [1/3]

◆  [2/3]

◆  [3/3]

◆ trace_size

◆ type [1/2]

◆  [2/2]

◆  [1/3]

◆ unload [2/3]

◆  [3/3]

◆  [1/2]

◆ uri [2/2]

◆  [1/2]

◆ uri_length [2/2]

◆ value [1/17]

◆ value [2/17]

◆ value [3/17]

◆ value [4/17]

◆ value [5/17]

◆ value [6/17]

◆ value [7/17]

◆ value [8/17]

◆ value [9/17]

◆ value [10/17]

◆ value [11/17]

◆ value [12/17]

◆ value [13/17]

◆  [14/17]

◆ value [15/17]

◆ value [16/17]

◆ value [17/17]

◆ wave_size

◆ workgroup_size