offload/test/ompt/veccopy_no_device_init.c

   1 // clang-format off
   2 // RUN: %libomptarget-compile-run-and-check-generic
   3 // REQUIRES: ompt
   4
   5 /*
   6  * Example OpenMP program that shows that if no device init callback
   7  * is registered, the other callbacks won't be activated.
   8  */
   9 // clang-format on
  10 #include <omp.h>
  11 #include <stdio.h>
  12
  13 #include "callbacks.h"
  14 #include "register_no_device_init.h"
  15
  16 int main() {
  17   int N = 100000;
  18
  19   int a[N];
  20   int b[N];
  21
  22   int i;
  23
  24   for (i = 0; i < N; i++)
  25     a[i] = 0;
  26
  27   for (i = 0; i < N; i++)
  28     b[i] = i;
  29
  30 #pragma omp target parallel for
  31   {
  32     for (int j = 0; j < N; j++)
  33       a[j] = b[j];
  34   }
  35
  36 #pragma omp target teams distribute parallel for
  37   {
  38     for (int j = 0; j < N; j++)
  39       a[j] = b[j];
  40   }
  41
  42   int rc = 0;
  43   for (i = 0; i < N; i++)
  44     if (a[i] != b[i]) {
  45       rc++;
  46       printf("Wrong value: a[%d]=%d\n", i, a[i]);
  47     }
  48
  49   if (!rc)
  50     printf("Success\n");
  51
  52   return rc;
  53 }
  54 // clang-format off
  55 /// CHECK-NOT: Callback Init:
  56 /// CHECK: Callback Load:
  57 /// CHECK: Callback Target: target_id=[[TARGET_ID:[0-9]+]] kind=1 endpoint=1
  58 /// CHECK: Callback DataOp: target_id=[[TARGET_ID:[0-9]+]] host_op_id=[[HOST_OP_ID:[0-9]+]] optype=1
  59 /// CHECK: Callback DataOp: target_id=[[TARGET_ID:[0-9]+]] host_op_id=[[HOST_OP_ID:[0-9]+]] optype=2
  60 /// CHECK: Callback DataOp: target_id=[[TARGET_ID:[0-9]+]] host_op_id=[[HOST_OP_ID:[0-9]+]] optype=1
  61 /// CHECK: Callback DataOp: target_id=[[TARGET_ID:[0-9]+]] host_op_id=[[HOST_OP_ID:[0-9]+]] optype=2
  62 /// CHECK: Callback Submit: target_id=[[TARGET_ID:[0-9]+]] host_op_id=[[HOST_OP_ID:[0-9]+]] req_num_teams=1
  63 /// CHECK: Callback DataOp: target_id=[[TARGET_ID:[0-9]+]] host_op_id=[[HOST_OP_ID:[0-9]+]] optype=3
  64 /// CHECK: Callback DataOp: target_id=[[TARGET_ID:[0-9]+]] host_op_id=[[HOST_OP_ID:[0-9]+]] optype=3
  65 /// CHECK: Callback DataOp: target_id=[[TARGET_ID:[0-9]+]] host_op_id=[[HOST_OP_ID:[0-9]+]] optype=4
  66 /// CHECK: Callback DataOp: target_id=[[TARGET_ID:[0-9]+]] host_op_id=[[HOST_OP_ID:[0-9]+]] optype=4
  67 /// CHECK: Callback Target: target_id=[[TARGET_ID:[0-9]+]] kind=1 endpoint=2
  68
  69 /// CHECK: Callback Target: target_id=[[TARGET_ID:[0-9]+]] kind=1 endpoint=1
  70 /// CHECK: Callback DataOp: target_id=[[TARGET_ID:[0-9]+]] host_op_id=[[HOST_OP_ID:[0-9]+]] optype=1
  71 /// CHECK: Callback DataOp: target_id=[[TARGET_ID:[0-9]+]] host_op_id=[[HOST_OP_ID:[0-9]+]] optype=2
  72 /// CHECK: Callback DataOp: target_id=[[TARGET_ID:[0-9]+]] host_op_id=[[HOST_OP_ID:[0-9]+]] optype=1
  73 /// CHECK: Callback DataOp: target_id=[[TARGET_ID:[0-9]+]] host_op_id=[[HOST_OP_ID:[0-9]+]] optype=2
  74 /// CHECK: Callback Submit: target_id=[[TARGET_ID:[0-9]+]] host_op_id=[[HOST_OP_ID:[0-9]+]] req_num_teams=0
  75 /// CHECK: Callback DataOp: target_id=[[TARGET_ID:[0-9]+]] host_op_id=[[HOST_OP_ID:[0-9]+]] optype=3
  76 /// CHECK: Callback DataOp: target_id=[[TARGET_ID:[0-9]+]] host_op_id=[[HOST_OP_ID:[0-9]+]] optype=3
  77 /// CHECK: Callback DataOp: target_id=[[TARGET_ID:[0-9]+]] host_op_id=[[HOST_OP_ID:[0-9]+]] optype=4
  78 /// CHECK: Callback DataOp: target_id=[[TARGET_ID:[0-9]+]] host_op_id=[[HOST_OP_ID:[0-9]+]] optype=4
  79 /// CHECK: Callback Target: target_id=[[TARGET_ID:[0-9]+]] kind=1 endpoint=2
  80 /// CHECK-NOT: Callback Fini: