The profiling records are asynchronously logged to the pool and can be associated with the respective GPU kernels.
More...
|
| 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) |
| |
|
| 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 |
| |
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.