1 // RUN: %libomptarget-compile-run-and-check-generic
2 // REQUIRES: ompt
3 // REQUIRES: gpu
4
5 /*
6 * Example OpenMP program that shows that both EMI and non-EMI
7 * callbacks cannot be registered for the same type. In the
8 * current implementation, the EMI callback overrides the non-EMI
9 * callback.
10 */
11
12 #include <omp.h>
13 #include <stdio.h>
14
15 #include "callbacks.h"
16 #include "register_both.h"
17
main()18 int main() {
19 int N = 100000;
20
21 int a[N];
22 int b[N];
23
24 int i;
25
26 for (i = 0; i < N; i++)
27 a[i] = 0;
28
29 for (i = 0; i < N; i++)
30 b[i] = i;
31
32 #pragma omp target parallel for
33 {
34 for (int j = 0; j < N; j++)
35 a[j] = b[j];
36 }
37
38 #pragma omp target teams distribute parallel for
39 {
40 for (int j = 0; j < N; j++)
41 a[j] = b[j];
42 }
43
44 int rc = 0;
45 for (i = 0; i < N; i++)
46 if (a[i] != b[i]) {
47 rc++;
48 printf("Wrong value: a[%d]=%d\n", i, a[i]);
49 }
50
51 if (!rc)
52 printf("Success\n");
53
54 return rc;
55 }
56
57 /// CHECK: Callback Init:
58 /// CHECK: Callback Load:
59 /// CHECK: Callback Target EMI: kind=1 endpoint=1
60 /// CHECK: Callback DataOp EMI: endpoint=1 optype=1
61 /// CHECK: Callback DataOp EMI: endpoint=2 optype=1
62 /// CHECK-NOT: dest=(nil)
63 /// CHECK: Callback DataOp EMI: endpoint=1 optype=2
64 /// CHECK: Callback DataOp EMI: endpoint=2 optype=2
65 /// CHECK: Callback DataOp EMI: endpoint=1 optype=1
66 /// CHECK: Callback DataOp EMI: endpoint=2 optype=1
67 /// CHECK-NOT: dest=(nil)
68 /// CHECK: Callback DataOp EMI: endpoint=1 optype=2
69 /// CHECK: Callback DataOp EMI: endpoint=2 optype=2
70 /// CHECK: Callback Submit: target_id=[[TARGET_ID:[0-9]+]] host_op_id=[[HOST_OP_ID:[0-9]+]] req_num_teams=1
71 /// CHECK: Callback DataOp EMI: endpoint=1 optype=3
72 /// CHECK: Callback DataOp EMI: endpoint=2 optype=3
73 /// CHECK: Callback DataOp EMI: endpoint=1 optype=3
74 /// CHECK: Callback DataOp EMI: endpoint=2 optype=3
75 /// CHECK: Callback DataOp EMI: endpoint=1 optype=4
76 /// CHECK: Callback DataOp EMI: endpoint=2 optype=4
77 /// CHECK: Callback DataOp EMI: endpoint=1 optype=4
78 /// CHECK: Callback DataOp EMI: endpoint=2 optype=4
79 /// CHECK: Callback Target EMI: kind=1 endpoint=2
80 /// CHECK: Callback Target EMI: kind=1 endpoint=1
81 /// CHECK: Callback DataOp EMI: endpoint=1 optype=1
82 /// CHECK: Callback DataOp EMI: endpoint=2 optype=1
83 /// CHECK-NOT: dest=(nil)
84 /// CHECK: Callback DataOp EMI: endpoint=1 optype=2
85 /// CHECK: Callback DataOp EMI: endpoint=2 optype=2
86 /// CHECK: Callback DataOp EMI: endpoint=1 optype=1
87 /// CHECK: Callback DataOp EMI: endpoint=2 optype=1
88 /// CHECK-NOT: dest=(nil)
89 /// CHECK: Callback DataOp EMI: endpoint=1 optype=2
90 /// CHECK: Callback DataOp EMI: endpoint=2 optype=2
91 /// CHECK: Callback Submit: target_id=[[TARGET_ID:[0-9]+]] host_op_id=[[HOST_OP_ID:[0-9]+]] req_num_teams=0
92 /// CHECK: Callback DataOp EMI: endpoint=1 optype=3
93 /// CHECK: Callback DataOp EMI: endpoint=2 optype=3
94 /// CHECK: Callback DataOp EMI: endpoint=1 optype=3
95 /// CHECK: Callback DataOp EMI: endpoint=2 optype=3
96 /// CHECK: Callback DataOp EMI: endpoint=1 optype=4
97 /// CHECK: Callback DataOp EMI: endpoint=2 optype=4
98 /// CHECK: Callback DataOp EMI: endpoint=1 optype=4
99 /// CHECK: Callback DataOp EMI: endpoint=2 optype=4
100 /// CHECK: Callback Target EMI: kind=1 endpoint=2
101 /// CHECK: Callback Fini:
102