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 | |
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(format: "Wrong value: a[%d]=%d\n" , i, a[i]); |
49 | } |
50 | |
51 | if (!rc) |
52 | printf(format: "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 | |