5fae049dc2
libgomp/ * acc_prof.h: New file. * oacc-profiling.c: Likewise. * Makefile.am (nodist_libsubinclude_HEADERS, libgomp_la_SOURCES): Add these, respectively. * Makefile.in: Regenerate. * env.c (initialize_env): Call goacc_profiling_initialize. * oacc-plugin.c (GOMP_PLUGIN_goacc_thread) (GOMP_PLUGIN_goacc_profiling_dispatch): New functions. * oacc-plugin.h (GOMP_PLUGIN_goacc_thread) (GOMP_PLUGIN_goacc_profiling_dispatch): Declare. * libgomp.map (OACC_2.5.1): Add acc_prof_lookup, acc_prof_register, acc_prof_unregister, and acc_register_library. (GOMP_PLUGIN_1.3): Add GOMP_PLUGIN_goacc_profiling_dispatch, and GOMP_PLUGIN_goacc_thread. * oacc-int.h (struct goacc_thread): Add prof_info, api_info, prof_callbacks_enabled members. (goacc_prof_enabled, goacc_profiling_initialize) (_goacc_profiling_dispatch_p, _goacc_profiling_setup_p) (goacc_profiling_dispatch): Declare. (GOACC_PROF_ENABLED, GOACC_PROFILING_DISPATCH_P) (GOACC_PROFILING_SETUP_P): Define. * oacc-async.c (acc_async_test, acc_async_test_all, acc_wait) (acc_wait_async, acc_wait_all, acc_wait_all_async): Update for OpenACC Profiling Interface. * oacc-cuda.c (acc_get_current_cuda_device) (acc_get_current_cuda_context, acc_get_cuda_stream) (acc_set_cuda_stream): Likewise. * oacc-init.c (acc_init_1, goacc_attach_host_thread_to_device) (acc_init, acc_set_device_type, acc_get_device_type) (acc_get_device_num, goacc_lazy_initialize): Likewise. * oacc-mem.c (acc_malloc, acc_free, memcpy_tofrom_device) (acc_deviceptr, acc_hostptr, acc_is_present, acc_map_data) (acc_unmap_data, present_create_copy, delete_copyout) (update_dev_host): Likewise. * oacc-parallel.c (GOACC_parallel_keyed, GOACC_data_start) (GOACC_data_end, GOACC_enter_exit_data, GOACC_update, GOACC_wait): Likewise. * plugin/plugin-nvptx.c (nvptx_exec, nvptx_alloc, nvptx_free) (GOMP_OFFLOAD_openacc_exec, GOMP_OFFLOAD_openacc_async_exec): Likewise. * libgomp.texi: Update. * testsuite/libgomp.oacc-c-c++-common/acc_prof-dispatch-1.c: New file. * testsuite/libgomp.oacc-c-c++-common/acc_prof-init-1.c: Likewise. * testsuite/libgomp.oacc-c-c++-common/acc_prof-kernels-1.c: Likewise. * testsuite/libgomp.oacc-c-c++-common/acc_prof-parallel-1.c: Likewise. * testsuite/libgomp.oacc-c-c++-common/acc_prof-valid_bytes-1.c: Likewise. * testsuite/libgomp.oacc-c-c++-common/acc_prof-version-1.c: Likewise. From-SVN: r271346
77 lines
2.5 KiB
C
77 lines
2.5 KiB
C
/* Test the 'version' field of 'acc_prof_info'. */
|
|
|
|
#undef NDEBUG
|
|
#include <assert.h>
|
|
|
|
#include <acc_prof.h>
|
|
|
|
|
|
#define DEBUG_printf(...) //__builtin_printf (__VA_ARGS__)
|
|
|
|
|
|
static int ev_count;
|
|
|
|
|
|
static void cb_any_event (acc_prof_info *prof_info, acc_event_info *event_info, acc_api_info *api_info)
|
|
{
|
|
DEBUG_printf ("%s %d\n", __FUNCTION__, prof_info->event_type);
|
|
|
|
assert (prof_info->version == 201711);
|
|
|
|
++ev_count;
|
|
}
|
|
|
|
|
|
void acc_register_library (acc_prof_reg reg_, acc_prof_reg unreg_, acc_prof_lookup_func lookup_)
|
|
{
|
|
DEBUG_printf ("%s\n", __FUNCTION__);
|
|
|
|
reg_ (acc_ev_device_init_start, cb_any_event, acc_reg);
|
|
reg_ (acc_ev_device_init_end, cb_any_event, acc_reg);
|
|
reg_ (acc_ev_device_shutdown_start, cb_any_event, acc_reg);
|
|
reg_ (acc_ev_device_shutdown_end, cb_any_event, acc_reg);
|
|
reg_ (acc_ev_runtime_shutdown, cb_any_event, acc_reg);
|
|
reg_ (acc_ev_create, cb_any_event, acc_reg);
|
|
reg_ (acc_ev_delete, cb_any_event, acc_reg);
|
|
reg_ (acc_ev_alloc, cb_any_event, acc_reg);
|
|
reg_ (acc_ev_free, cb_any_event, acc_reg);
|
|
reg_ (acc_ev_enter_data_start, cb_any_event, acc_reg);
|
|
reg_ (acc_ev_enter_data_end, cb_any_event, acc_reg);
|
|
reg_ (acc_ev_exit_data_start, cb_any_event, acc_reg);
|
|
reg_ (acc_ev_exit_data_end, cb_any_event, acc_reg);
|
|
reg_ (acc_ev_update_start, cb_any_event, acc_reg);
|
|
reg_ (acc_ev_update_end, cb_any_event, acc_reg);
|
|
reg_ (acc_ev_compute_construct_start, cb_any_event, acc_reg);
|
|
reg_ (acc_ev_compute_construct_end, cb_any_event, acc_reg);
|
|
reg_ (acc_ev_enqueue_launch_start, cb_any_event, acc_reg);
|
|
reg_ (acc_ev_enqueue_launch_end, cb_any_event, acc_reg);
|
|
reg_ (acc_ev_enqueue_upload_start, cb_any_event, acc_reg);
|
|
reg_ (acc_ev_enqueue_upload_end, cb_any_event, acc_reg);
|
|
reg_ (acc_ev_enqueue_download_start, cb_any_event, acc_reg);
|
|
reg_ (acc_ev_enqueue_download_end, cb_any_event, acc_reg);
|
|
reg_ (acc_ev_wait_start, cb_any_event, acc_reg);
|
|
reg_ (acc_ev_wait_end, cb_any_event, acc_reg);
|
|
}
|
|
|
|
|
|
int main()
|
|
{
|
|
acc_register_library (acc_prof_register, acc_prof_unregister, acc_prof_lookup);
|
|
|
|
ev_count = 0;
|
|
|
|
/* Trigger tests done in 'cb_*' functions. */
|
|
#pragma acc parallel
|
|
{
|
|
asm volatile ("" : : : "memory"); // TODO PR90488
|
|
}
|
|
|
|
DEBUG_printf ("ev_count = %d\n", ev_count);
|
|
/* We don't know exactly how many events to expect, but we at least expect
|
|
'acc_ev_device_init_start', 'acc_ev_device_init_end',
|
|
'acc_ev_compute_construct_start', 'acc_ev_compute_construct_end'. */
|
|
assert (ev_count >= 4);
|
|
|
|
return 0;
|
|
}
|