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
foo()30 void foo() {}
31
32 struct S {
SS33 S(): a(0) {}
SS34 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;
S7()43 S7() : a(0) {}
44
45 public:
S7(typename T::type v)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 }
operator =(S7 & s)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> {
S8()64 S8() {}
65
66 public:
S8(int v)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 }
operator =(S8 & s)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
main(int argc,char ** argv)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