xref: /llvm-project/openmp/runtime/test/ompt/tasks/explicit_task_thread_num.c (revision d6f00654fbc686f5413f9c8d1bac2c4050fdf350)
159a994e8S@vladaindjic // RUN: %libomp-compile-and-run | FileCheck %s
259a994e8S@vladaindjic // REQUIRES: ompt
359a994e8S@vladaindjic 
459a994e8S@vladaindjic #include "callback.h"
559a994e8S@vladaindjic #include <omp.h>
659a994e8S@vladaindjic 
759a994e8S@vladaindjic 
859a994e8S@vladaindjic __attribute__ ((noinline)) // workaround for bug in icc
print_task_info_at(int ancestor_level,int id)959a994e8S@vladaindjic void print_task_info_at(int ancestor_level, int id)
1059a994e8S@vladaindjic {
1159a994e8S@vladaindjic #pragma omp critical
1259a994e8S@vladaindjic   {
1359a994e8S@vladaindjic     int task_type;
1459a994e8S@vladaindjic     char buffer[2048];
1559a994e8S@vladaindjic     ompt_data_t *parallel_data;
1659a994e8S@vladaindjic     ompt_data_t *task_data;
1759a994e8S@vladaindjic     int thread_num;
1859a994e8S@vladaindjic     ompt_get_task_info(ancestor_level, &task_type, &task_data, NULL,
1959a994e8S@vladaindjic                        &parallel_data, &thread_num);
2059a994e8S@vladaindjic     format_task_type(task_type, buffer);
2159a994e8S@vladaindjic     printf("%" PRIu64 ": ancestor_level=%d id=%d task_type=%s=%d "
2259a994e8S@vladaindjic                       "parallel_id=%" PRIu64 " task_id=%" PRIu64
2359a994e8S@vladaindjic                       " thread_num=%d\n",
2459a994e8S@vladaindjic         ompt_get_thread_data()->value, ancestor_level, id, buffer,
2559a994e8S@vladaindjic         task_type, parallel_data->value, task_data->value, thread_num);
2659a994e8S@vladaindjic   }
2759a994e8S@vladaindjic };
2859a994e8S@vladaindjic 
main()2959a994e8S@vladaindjic int main()
3059a994e8S@vladaindjic {
3159a994e8S@vladaindjic 
3259a994e8S@vladaindjic #pragma omp parallel num_threads(2)
3359a994e8S@vladaindjic   {
3459a994e8S@vladaindjic 
3559a994e8S@vladaindjic     if (omp_get_thread_num() == 1) {
3659a994e8S@vladaindjic       // To assert that task is executed by the worker thread,
3759a994e8S@vladaindjic       // if(0) is used in order to ensure that the task is immediately
3859a994e8S@vladaindjic       // executed after its creation.
3959a994e8S@vladaindjic #pragma omp task if(0)
4059a994e8S@vladaindjic       {
4159a994e8S@vladaindjic         // thread_num should be equal to 1 for both explicit and implicit task
4259a994e8S@vladaindjic         print_task_info_at(0, 1);
4359a994e8S@vladaindjic         print_task_info_at(1, 0);
4459a994e8S@vladaindjic       };
4559a994e8S@vladaindjic     }
4659a994e8S@vladaindjic   }
4759a994e8S@vladaindjic 
4859a994e8S@vladaindjic   // Check if libomp supports the callbacks for this test.
4959a994e8S@vladaindjic   // CHECK-NOT: {{^}}0: Could not register callback 'ompt_event_parallel_begin'
5059a994e8S@vladaindjic   // CHECK-NOT: {{^}}0: Could not register callback 'ompt_callback_task_create'
5159a994e8S@vladaindjic   // CHECK-NOT: {{^}}0: Could not register callback 'ompt_callback_implicit_task'
5259a994e8S@vladaindjic 
5359a994e8S@vladaindjic   // CHECK: {{^}}0: NULL_POINTER=[[NULL:.*$]]
5459a994e8S@vladaindjic   // CHECK: {{^}}[[MASTER_ID:[0-9]+]]: ompt_event_initial_task_begin
5559a994e8S@vladaindjic 
5659a994e8S@vladaindjic   // parallel region used only to determine worker thread id
5759a994e8S@vladaindjic   // CHECK: {{^}}[[MASTER_ID]]: ompt_event_parallel_begin
58*d6f00654SAlex   // CHECK: {{^}}[[WID:[0-9]+]]: ompt_event_implicit_task{{.*}}thread_num=1
5959a994e8S@vladaindjic 
6059a994e8S@vladaindjic   // thread_num must be equal to 1 for both explicit and the implicit tasks
61*d6f00654SAlex   // CHECK: {{^}}[[WID]]: ancestor_level=0 id=1 task_type=ompt_task_explicit
6259a994e8S@vladaindjic   // CHECK-SAME: thread_num=1
63*d6f00654SAlex   // CHECK: {{^}}[[WID]]: ancestor_level=1 id=0 task_type=ompt_task_implicit
6459a994e8S@vladaindjic   // CHECK-SAME: thread_num=1
6559a994e8S@vladaindjic 
6659a994e8S@vladaindjic   return 0;
6759a994e8S@vladaindjic }
68