1 // RUN: %clang_cc1 -verify -fopenmp -fopenmp-version=45 -ast-print %s -Wno-openmp-mapping | FileCheck %s --check-prefix=CHECK --check-prefix=OMP45
2 // RUN: %clang_cc1 -fopenmp -fopenmp-version=45 -x c++ -std=c++11 -emit-pch -o %t %s -Wno-openmp-mapping
3 // RUN: %clang_cc1 -fopenmp -fopenmp-version=45 -std=c++11 -include-pch %t -fsyntax-only -verify %s -ast-print -Wno-openmp-mapping | FileCheck %s --check-prefix=CHECK --check-prefix=OMP45
4 // RUN: %clang_cc1 -verify -fopenmp -fopenmp-version=50 -ast-print %s -Wno-openmp-mapping -DOMP5 | FileCheck %s --check-prefix=CHECK --check-prefix=OMP50
5 // RUN: %clang_cc1 -fopenmp -fopenmp-version=50 -x c++ -std=c++11 -emit-pch -o %t %s -Wno-openmp-mapping -DOMP5
6 // RUN: %clang_cc1 -fopenmp -fopenmp-version=50 -std=c++11 -include-pch %t -fsyntax-only -verify %s -ast-print -Wno-openmp-mapping -DOMP5 | FileCheck %s --check-prefix=CHECK --check-prefix=OMP50
7 
8 // RUN: %clang_cc1 -verify -fopenmp-simd -fopenmp-version=45 -ast-print %s -Wno-openmp-mapping | FileCheck %s --check-prefix=CHECK --check-prefix=OMP45
9 // RUN: %clang_cc1 -fopenmp-simd -fopenmp-version=45 -x c++ -std=c++11 -emit-pch -o %t %s -Wno-openmp-mapping
10 // RUN: %clang_cc1 -fopenmp-simd -fopenmp-version=45 -std=c++11 -include-pch %t -fsyntax-only -verify %s -ast-print -Wno-openmp-mapping | FileCheck %s --check-prefix=CHECK --check-prefix=OMP45
11 // RUN: %clang_cc1 -verify -fopenmp-simd -fopenmp-version=50 -ast-print %s -Wno-openmp-mapping -DOMP5 | FileCheck %s --check-prefix=CHECK --check-prefix=OMP50
12 // RUN: %clang_cc1 -fopenmp-simd -fopenmp-version=50 -x c++ -std=c++11 -emit-pch -o %t %s -Wno-openmp-mapping -DOMP5
13 // RUN: %clang_cc1 -fopenmp-simd -fopenmp-version=50 -std=c++11 -include-pch %t -fsyntax-only -verify %s -ast-print -Wno-openmp-mapping -DOMP5 | FileCheck %s --check-prefix=CHECK --check-prefix=OMP50
14 // expected-no-diagnostics
15 
16 #ifndef HEADER
17 #define HEADER
18 
19 typedef void **omp_allocator_handle_t;
20 extern const omp_allocator_handle_t omp_null_allocator;
21 extern const omp_allocator_handle_t omp_default_mem_alloc;
22 extern const omp_allocator_handle_t omp_large_cap_mem_alloc;
23 extern const omp_allocator_handle_t omp_const_mem_alloc;
24 extern const omp_allocator_handle_t omp_high_bw_mem_alloc;
25 extern const omp_allocator_handle_t omp_low_lat_mem_alloc;
26 extern const omp_allocator_handle_t omp_cgroup_mem_alloc;
27 extern const omp_allocator_handle_t omp_pteam_mem_alloc;
28 extern const omp_allocator_handle_t omp_thread_mem_alloc;
29 
30 void foo() {}
31 
32 struct S {
33   S(): a(0) {}
34   S(int v) : a(v) {}
35   int a;
36   typedef int type;
37 };
38 
39 template <typename T>
40 class S7 : public T {
41 protected:
42   T a;
43   S7() : a(0) {}
44 
45 public:
46   S7(typename T::type v) : a(v) {
47 #pragma omp target parallel for simd private(a) private(this->a) private(T::a)
48     for (int k = 0; k < a.a; ++k)
49       ++this->a.a;
50   }
51   S7 &operator=(S7 &s) {
52 #pragma omp target parallel for simd private(a) private(this->a)
53     for (int k = 0; k < s.a.a; ++k)
54       ++s.a.a;
55     return *this;
56   }
57 };
58 
59 // CHECK: #pragma omp target parallel for simd private(this->a) private(this->a) private(T::a){{$}}
60 // CHECK: #pragma omp target parallel for simd private(this->a) private(this->a)
61 // CHECK: #pragma omp target parallel for simd private(this->a) private(this->a) private(this->S::a)
62 
63 class S8 : public S7<S> {
64   S8() {}
65 
66 public:
67   S8(int v) : S7<S>(v){
68 #pragma omp target parallel for simd private(a) private(this->a) private(S7<S>::a)
69     for (int k = 0; k < a.a; ++k)
70       ++this->a.a;
71   }
72   S8 &operator=(S8 &s) {
73 #pragma omp target parallel for simd private(a) private(this->a)
74     for (int k = 0; k < s.a.a; ++k)
75       ++s.a.a;
76     return *this;
77   }
78 };
79 
80 // CHECK: #pragma omp target parallel for simd private(this->a) private(this->a) private(this->S7<S>::a)
81 // CHECK: #pragma omp target parallel for simd private(this->a) private(this->a)
82 
83 template <class T, int N>
84 T tmain(T argc, T *argv) {
85   T b = argc, c, d, e, f, h;
86   T arr[N][10], arr1[N];
87   T i, j;
88   T s;
89   static T a;
90 // CHECK: static T a;
91   static T g;
92   const T clen = 5;
93 // CHECK: T clen = 5;
94 #pragma omp threadprivate(g)
95 #pragma omp target parallel for simd schedule(dynamic) default(none) linear(a) allocate(a)
96   // CHECK: #pragma omp target parallel for simd schedule(dynamic) default(none) linear(a) allocate(a)
97   for (T i = 0; i < 2; ++i)
98     a = 2;
99 // CHECK-NEXT: for (T i = 0; i < 2; ++i)
100 // CHECK-NEXT: a = 2;
101 #pragma omp target parallel for simd allocate(d) private(argc, b), firstprivate(c, d), lastprivate(d, f) collapse(N) schedule(static, N) ordered if (parallel :argc) num_threads(N) default(shared) shared(e) reduction(+ : h)
102   for (int i = 0; i < 2; ++i)
103     for (int j = 0; j < 2; ++j)
104       for (int j = 0; j < 2; ++j)
105         for (int j = 0; j < 2; ++j)
106           for (int j = 0; j < 2; ++j)
107             foo();
108   // CHECK-NEXT: #pragma omp target parallel for simd allocate(d) private(argc,b) firstprivate(c,d) lastprivate(d,f) collapse(N) schedule(static, N) ordered if(parallel: argc) num_threads(N) default(shared) shared(e) reduction(+: h)
109   // CHECK-NEXT: for (int i = 0; i < 2; ++i)
110   // CHECK-NEXT: for (int j = 0; j < 2; ++j)
111   // CHECK-NEXT: for (int j = 0; j < 2; ++j)
112   // CHECK-NEXT: for (int j = 0; j < 2; ++j)
113   // CHECK-NEXT: for (int j = 0; j < 2; ++j)
114   // CHECK-NEXT: foo();
115 
116 #pragma omp target parallel for simd default(none), private(argc,b) firstprivate(argv) shared (d) if(parallel:argc > 0) num_threads(N) proc_bind(master) reduction(+:c, arr1[argc]) reduction(max:e, arr[:N][0:10])
117   for (T i = 0; i < 2; ++i) {}
118   // CHECK: #pragma omp target parallel for simd default(none) private(argc,b) firstprivate(argv) shared(d) if(parallel: argc > 0) num_threads(N) proc_bind(master) reduction(+: c,arr1[argc]) reduction(max: e,arr[:N][0:10])
119   // CHECK-NEXT: for (T i = 0; i < 2; ++i) {
120   // CHECK-NEXT: }
121 
122 #pragma omp target parallel for simd if(N) num_threads(s) proc_bind(close) reduction(^:e, f, arr[0:N][:argc]) reduction(&& : h)
123   for (T i = 0; i < 2; ++i) {}
124   // CHECK: #pragma omp target parallel for simd if(N) num_threads(s) proc_bind(close) reduction(^: e,f,arr[0:N][:argc]) reduction(&&: h)
125   // CHECK-NEXT: for (T i = 0; i < 2; ++i) {
126   // CHECK-NEXT: }
127 
128 #ifdef OMP5
129 #pragma omp target parallel for simd if(target:argc > 0) if (simd: argc) nontemporal(argc, c, d) order(concurrent) allocate(omp_high_bw_mem_alloc:f) private(f) uses_allocators(omp_high_bw_mem_alloc)
130 #else
131 #pragma omp target parallel for simd if(target:argc > 0)
132 #endif // OMP5
133   for (T i = 0; i < 2; ++i) {}
134   // OMP45: #pragma omp target parallel for simd if(target: argc > 0)
135   // OMP50: #pragma omp target parallel for simd if(target: argc > 0) if(simd: argc) nontemporal(argc,c,d) order(concurrent) allocate(omp_high_bw_mem_alloc: f) private(f) uses_allocators(omp_high_bw_mem_alloc)
136   // CHECK-NEXT: for (T i = 0; i < 2; ++i) {
137   // CHECK-NEXT: }
138 
139 #pragma omp target parallel for simd if(parallel:argc > 0)
140   for (T i = 0; i < 2; ++i) {}
141   // CHECK: #pragma omp target parallel for simd if(parallel: argc > 0)
142   // CHECK-NEXT: for (T i = 0; i < 2; ++i) {
143   // CHECK-NEXT: }
144 
145 #pragma omp target parallel for simd if(N)
146   for (T i = 0; i < 2; ++i) {}
147   // CHECK: #pragma omp target parallel for simd if(N)
148   // CHECK-NEXT: for (T i = 0; i < 2; ++i) {
149   // CHECK-NEXT: }
150 
151 #pragma omp target parallel for simd map(i)
152   for (T i = 0; i < 2; ++i) {}
153   // CHECK: #pragma omp target parallel for simd map(tofrom: i)
154   // CHECK-NEXT: for (T i = 0; i < 2; ++i) {
155   // CHECK-NEXT: }
156 
157 #pragma omp target parallel for simd map(arr1[0:10], i)
158   for (T i = 0; i < 2; ++i) {}
159   // CHECK: #pragma omp target parallel for simd map(tofrom: arr1[0:10],i)
160   // CHECK-NEXT: for (T i = 0; i < 2; ++i) {
161   // CHECK-NEXT: }
162 
163 #pragma omp target parallel for simd map(to: i) map(from: j)
164   for (T i = 0; i < 2; ++i) {}
165   // CHECK: #pragma omp target parallel for simd map(to: i) map(from: j)
166   // CHECK-NEXT: for (T i = 0; i < 2; ++i) {
167   // CHECK-NEXT: }
168 
169 #pragma omp target parallel for simd map(always,alloc: i)
170   for (T i = 0; i < 2; ++i) {}
171   // CHECK: #pragma omp target parallel for simd map(always,alloc: i)
172   // CHECK-NEXT: for (T i = 0; i < 2; ++i) {
173   // CHECK-NEXT: }
174 
175 #pragma omp target parallel for simd nowait
176   for (T i = 0; i < 2; ++i) {}
177   // CHECK: #pragma omp target parallel for simd nowait
178   // CHECK-NEXT: for (T i = 0; i < 2; ++i) {
179   // CHECK-NEXT: }
180 
181 #pragma omp target parallel for simd depend(in : argc, arr[i:argc], arr1[:])
182   for (T i = 0; i < 2; ++i) {}
183   // CHECK: #pragma omp target parallel for simd depend(in : argc,arr[i:argc],arr1[:])
184   // CHECK-NEXT: for (T i = 0; i < 2; ++i) {
185   // CHECK-NEXT: }
186 
187 #pragma omp target parallel for simd defaultmap(tofrom: scalar)
188   for (T i = 0; i < 2; ++i) {}
189   // CHECK: #pragma omp target parallel for simd defaultmap(tofrom: scalar)
190   // CHECK-NEXT: for (T i = 0; i < 2; ++i) {
191   // CHECK-NEXT: }
192 
193 #pragma omp target parallel for simd safelen(clen-1)
194   for (T i = 0; i < 2; ++i) {}
195   // CHECK: #pragma omp target parallel for simd safelen(clen - 1)
196   // CHECK-NEXT: for (T i = 0; i < 2; ++i) {
197   // CHECK-NEXT: }
198 
199 #pragma omp target parallel for simd simdlen(clen-1)
200   for (T i = 0; i < 2; ++i) {}
201   // CHECK: #pragma omp target parallel for simd simdlen(clen - 1)
202   // CHECK-NEXT: for (T i = 0; i < 2; ++i) {
203   // CHECK-NEXT: }
204 
205 #pragma omp target parallel for simd aligned(arr1:N-1)
206   for (T i = 0; i < N; ++i) {}
207   // CHECK: #pragma omp target parallel for simd aligned(arr1: N - 1)
208   // CHECK-NEXT: for (T i = 0; i < N; ++i) {
209   // CHECK-NEXT: }
210 
211   return T();
212 }
213 
214 int main(int argc, char **argv) {
215   int b = argc, c, d, e, f, h;
216   int arr[5][10], arr1[5];
217   int i, j;
218   int s;
219   static int a;
220 // CHECK: static int a;
221   const int clen = 5;
222 // CHECK: int clen = 5;
223   static float g;
224 #pragma omp threadprivate(g)
225 #pragma omp target parallel for simd schedule(guided, argc) default(none) linear(a) shared(argc)
226   // CHECK: #pragma omp target parallel for simd schedule(guided, argc) default(none) linear(a) shared(argc)
227   for (int i = 0; i < 2; ++i)
228     a = 2;
229 // CHECK-NEXT: for (int i = 0; i < 2; ++i)
230 // CHECK-NEXT: a = 2;
231 
232 #pragma omp target parallel for simd private(argc, b), firstprivate(argv, c), lastprivate(d, f) collapse(2) schedule(auto) ordered if (target: argc) num_threads(a) default(shared) shared(e) reduction(+ : h) linear(a:-5)
233   for (int i = 0; i < 10; ++i)
234     for (int j = 0; j < 10; ++j)
235       foo();
236   // CHECK: #pragma omp target parallel for simd private(argc,b) firstprivate(argv,c) lastprivate(d,f) collapse(2) schedule(auto) ordered if(target: argc) num_threads(a) default(shared) shared(e) reduction(+: h) linear(a: -5)
237   // CHECK-NEXT: for (int i = 0; i < 10; ++i)
238   // CHECK-NEXT: for (int j = 0; j < 10; ++j)
239   // CHECK-NEXT: foo();
240 
241 #pragma omp target parallel for simd default(none), private(argc,b) firstprivate(argv) shared (d) if (parallel:argc > 0) num_threads(5) proc_bind(master) reduction(+:c, arr1[argc]) reduction(max:e, arr[:5][0:10])
242   for (int i = 0; i < 2; ++i) {}
243   // CHECK: #pragma omp target parallel for simd default(none) private(argc,b) firstprivate(argv) shared(d) if(parallel: argc > 0) num_threads(5) proc_bind(master) reduction(+: c,arr1[argc]) reduction(max: e,arr[:5][0:10])
244   // CHECK-NEXT: for (int i = 0; i < 2; ++i) {
245   // CHECK-NEXT: }
246 
247 #pragma omp target parallel for simd if (5) num_threads(s) proc_bind(close) reduction(^:e, f, arr[0:5][:argc]) reduction(&& : h)
248   for (int i = 0; i < 2; ++i) {}
249   // CHECK: #pragma omp target parallel for simd if(5) num_threads(s) proc_bind(close) reduction(^: e,f,arr[0:5][:argc]) reduction(&&: h)
250   // CHECK-NEXT: for (int i = 0; i < 2; ++i) {
251   // CHECK-NEXT: }
252 
253 #pragma omp target parallel for simd if (target:argc > 0)
254   for (int i = 0; i < 2; ++i) {}
255   // CHECK: #pragma omp target parallel for simd if(target: argc > 0)
256   // CHECK-NEXT: for (int i = 0; i < 2; ++i) {
257   // CHECK-NEXT: }
258 
259 #ifdef OMP5
260 #pragma omp target parallel for simd if (parallel:argc > 0) if(simd: argc)
261 #else
262 #pragma omp target parallel for simd if (parallel:argc > 0)
263 #endif // OMP5
264   for (int i = 0; i < 2; ++i) {}
265   // OMP45: #pragma omp target parallel for simd if(parallel: argc > 0)
266   // OMP50: #pragma omp target parallel for simd if(parallel: argc > 0) if(simd: argc)
267   // CHECK-NEXT: for (int i = 0; i < 2; ++i) {
268   // CHECK-NEXT: }
269 
270 #pragma omp target parallel for simd if (5)
271   for (int i = 0; i < 2; ++i) {}
272   // CHECK: #pragma omp target parallel for simd if(5)
273   // CHECK-NEXT: for (int i = 0; i < 2; ++i) {
274   // CHECK-NEXT: }
275 
276 #pragma omp target parallel for simd map(i)
277   for (int i = 0; i < 2; ++i) {}
278   // CHECK: #pragma omp target parallel for simd  map(tofrom: i)
279   // CHECK-NEXT: for (int i = 0; i < 2; ++i) {
280   // CHECK-NEXT: }
281 
282 #pragma omp target parallel for simd map(arr1[0:10], i)
283   for (int i = 0; i < 2; ++i) {}
284   // CHECK: #pragma omp target parallel for simd map(tofrom: arr1[0:10],i)
285   // CHECK-NEXT: for (int i = 0; i < 2; ++i) {
286   // CHECK-NEXT: }
287 
288 #pragma omp target parallel for simd map(to: i) map(from: j)
289   for (int i = 0; i < 2; ++i) {}
290   // CHECK: #pragma omp target parallel for simd map(to: i) map(from: j)
291   // CHECK-NEXT: for (int i = 0; i < 2; ++i) {
292   // CHECK-NEXT: }
293 
294 #pragma omp target parallel for simd map(always,alloc: i)
295   for (int i = 0; i < 2; ++i) {}
296   // CHECK: #pragma omp target parallel for simd map(always,alloc: i)
297   // CHECK-NEXT: for (int i = 0; i < 2; ++i) {
298   // CHECK-NEXT: }
299 
300 #pragma omp target parallel for simd nowait
301   for (int i = 0; i < 2; ++i) {}
302   // CHECK: #pragma omp target parallel for simd nowait
303   // CHECK-NEXT: for (int i = 0; i < 2; ++i) {
304   // CHECK-NEXT: }
305 
306 #pragma omp target parallel for simd depend(in : argc, arr[i:argc], arr1[:])
307   for (int i = 0; i < 2; ++i) {}
308   // CHECK: #pragma omp target parallel for simd depend(in : argc,arr[i:argc],arr1[:])
309   // CHECK-NEXT: for (int i = 0; i < 2; ++i) {
310   // CHECK-NEXT: }
311 
312 #pragma omp target parallel for simd defaultmap(tofrom: scalar)
313   for (int i = 0; i < 2; ++i) {}
314   // CHECK: #pragma omp target parallel for simd defaultmap(tofrom: scalar)
315   // CHECK-NEXT: for (int i = 0; i < 2; ++i) {
316   // CHECK-NEXT: }
317 
318 #pragma omp target parallel for simd safelen(clen-1)
319   for (int i = 0; i < 2; ++i) {}
320   // CHECK: #pragma omp target parallel for simd safelen(clen - 1)
321   // CHECK-NEXT: for (int i = 0; i < 2; ++i) {
322   // CHECK-NEXT: }
323 
324 #pragma omp target parallel for simd simdlen(clen-1)
325   for (int i = 0; i < 2; ++i) {}
326   // CHECK: #pragma omp target parallel for simd simdlen(clen - 1)
327   // CHECK-NEXT: for (int i = 0; i < 2; ++i) {
328   // CHECK-NEXT: }
329 
330 #pragma omp target parallel for simd aligned(arr1:4)
331   for (int i = 0; i < 2; ++i) {}
332   // CHECK: #pragma omp target parallel for simd aligned(arr1: 4)
333   // CHECK-NEXT: for (int i = 0; i < 2; ++i) {
334   // CHECK-NEXT: }
335 
336   return (tmain<int, 5>(argc, &argc));
337 }
338 
339 #endif
340