Gitiles
Code Review Sign In
gerrit-public.fairphone.software / toolchain / llvm-project / fbb4d1e43d0db9f8d1514a0209bb01f56e49d75f / . / clang / test / OpenMP / nvptx_SPMD_codegen.cpp
blob: 5fa820fcba703787519a26523ccaacf70ea2d43d [file] [log] [blame]
Alexey Bataev8d8e1232018-08-29 18:32:21 +0000[diff] [blame]1// Test target codegen - host bc file has to be created first.
2// RUN: %clang_cc1 -verify -fopenmp -x c++ -triple powerpc64le-unknown-unknown -fopenmp-targets=nvptx64-nvidia-cuda -emit-llvm-bc %s -o %t-ppc-host.bc
3// RUN: %clang_cc1 -verify -fopenmp -x c++ -triple nvptx64-unknown-unknown -fopenmp-targets=nvptx64-nvidia-cuda -emit-llvm %s -fopenmp-is-device -fopenmp-host-ir-file-path %t-ppc-host.bc -o - | FileCheck %s
4// RUN: %clang_cc1 -verify -fopenmp -x c++ -triple i386-unknown-unknown -fopenmp-targets=nvptx-nvidia-cuda -emit-llvm-bc %s -o %t-x86-host.bc
5// RUN: %clang_cc1 -verify -fopenmp -x c++ -triple nvptx-unknown-unknown -fopenmp-targets=nvptx-nvidia-cuda -emit-llvm %s -fopenmp-is-device -fopenmp-host-ir-file-path %t-x86-host.bc -o - | FileCheck %s
6// RUN: %clang_cc1 -verify -fopenmp -fexceptions -fcxx-exceptions -x c++ -triple nvptx-unknown-unknown -fopenmp-targets=nvptx-nvidia-cuda -emit-llvm %s -fopenmp-is-device -fopenmp-host-ir-file-path %t-x86-host.bc -o - | FileCheck %s
7// expected-no-diagnostics
8#ifndef HEADER
9#define HEADER
10
Alexey Bataev5e287932019-04-16 15:39:12 +0000[diff] [blame]11int a;
12
Alexey Bataev8d8e1232018-08-29 18:32:21 +0000[diff] [blame]13// CHECK-NOT: @__omp_offloading_{{.+}}_exec_mode = weak constant i8 1
Alexey Bataeve8ad4b72018-11-26 18:37:09 +0000[diff] [blame]14// CHECK-DAG: [[DISTR_LIGHT:@.+]] = private unnamed_addr constant %struct.ident_t { i32 0, i32 2050, i32 3, i32 0, i8* getelementptr inbounds
15// CHECK-DAG: [[FOR_LIGHT:@.+]] = private unnamed_addr constant %struct.ident_t { i32 0, i32 514, i32 3, i32 0, i8* getelementptr inbounds
16// CHECK-DAG: [[LIGHT:@.+]] = private unnamed_addr constant %struct.ident_t { i32 0, i32 2, i32 3, i32 0, i8* getelementptr inbounds
17// CHECK-DAG: [[DISTR_FULL:@.+]] = private unnamed_addr constant %struct.ident_t { i32 0, i32 2050, i32 1, i32 0, i8* getelementptr inbounds
18// CHECK-DAG: [[FULL:@.+]] = private unnamed_addr constant %struct.ident_t { i32 0, i32 2, i32 1, i32 0, i8* getelementptr inbounds
19// CHECK-DAG: [[BAR_LIGHT:@.+]] = private unnamed_addr constant %struct.ident_t { i32 0, i32 66, i32 3, i32 0, i8* getelementptr inbounds
20// CHECK-DAG: [[BAR_FULL:@.+]] = private unnamed_addr constant %struct.ident_t { i32 0, i32 66, i32 1, i32 0, i8* getelementptr inbounds
Alexey Bataevceeaa482018-11-21 21:04:34 +0000[diff] [blame]21// CHECK-NOT: @__omp_offloading_{{.+}}_exec_mode = weak constant i8 1
Alexey Bataev8d8e1232018-08-29 18:32:21 +0000[diff] [blame]22
23void foo() {
24// CHECK: call void @__kmpc_spmd_kernel_init(i32 {{.+}}, i16 0, i16 0)
Alexey Bataeve8ad4b72018-11-26 18:37:09 +0000[diff] [blame]25// CHECK-DAG: [[DISTR_LIGHT]]
26// CHECK-DAG: [[FOR_LIGHT]]
27// CHECK-DAG: [[LIGHT]]
Alexey Bataev8d8e1232018-08-29 18:32:21 +0000[diff] [blame]28// CHECK: call void @__kmpc_spmd_kernel_init(i32 {{.+}}, i16 0, i16 0)
Alexey Bataeve8ad4b72018-11-26 18:37:09 +0000[diff] [blame]29// CHECK-DAG: [[DISTR_LIGHT]]
30// CHECK-DAG: [[FOR_LIGHT]]
31// CHECK-DAG: [[LIGHT]]
Alexey Bataev8d8e1232018-08-29 18:32:21 +0000[diff] [blame]32// CHECK: call void @__kmpc_spmd_kernel_init(i32 {{.+}}, i16 0, i16 0)
Alexey Bataeve8ad4b72018-11-26 18:37:09 +0000[diff] [blame]33// CHECK-DAG: [[DISTR_LIGHT]]
34// CHECK-DAG: [[FOR_LIGHT]]
35// CHECK-DAG: [[LIGHT]]
Alexey Bataev8d8e1232018-08-29 18:32:21 +0000[diff] [blame]36// CHECK: call void @__kmpc_spmd_kernel_init(i32 {{.+}}, i16 1, i16 {{.+}})
Alexey Bataeve8ad4b72018-11-26 18:37:09 +0000[diff] [blame]37// CHECK-DAG: [[DISTR_FULL]]
38// CHECK-DAG: [[FULL]]
Alexey Bataev8d8e1232018-08-29 18:32:21 +0000[diff] [blame]39// CHECK: call void @__kmpc_spmd_kernel_init(i32 {{.+}}, i16 1, i16 {{.+}})
Alexey Bataeve8ad4b72018-11-26 18:37:09 +0000[diff] [blame]40// CHECK-DAG: [[DISTR_FULL]]
41// CHECK-DAG: [[FULL]]
Alexey Bataev8d8e1232018-08-29 18:32:21 +0000[diff] [blame]42// CHECK: call void @__kmpc_spmd_kernel_init(i32 {{.+}}, i16 1, i16 {{.+}})
Alexey Bataeve8ad4b72018-11-26 18:37:09 +0000[diff] [blame]43// CHECK-DAG: [[DISTR_FULL]]
44// CHECK-DAG: [[FULL]]
Alexey Bataev8d8e1232018-08-29 18:32:21 +0000[diff] [blame]45// CHECK: call void @__kmpc_spmd_kernel_init(i32 {{.+}}, i16 1, i16 {{.+}})
Alexey Bataeve8ad4b72018-11-26 18:37:09 +0000[diff] [blame]46// CHECK-DAG: [[DISTR_FULL]]
47// CHECK-DAG: [[FULL]]
Alexey Bataev5e287932019-04-16 15:39:12 +0000[diff] [blame]48#pragma omp target teams distribute parallel for simd if(a)
Alexey Bataev8d8e1232018-08-29 18:32:21 +0000[diff] [blame]49 for (int i = 0; i < 10; ++i)
50 ;
51#pragma omp target teams distribute parallel for simd schedule(static)
52 for (int i = 0; i < 10; ++i)
53 ;
54#pragma omp target teams distribute parallel for simd schedule(static, 1)
55 for (int i = 0; i < 10; ++i)
56 ;
57#pragma omp target teams distribute parallel for simd schedule(auto)
58 for (int i = 0; i < 10; ++i)
59 ;
60#pragma omp target teams distribute parallel for simd schedule(runtime)
61 for (int i = 0; i < 10; ++i)
62 ;
63#pragma omp target teams distribute parallel for simd schedule(dynamic)
64 for (int i = 0; i < 10; ++i)
65 ;
66#pragma omp target teams distribute parallel for simd schedule(guided)
67 for (int i = 0; i < 10; ++i)
68 ;
69int a;
Alexey Bataev8bcc69c2018-11-09 20:03:19 +0000[diff] [blame]70// CHECK: call void @__kmpc_spmd_kernel_init(i32 {{.+}}, i16 0, i16 0)
Alexey Bataeve8ad4b72018-11-26 18:37:09 +0000[diff] [blame]71// CHECK-DAG: [[DISTR_LIGHT]]
72// CHECK-DAG: [[FOR_LIGHT]]
73// CHECK-DAG: [[LIGHT]]
Alexey Bataev8d8e1232018-08-29 18:32:21 +0000[diff] [blame]74// CHECK: call void @__kmpc_spmd_kernel_init(i32 {{.+}}, i16 0, i16 0)
Alexey Bataeve8ad4b72018-11-26 18:37:09 +0000[diff] [blame]75// CHECK-DAG: [[DISTR_LIGHT]]
76// CHECK-DAG: [[FOR_LIGHT]]
77// CHECK-DAG: [[LIGHT]]
Alexey Bataev8d8e1232018-08-29 18:32:21 +0000[diff] [blame]78// CHECK: call void @__kmpc_spmd_kernel_init(i32 {{.+}}, i16 0, i16 0)
Alexey Bataeve8ad4b72018-11-26 18:37:09 +0000[diff] [blame]79// CHECK-DAG: [[DISTR_LIGHT]]
80// CHECK-DAG: [[FOR_LIGHT]]
81// CHECK-DAG: [[LIGHT]]
Alexey Bataev8d8e1232018-08-29 18:32:21 +0000[diff] [blame]82// CHECK: call void @__kmpc_spmd_kernel_init(i32 {{.+}}, i16 1, i16 {{.+}})
Alexey Bataeve8ad4b72018-11-26 18:37:09 +0000[diff] [blame]83// CHECK-DAG: [[DISTR_FULL]]
84// CHECK-DAG: [[FULL]]
Alexey Bataev8d8e1232018-08-29 18:32:21 +0000[diff] [blame]85// CHECK: call void @__kmpc_spmd_kernel_init(i32 {{.+}}, i16 1, i16 {{.+}})
Alexey Bataeve8ad4b72018-11-26 18:37:09 +0000[diff] [blame]86// CHECK-DAG: [[DISTR_FULL]]
87// CHECK-DAG: [[FULL]]
Alexey Bataev8d8e1232018-08-29 18:32:21 +0000[diff] [blame]88// CHECK: call void @__kmpc_spmd_kernel_init(i32 {{.+}}, i16 1, i16 {{.+}})
Alexey Bataeve8ad4b72018-11-26 18:37:09 +0000[diff] [blame]89// CHECK-DAG: [[DISTR_FULL]]
90// CHECK-DAG: [[FULL]]
Alexey Bataev8d8e1232018-08-29 18:32:21 +0000[diff] [blame]91// CHECK: call void @__kmpc_spmd_kernel_init(i32 {{.+}}, i16 1, i16 {{.+}})
Alexey Bataeve8ad4b72018-11-26 18:37:09 +0000[diff] [blame]92// CHECK-DAG: [[DISTR_FULL]]
93// CHECK-DAG: [[FULL]]
Alexey Bataev8d8e1232018-08-29 18:32:21 +0000[diff] [blame]94#pragma omp target teams distribute parallel for lastprivate(a)
95 for (int i = 0; i < 10; ++i)
96 a = i;
97#pragma omp target teams distribute parallel for schedule(static)
98 for (int i = 0; i < 10; ++i)
99 ;
100#pragma omp target teams distribute parallel for schedule(static, 1)
101 for (int i = 0; i < 10; ++i)
102 ;
103#pragma omp target teams distribute parallel for schedule(auto)
104 for (int i = 0; i < 10; ++i)
105 ;
106#pragma omp target teams distribute parallel for schedule(runtime)
107 for (int i = 0; i < 10; ++i)
108 ;
109#pragma omp target teams distribute parallel for schedule(dynamic)
110 for (int i = 0; i < 10; ++i)
111 ;
112#pragma omp target teams distribute parallel for schedule(guided)
113 for (int i = 0; i < 10; ++i)
114 ;
115// CHECK: call void @__kmpc_spmd_kernel_init(i32 {{.+}}, i16 0, i16 0)
Alexey Bataeve8ad4b72018-11-26 18:37:09 +0000[diff] [blame]116// CHECK-DAG: [[DISTR_LIGHT]]
117// CHECK-DAG: [[FOR_LIGHT]]
118// CHECK-DAG: [[LIGHT]]
Alexey Bataev8d8e1232018-08-29 18:32:21 +0000[diff] [blame]119// CHECK: call void @__kmpc_spmd_kernel_init(i32 {{.+}}, i16 0, i16 0)
Alexey Bataeve8ad4b72018-11-26 18:37:09 +0000[diff] [blame]120// CHECK-DAG: [[DISTR_LIGHT]]
121// CHECK-DAG: [[FOR_LIGHT]]
122// CHECK-DAG: [[LIGHT]]
Alexey Bataev8d8e1232018-08-29 18:32:21 +0000[diff] [blame]123// CHECK: call void @__kmpc_spmd_kernel_init(i32 {{.+}}, i16 0, i16 0)
Alexey Bataeve8ad4b72018-11-26 18:37:09 +0000[diff] [blame]124// CHECK-DAG: [[DISTR_LIGHT]]
125// CHECK-DAG: [[FOR_LIGHT]]
126// CHECK-DAG: [[LIGHT]]
Alexey Bataev8d8e1232018-08-29 18:32:21 +0000[diff] [blame]127// CHECK: call void @__kmpc_spmd_kernel_init(i32 {{.+}}, i16 1, i16 {{.+}})
Alexey Bataeve8ad4b72018-11-26 18:37:09 +0000[diff] [blame]128// CHECK-DAG: [[DISTR_FULL]]
129// CHECK-DAG: [[FULL]]
Alexey Bataev8d8e1232018-08-29 18:32:21 +0000[diff] [blame]130// CHECK: call void @__kmpc_spmd_kernel_init(i32 {{.+}}, i16 1, i16 {{.+}})
Alexey Bataeve8ad4b72018-11-26 18:37:09 +0000[diff] [blame]131// CHECK-DAG: [[DISTR_FULL]]
132// CHECK-DAG: [[FULL]]
Alexey Bataev8d8e1232018-08-29 18:32:21 +0000[diff] [blame]133// CHECK: call void @__kmpc_spmd_kernel_init(i32 {{.+}}, i16 1, i16 {{.+}})
Alexey Bataeve8ad4b72018-11-26 18:37:09 +0000[diff] [blame]134// CHECK-DAG: [[DISTR_FULL]]
135// CHECK-DAG: [[FULL]]
Alexey Bataev8d8e1232018-08-29 18:32:21 +0000[diff] [blame]136// CHECK: call void @__kmpc_spmd_kernel_init(i32 {{.+}}, i16 1, i16 {{.+}})
Alexey Bataeve8ad4b72018-11-26 18:37:09 +0000[diff] [blame]137// CHECK-DAG: [[DISTR_FULL]]
138// CHECK-DAG: [[FULL]]
Alexey Bataev8d8e1232018-08-29 18:32:21 +0000[diff] [blame]139#pragma omp target teams
Alexey Bataev8bcc69c2018-11-09 20:03:19 +0000[diff] [blame]140 {
141 int b;
Alexey Bataev8d8e1232018-08-29 18:32:21 +0000[diff] [blame]142#pragma omp distribute parallel for simd
143 for (int i = 0; i < 10; ++i)
144 ;
Alexey Bataev8bcc69c2018-11-09 20:03:19 +0000[diff] [blame]145 ;
146 }
Alexey Bataev8d8e1232018-08-29 18:32:21 +0000[diff] [blame]147#pragma omp target teams
Alexey Bataev8bcc69c2018-11-09 20:03:19 +0000[diff] [blame]148 {
149 int b[] = {2, 3, sizeof(int)};
Alexey Bataev8d8e1232018-08-29 18:32:21 +0000[diff] [blame]150#pragma omp distribute parallel for simd schedule(static)
151 for (int i = 0; i < 10; ++i)
152 ;
Alexey Bataev8bcc69c2018-11-09 20:03:19 +0000[diff] [blame]153 }
Alexey Bataev8d8e1232018-08-29 18:32:21 +0000[diff] [blame]154#pragma omp target teams
Alexey Bataev8bcc69c2018-11-09 20:03:19 +0000[diff] [blame]155 {
156 int b;
Alexey Bataev8d8e1232018-08-29 18:32:21 +0000[diff] [blame]157#pragma omp distribute parallel for simd schedule(static, 1)
158 for (int i = 0; i < 10; ++i)
159 ;
Alexey Bataev8bcc69c2018-11-09 20:03:19 +0000[diff] [blame]160 int &c = b;
161 }
Alexey Bataev8d8e1232018-08-29 18:32:21 +0000[diff] [blame]162#pragma omp target teams
163#pragma omp distribute parallel for simd schedule(auto)
164 for (int i = 0; i < 10; ++i)
165 ;
166#pragma omp target teams
167#pragma omp distribute parallel for simd schedule(runtime)
168 for (int i = 0; i < 10; ++i)
169 ;
170#pragma omp target teams
171#pragma omp distribute parallel for simd schedule(dynamic)
172 for (int i = 0; i < 10; ++i)
173 ;
174#pragma omp target teams
175#pragma omp distribute parallel for simd schedule(guided)
176 for (int i = 0; i < 10; ++i)
177 ;
178// CHECK: call void @__kmpc_spmd_kernel_init(i32 {{.+}}, i16 0, i16 0)
Alexey Bataeve8ad4b72018-11-26 18:37:09 +0000[diff] [blame]179// CHECK-DAG: [[DISTR_LIGHT]]
180// CHECK-DAG: [[FOR_LIGHT]]
181// CHECK-DAG: [[LIGHT]]
Alexey Bataev8d8e1232018-08-29 18:32:21 +0000[diff] [blame]182// CHECK: call void @__kmpc_spmd_kernel_init(i32 {{.+}}, i16 0, i16 0)
Alexey Bataeve8ad4b72018-11-26 18:37:09 +0000[diff] [blame]183// CHECK-DAG: [[DISTR_LIGHT]]
184// CHECK-DAG: [[FOR_LIGHT]]
185// CHECK-DAG: [[LIGHT]]
Alexey Bataev8d8e1232018-08-29 18:32:21 +0000[diff] [blame]186// CHECK: call void @__kmpc_spmd_kernel_init(i32 {{.+}}, i16 0, i16 0)
Alexey Bataeve8ad4b72018-11-26 18:37:09 +0000[diff] [blame]187// CHECK-DAG: [[DISTR_LIGHT]]
188// CHECK-DAG: [[FOR_LIGHT]]
189// CHECK-DAG: [[LIGHT]]
Alexey Bataev8d8e1232018-08-29 18:32:21 +0000[diff] [blame]190// CHECK: call void @__kmpc_spmd_kernel_init(i32 {{.+}}, i16 1, i16 {{.+}})
Alexey Bataeve8ad4b72018-11-26 18:37:09 +0000[diff] [blame]191// CHECK-DAG: [[DISTR_FULL]]
192// CHECK-DAG: [[FULL]]
Alexey Bataev8d8e1232018-08-29 18:32:21 +0000[diff] [blame]193// CHECK: call void @__kmpc_spmd_kernel_init(i32 {{.+}}, i16 1, i16 {{.+}})
Alexey Bataeve8ad4b72018-11-26 18:37:09 +0000[diff] [blame]194// CHECK-DAG: [[DISTR_FULL]]
195// CHECK-DAG: [[FULL]]
Alexey Bataev8d8e1232018-08-29 18:32:21 +0000[diff] [blame]196// CHECK: call void @__kmpc_spmd_kernel_init(i32 {{.+}}, i16 1, i16 {{.+}})
Alexey Bataeve8ad4b72018-11-26 18:37:09 +0000[diff] [blame]197// CHECK-DAG: [[DISTR_FULL]]
198// CHECK-DAG: [[FULL]]
Alexey Bataev8d8e1232018-08-29 18:32:21 +0000[diff] [blame]199// CHECK: call void @__kmpc_spmd_kernel_init(i32 {{.+}}, i16 1, i16 {{.+}})
Alexey Bataeve8ad4b72018-11-26 18:37:09 +0000[diff] [blame]200// CHECK-DAG: [[DISTR_FULL]]
201// CHECK-DAG: [[FULL]]
Alexey Bataev8d8e1232018-08-29 18:32:21 +0000[diff] [blame]202#pragma omp target teams
203#pragma omp distribute parallel for
204 for (int i = 0; i < 10; ++i)
205 ;
206#pragma omp target teams
207#pragma omp distribute parallel for schedule(static)
208 for (int i = 0; i < 10; ++i)
209 ;
210#pragma omp target teams
211#pragma omp distribute parallel for schedule(static, 1)
212 for (int i = 0; i < 10; ++i)
213 ;
214#pragma omp target teams
215#pragma omp distribute parallel for schedule(auto)
216 for (int i = 0; i < 10; ++i)
217 ;
218#pragma omp target teams
219#pragma omp distribute parallel for schedule(runtime)
220 for (int i = 0; i < 10; ++i)
221 ;
222#pragma omp target teams
223#pragma omp distribute parallel for schedule(dynamic)
224 for (int i = 0; i < 10; ++i)
225 ;
226#pragma omp target teams
227#pragma omp distribute parallel for schedule(guided)
228 for (int i = 0; i < 10; ++i)
229 ;
230// CHECK: call void @__kmpc_spmd_kernel_init(i32 {{.+}}, i16 0, i16 0)
Alexey Bataeve8ad4b72018-11-26 18:37:09 +0000[diff] [blame]231// CHECK-DAG: [[DISTR_LIGHT]]
232// CHECK-DAG: [[FOR_LIGHT]]
233// CHECK-DAG: [[LIGHT]]
Alexey Bataev8d8e1232018-08-29 18:32:21 +0000[diff] [blame]234// CHECK: call void @__kmpc_spmd_kernel_init(i32 {{.+}}, i16 0, i16 0)
Alexey Bataeve8ad4b72018-11-26 18:37:09 +0000[diff] [blame]235// CHECK-DAG: [[DISTR_LIGHT]]
236// CHECK-DAG: [[FOR_LIGHT]]
237// CHECK-DAG: [[LIGHT]]
Alexey Bataev8d8e1232018-08-29 18:32:21 +0000[diff] [blame]238// CHECK: call void @__kmpc_spmd_kernel_init(i32 {{.+}}, i16 0, i16 0)
Alexey Bataeve8ad4b72018-11-26 18:37:09 +0000[diff] [blame]239// CHECK-DAG: [[DISTR_LIGHT]]
240// CHECK-DAG: [[FOR_LIGHT]]
241// CHECK-DAG: [[LIGHT]]
Alexey Bataev8d8e1232018-08-29 18:32:21 +0000[diff] [blame]242// CHECK: call void @__kmpc_spmd_kernel_init(i32 {{.+}}, i16 1, i16 {{.+}})
Alexey Bataeve8ad4b72018-11-26 18:37:09 +0000[diff] [blame]243// CHECK-DAG: [[DISTR_FULL]]
244// CHECK-DAG: [[FULL]]
Alexey Bataev8d8e1232018-08-29 18:32:21 +0000[diff] [blame]245// CHECK: call void @__kmpc_spmd_kernel_init(i32 {{.+}}, i16 1, i16 {{.+}})
Alexey Bataeve8ad4b72018-11-26 18:37:09 +0000[diff] [blame]246// CHECK-DAG: [[DISTR_FULL]]
247// CHECK-DAG: [[FULL]]
Alexey Bataev8d8e1232018-08-29 18:32:21 +0000[diff] [blame]248// CHECK: call void @__kmpc_spmd_kernel_init(i32 {{.+}}, i16 1, i16 {{.+}})
Alexey Bataeve8ad4b72018-11-26 18:37:09 +0000[diff] [blame]249// CHECK-DAG: [[DISTR_FULL]]
250// CHECK-DAG: [[FULL]]
Alexey Bataev8d8e1232018-08-29 18:32:21 +0000[diff] [blame]251// CHECK: call void @__kmpc_spmd_kernel_init(i32 {{.+}}, i16 1, i16 {{.+}})
Alexey Bataeve8ad4b72018-11-26 18:37:09 +0000[diff] [blame]252// CHECK-DAG: [[DISTR_FULL]]
253// CHECK-DAG: [[FULL]]
Alexey Bataev8d8e1232018-08-29 18:32:21 +0000[diff] [blame]254#pragma omp target
255#pragma omp teams
256#pragma omp distribute parallel for
257 for (int i = 0; i < 10; ++i)
258 ;
259#pragma omp target
260#pragma omp teams
261#pragma omp distribute parallel for schedule(static)
262 for (int i = 0; i < 10; ++i)
263 ;
264#pragma omp target
265#pragma omp teams
266#pragma omp distribute parallel for schedule(static, 1)
267 for (int i = 0; i < 10; ++i)
268 ;
269#pragma omp target
270#pragma omp teams
271#pragma omp distribute parallel for schedule(auto)
272 for (int i = 0; i < 10; ++i)
273 ;
274#pragma omp target
275#pragma omp teams
276#pragma omp distribute parallel for schedule(runtime)
277 for (int i = 0; i < 10; ++i)
278 ;
279#pragma omp target
280#pragma omp teams
281#pragma omp distribute parallel for schedule(dynamic)
282 for (int i = 0; i < 10; ++i)
283 ;
284#pragma omp target
285#pragma omp teams
286#pragma omp distribute parallel for schedule(guided)
287 for (int i = 0; i < 10; ++i)
288 ;
289// CHECK: call void @__kmpc_spmd_kernel_init(i32 {{.+}}, i16 0, i16 0)
Alexey Bataeve8ad4b72018-11-26 18:37:09 +0000[diff] [blame]290// CHECK-DAG: [[FOR_LIGHT]]
291// CHECK-DAG: [[LIGHT]]
Alexey Bataev8d8e1232018-08-29 18:32:21 +0000[diff] [blame]292// CHECK: call void @__kmpc_spmd_kernel_init(i32 {{.+}}, i16 0, i16 0)
Alexey Bataeve8ad4b72018-11-26 18:37:09 +0000[diff] [blame]293// CHECK-DAG: [[FOR_LIGHT]]
294// CHECK-DAG: [[LIGHT]]
Alexey Bataev8d8e1232018-08-29 18:32:21 +0000[diff] [blame]295// CHECK: call void @__kmpc_spmd_kernel_init(i32 {{.+}}, i16 0, i16 0)
Alexey Bataeve8ad4b72018-11-26 18:37:09 +0000[diff] [blame]296// CHECK-DAG: [[FOR_LIGHT]]
297// CHECK-DAG: [[LIGHT]]
Alexey Bataev8d8e1232018-08-29 18:32:21 +0000[diff] [blame]298// CHECK: call void @__kmpc_spmd_kernel_init(i32 {{.+}}, i16 1, i16 {{.+}})
Alexey Bataeve8ad4b72018-11-26 18:37:09 +0000[diff] [blame]299// CHECK-DAG: [[FULL]]
Alexey Bataev8d8e1232018-08-29 18:32:21 +0000[diff] [blame]300// CHECK: call void @__kmpc_spmd_kernel_init(i32 {{.+}}, i16 1, i16 {{.+}})
Alexey Bataeve8ad4b72018-11-26 18:37:09 +0000[diff] [blame]301// CHECK-DAG: [[FULL]]
Alexey Bataev8d8e1232018-08-29 18:32:21 +0000[diff] [blame]302// CHECK: call void @__kmpc_spmd_kernel_init(i32 {{.+}}, i16 1, i16 {{.+}})
Alexey Bataeve8ad4b72018-11-26 18:37:09 +0000[diff] [blame]303// CHECK-DAG: [[FULL]]
Alexey Bataev8d8e1232018-08-29 18:32:21 +0000[diff] [blame]304// CHECK: call void @__kmpc_spmd_kernel_init(i32 {{.+}}, i16 1, i16 {{.+}})
Alexey Bataeve8ad4b72018-11-26 18:37:09 +0000[diff] [blame]305// CHECK-DAG: [[FULL]]
Alexey Bataev5e287932019-04-16 15:39:12 +0000[diff] [blame]306#pragma omp target parallel for if(a)
Alexey Bataev8d8e1232018-08-29 18:32:21 +0000[diff] [blame]307 for (int i = 0; i < 10; ++i)
308 ;
309#pragma omp target parallel for schedule(static)
310 for (int i = 0; i < 10; ++i)
311 ;
312#pragma omp target parallel for schedule(static, 1)
313 for (int i = 0; i < 10; ++i)
314 ;
315#pragma omp target parallel for schedule(auto)
316 for (int i = 0; i < 10; ++i)
317 ;
318#pragma omp target parallel for schedule(runtime)
319 for (int i = 0; i < 10; ++i)
320 ;
321#pragma omp target parallel for schedule(dynamic)
322 for (int i = 0; i < 10; ++i)
323 ;
324#pragma omp target parallel for schedule(guided)
325 for (int i = 0; i < 10; ++i)
326 ;
327// CHECK: call void @__kmpc_spmd_kernel_init(i32 {{.+}}, i16 0, i16 0)
Alexey Bataeve8ad4b72018-11-26 18:37:09 +0000[diff] [blame]328// CHECK-DAG: [[FOR_LIGHT]]
329// CHECK-DAG: [[LIGHT]]
330// CHECK-DAG: [[BAR_LIGHT]]
Alexey Bataev8d8e1232018-08-29 18:32:21 +0000[diff] [blame]331// CHECK: call void @__kmpc_spmd_kernel_init(i32 {{.+}}, i16 0, i16 0)
Alexey Bataeve8ad4b72018-11-26 18:37:09 +0000[diff] [blame]332// CHECK-DAG: [[FOR_LIGHT]]
333// CHECK-DAG: [[LIGHT]]
334// CHECK-DAG: [[BAR_LIGHT]]
Alexey Bataev8d8e1232018-08-29 18:32:21 +0000[diff] [blame]335// CHECK: call void @__kmpc_spmd_kernel_init(i32 {{.+}}, i16 0, i16 0)
Alexey Bataeve8ad4b72018-11-26 18:37:09 +0000[diff] [blame]336// CHECK-DAG: [[FOR_LIGHT]]
337// CHECK-DAG: [[LIGHT]]
338// CHECK-DAG: [[BAR_LIGHT]]
Alexey Bataev8d8e1232018-08-29 18:32:21 +0000[diff] [blame]339// CHECK: call void @__kmpc_spmd_kernel_init(i32 {{.+}}, i16 1, i16 {{.+}})
Alexey Bataeve8ad4b72018-11-26 18:37:09 +0000[diff] [blame]340// CHECK-DAG: [[FULL]]
341// CHECK-DAG: [[BAR_FULL]]
Alexey Bataev8d8e1232018-08-29 18:32:21 +0000[diff] [blame]342// CHECK: call void @__kmpc_spmd_kernel_init(i32 {{.+}}, i16 1, i16 {{.+}})
Alexey Bataeve8ad4b72018-11-26 18:37:09 +0000[diff] [blame]343// CHECK-DAG: [[FULL]]
344// CHECK-DAG: [[BAR_FULL]]
Alexey Bataev8d8e1232018-08-29 18:32:21 +0000[diff] [blame]345// CHECK: call void @__kmpc_spmd_kernel_init(i32 {{.+}}, i16 1, i16 {{.+}})
Alexey Bataeve8ad4b72018-11-26 18:37:09 +0000[diff] [blame]346// CHECK-DAG: [[FULL]]
347// CHECK-DAG: [[BAR_FULL]]
Alexey Bataev8d8e1232018-08-29 18:32:21 +0000[diff] [blame]348// CHECK: call void @__kmpc_spmd_kernel_init(i32 {{.+}}, i16 1, i16 {{.+}})
Alexey Bataeve8ad4b72018-11-26 18:37:09 +0000[diff] [blame]349// CHECK-DAG: [[FULL]]
350// CHECK-DAG: [[BAR_FULL]]
Alexey Bataev5e287932019-04-16 15:39:12 +0000[diff] [blame]351#pragma omp target parallel if(a)
Alexey Bataev8d8e1232018-08-29 18:32:21 +0000[diff] [blame]352#pragma omp for simd
353 for (int i = 0; i < 10; ++i)
354 ;
355#pragma omp target parallel
356#pragma omp for simd schedule(static)
357 for (int i = 0; i < 10; ++i)
358 ;
359#pragma omp target parallel
360#pragma omp for simd schedule(static, 1)
361 for (int i = 0; i < 10; ++i)
362 ;
363#pragma omp target parallel
364#pragma omp for simd schedule(auto)
365 for (int i = 0; i < 10; ++i)
366 ;
367#pragma omp target parallel
368#pragma omp for simd schedule(runtime)
369 for (int i = 0; i < 10; ++i)
370 ;
371#pragma omp target parallel
372#pragma omp for simd schedule(dynamic)
373 for (int i = 0; i < 10; ++i)
374 ;
375#pragma omp target parallel
376#pragma omp for simd schedule(guided)
377 for (int i = 0; i < 10; ++i)
378 ;
379// CHECK: call void @__kmpc_spmd_kernel_init(i32 {{.+}}, i16 1, i16 {{.+}})
Alexey Bataeve8ad4b72018-11-26 18:37:09 +0000[diff] [blame]380// CHECK-DAG: [[FULL]]
381// CHECK-DAG: [[BAR_FULL]]
Alexey Bataev8d8e1232018-08-29 18:32:21 +0000[diff] [blame]382// CHECK: call void @__kmpc_spmd_kernel_init(i32 {{.+}}, i16 0, i16 0)
Alexey Bataeve8ad4b72018-11-26 18:37:09 +0000[diff] [blame]383// CHECK-DAG: [[FOR_LIGHT]]
384// CHECK-DAG: [[LIGHT]]
385// CHECK-DAG: [[BAR_LIGHT]]
Alexey Bataev8d8e1232018-08-29 18:32:21 +0000[diff] [blame]386// CHECK: call void @__kmpc_spmd_kernel_init(i32 {{.+}}, i16 0, i16 0)
Alexey Bataeve8ad4b72018-11-26 18:37:09 +0000[diff] [blame]387// CHECK-DAG: [[FOR_LIGHT]]
388// CHECK-DAG: [[LIGHT]]
389// CHECK-DAG: [[BAR_LIGHT]]
Alexey Bataev8d8e1232018-08-29 18:32:21 +0000[diff] [blame]390// CHECK: call void @__kmpc_spmd_kernel_init(i32 {{.+}}, i16 1, i16 {{.+}})
Alexey Bataeve8ad4b72018-11-26 18:37:09 +0000[diff] [blame]391// CHECK-DAG: [[FULL]]
392// CHECK-DAG: [[BAR_FULL]]
Alexey Bataev8d8e1232018-08-29 18:32:21 +0000[diff] [blame]393// CHECK: call void @__kmpc_spmd_kernel_init(i32 {{.+}}, i16 1, i16 {{.+}})
Alexey Bataeve8ad4b72018-11-26 18:37:09 +0000[diff] [blame]394// CHECK-DAG: [[FULL]]
395// CHECK-DAG: [[BAR_FULL]]
Alexey Bataev8d8e1232018-08-29 18:32:21 +0000[diff] [blame]396// CHECK: call void @__kmpc_spmd_kernel_init(i32 {{.+}}, i16 1, i16 {{.+}})
Alexey Bataeve8ad4b72018-11-26 18:37:09 +0000[diff] [blame]397// CHECK-DAG: [[FULL]]
398// CHECK-DAG: [[BAR_FULL]]
Alexey Bataev8d8e1232018-08-29 18:32:21 +0000[diff] [blame]399// CHECK: call void @__kmpc_spmd_kernel_init(i32 {{.+}}, i16 1, i16 {{.+}})
Alexey Bataeve8ad4b72018-11-26 18:37:09 +0000[diff] [blame]400// CHECK-DAG: [[FULL]]
401// CHECK-DAG: [[BAR_FULL]]
Alexey Bataev8d8e1232018-08-29 18:32:21 +0000[diff] [blame]402#pragma omp target
403#pragma omp parallel
404#pragma omp for simd ordered
405 for (int i = 0; i < 10; ++i)
406 ;
407#pragma omp target
408#pragma omp parallel
409#pragma omp for simd schedule(static)
410 for (int i = 0; i < 10; ++i)
411 ;
412#pragma omp target
413#pragma omp parallel
414#pragma omp for simd schedule(static, 1)
415 for (int i = 0; i < 10; ++i)
416 ;
417#pragma omp target
418#pragma omp parallel
419#pragma omp for simd schedule(auto)
420 for (int i = 0; i < 10; ++i)
421 ;
422#pragma omp target
423#pragma omp parallel
424#pragma omp for simd schedule(runtime)
425 for (int i = 0; i < 10; ++i)
426 ;
427#pragma omp target
428#pragma omp parallel
429#pragma omp for simd schedule(dynamic)
430 for (int i = 0; i < 10; ++i)
431 ;
432#pragma omp target
433#pragma omp parallel
434#pragma omp for simd schedule(guided)
435 for (int i = 0; i < 10; ++i)
436 ;
437// CHECK: call void @__kmpc_spmd_kernel_init(i32 {{.+}}, i16 0, i16 0)
Alexey Bataeve8ad4b72018-11-26 18:37:09 +0000[diff] [blame]438// CHECK-DAG: [[FOR_LIGHT]]
439// CHECK-DAG: [[LIGHT]]
Alexey Bataev8d8e1232018-08-29 18:32:21 +0000[diff] [blame]440// CHECK: call void @__kmpc_spmd_kernel_init(i32 {{.+}}, i16 0, i16 0)
Alexey Bataeve8ad4b72018-11-26 18:37:09 +0000[diff] [blame]441// CHECK-DAG: [[FOR_LIGHT]]
442// CHECK-DAG: [[LIGHT]]
Alexey Bataev8d8e1232018-08-29 18:32:21 +0000[diff] [blame]443// CHECK: call void @__kmpc_spmd_kernel_init(i32 {{.+}}, i16 0, i16 0)
Alexey Bataeve8ad4b72018-11-26 18:37:09 +0000[diff] [blame]444// CHECK-DAG: [[FOR_LIGHT]]
445// CHECK-DAG: [[LIGHT]]
Alexey Bataev8d8e1232018-08-29 18:32:21 +0000[diff] [blame]446// CHECK: call void @__kmpc_spmd_kernel_init(i32 {{.+}}, i16 1, i16 {{.+}})
Alexey Bataeve8ad4b72018-11-26 18:37:09 +0000[diff] [blame]447// CHECK-DAG: [[FULL]]
Alexey Bataev8d8e1232018-08-29 18:32:21 +0000[diff] [blame]448// CHECK: call void @__kmpc_spmd_kernel_init(i32 {{.+}}, i16 1, i16 {{.+}})
Alexey Bataeve8ad4b72018-11-26 18:37:09 +0000[diff] [blame]449// CHECK-DAG: [[FULL]]
Alexey Bataev8d8e1232018-08-29 18:32:21 +0000[diff] [blame]450// CHECK: call void @__kmpc_spmd_kernel_init(i32 {{.+}}, i16 1, i16 {{.+}})
Alexey Bataeve8ad4b72018-11-26 18:37:09 +0000[diff] [blame]451// CHECK-DAG: [[FULL]]
Alexey Bataev8d8e1232018-08-29 18:32:21 +0000[diff] [blame]452// CHECK: call void @__kmpc_spmd_kernel_init(i32 {{.+}}, i16 1, i16 {{.+}})
Alexey Bataeve8ad4b72018-11-26 18:37:09 +0000[diff] [blame]453// CHECK-DAG: [[FULL]]
Alexey Bataev8d8e1232018-08-29 18:32:21 +0000[diff] [blame]454#pragma omp target
455#pragma omp parallel for
456 for (int i = 0; i < 10; ++i)
457 ;
458#pragma omp target
459#pragma omp parallel for schedule(static)
460 for (int i = 0; i < 10; ++i)
461 ;
462#pragma omp target
463#pragma omp parallel for schedule(static, 1)
464 for (int i = 0; i < 10; ++i)
465 ;
466#pragma omp target
467#pragma omp parallel for schedule(auto)
468 for (int i = 0; i < 10; ++i)
469 ;
470#pragma omp target
471#pragma omp parallel for schedule(runtime)
472 for (int i = 0; i < 10; ++i)
473 ;
474#pragma omp target
475#pragma omp parallel for schedule(dynamic)
476 for (int i = 0; i < 10; ++i)
477 ;
478#pragma omp target
479#pragma omp parallel for schedule(guided)
480 for (int i = 0; i < 10; ++i)
481 ;
482}
483
484#endif
485