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