blob: e42776c740b55cc23efc8b64c116e1d3d1acaa6a [file] [log] [blame]
Alexey Bataevdb390212015-05-20 04:24:19 +00001// RUN: %clang_cc1 -verify -fopenmp -x c++ -triple x86_64-apple-darwin10 -emit-llvm %s -o - | FileCheck %s
2// RUN: %clang_cc1 -fopenmp -x c++ -std=c++11 -triple x86_64-apple-darwin10 -emit-pch -o %t %s
3// RUN: %clang_cc1 -fopenmp -x c++ -triple x86_64-apple-darwin10 -std=c++11 -include-pch %t -verify %s -emit-llvm -o - | FileCheck %s
4// RUN: %clang_cc1 -verify -fopenmp -x c++ -std=c++11 -DLAMBDA -triple x86_64-apple-darwin10 -emit-llvm %s -o - | FileCheck -check-prefix=LAMBDA %s
5// RUN: %clang_cc1 -verify -fopenmp -x c++ -fblocks -DBLOCKS -triple x86_64-apple-darwin10 -emit-llvm %s -o - | FileCheck -check-prefix=BLOCKS %s
Alexey Bataev794ba0d2015-04-10 10:43:45 +00006// expected-no-diagnostics
7#ifndef HEADER
8#define HEADER
9
Alexey Bataev1d7f0fa2015-09-10 09:48:30 +000010volatile int g __attribute__((aligned(128))) = 1212;
Alexey Bataev794ba0d2015-04-10 10:43:45 +000011
12template <class T>
13struct S {
14 T f;
15 S(T a) : f(a + g) {}
16 S() : f(g) {}
17 operator T() { return T(); }
18 S &operator&(const S &) { return *this; }
19 ~S() {}
20};
21
Alexey Bataev61205072016-03-02 04:57:40 +000022struct SS {
23 int a;
24 int b : 4;
25 int &c;
26 SS(int &d) : a(0), b(0), c(d) {
27#pragma omp parallel reduction(+: a, b, c)
28#ifdef LAMBDA
29 [&]() {
30 ++this->a, --b, (this)->c /= 1;
31#pragma omp parallel reduction(&: a, b, c)
32 ++(this)->a, --b, this->c /= 1;
33 }();
34#elif defined(BLOCKS)
35 ^{
36 ++a;
37 --this->b;
38 (this)->c /= 1;
39#pragma omp parallel reduction(-: a, b, c)
40 ++(this)->a, --b, this->c /= 1;
41 }();
42#else
43 ++this->a, --b, c /= 1;
44#endif
45 }
46};
47
48template<typename T>
49struct SST {
50 T a;
51 SST() : a(T()) {
52#pragma omp parallel reduction(*: a)
53#ifdef LAMBDA
54 [&]() {
55 [&]() {
56 ++this->a;
57#pragma omp parallel reduction(&& :a)
58 ++(this)->a;
59 }();
60 }();
61#elif defined(BLOCKS)
62 ^{
63 ^{
64 ++a;
65#pragma omp parallel reduction(|: a)
66 ++(this)->a;
67 }();
68 }();
69#else
70 ++(this)->a;
71#endif
72 }
73};
74
75// CHECK: [[SS_TY:%.+]] = type { i{{[0-9]+}}, i8
76// LAMBDA: [[SS_TY:%.+]] = type { i{{[0-9]+}}, i8
77// BLOCKS: [[SS_TY:%.+]] = type { i{{[0-9]+}}, i8
Alexey Bataev794ba0d2015-04-10 10:43:45 +000078// CHECK-DAG: [[S_FLOAT_TY:%.+]] = type { float }
79// CHECK-DAG: [[S_INT_TY:%.+]] = type { i{{[0-9]+}} }
Alexey Bataev794ba0d2015-04-10 10:43:45 +000080// CHECK-DAG: [[REDUCTION_LOC:@.+]] = private unnamed_addr constant %{{.+}} { i32 0, i32 18, i32 0, i32 0, i8*
81// CHECK-DAG: [[REDUCTION_LOCK:@.+]] = common global [8 x i32] zeroinitializer
82
83template <typename T>
84T tmain() {
85 T t;
86 S<T> test;
Alexey Bataev61205072016-03-02 04:57:40 +000087 SST<T> sst;
Alexey Bataev1d7f0fa2015-09-10 09:48:30 +000088 T t_var __attribute__((aligned(128))) = T(), t_var1 __attribute__((aligned(128)));
Alexey Bataev794ba0d2015-04-10 10:43:45 +000089 T vec[] = {1, 2};
Alexey Bataev1d7f0fa2015-09-10 09:48:30 +000090 S<T> s_arr[] = {1, 2};
91 S<T> var __attribute__((aligned(128))) (3), var1 __attribute__((aligned(128)));
Alexey Bataev794ba0d2015-04-10 10:43:45 +000092#pragma omp parallel reduction(+:t_var) reduction(&:var) reduction(&& : var1) reduction(min: t_var1)
93 {
94 vec[0] = t_var;
95 s_arr[0] = var;
96 }
97 return T();
98}
99
Alexey Bataev61205072016-03-02 04:57:40 +0000100int sivar;
Alexey Bataev794ba0d2015-04-10 10:43:45 +0000101int main() {
Alexey Bataev61205072016-03-02 04:57:40 +0000102 SS ss(sivar);
Alexey Bataev794ba0d2015-04-10 10:43:45 +0000103#ifdef LAMBDA
104 // LAMBDA: [[G:@.+]] = global i{{[0-9]+}} 1212,
105 // LAMBDA-LABEL: @main
Alexey Bataev61205072016-03-02 04:57:40 +0000106 // LAMBDA: alloca [[SS_TY]],
107 // LAMBDA: alloca [[CAP_TY:%.+]],
108 // LAMBDA: call{{.*}} void [[OUTER_LAMBDA:@[^(]+]]([[CAP_TY]]*
Alexey Bataev794ba0d2015-04-10 10:43:45 +0000109 [&]() {
110 // LAMBDA: define{{.*}} internal{{.*}} void [[OUTER_LAMBDA]](
Alexey Bataev2377fe92015-09-10 08:12:02 +0000111 // LAMBDA: call void {{.+}} @__kmpc_fork_call({{.+}}, i32 1, {{.+}}* [[OMP_REGION:@.+]] to {{.+}}, i32* [[G]])
Alexey Bataev794ba0d2015-04-10 10:43:45 +0000112#pragma omp parallel reduction(+:g)
113 {
Alexey Bataev61205072016-03-02 04:57:40 +0000114 // LAMBDA: define {{.+}} @{{.+}}([[SS_TY]]*
115 // LAMBDA: getelementptr inbounds [[SS_TY]], [[SS_TY]]* %{{.+}}, i32 0, i32 0
116 // LAMBDA: store i{{[0-9]+}} 0, i{{[0-9]+}}* %
117 // LAMBDA: getelementptr inbounds [[SS_TY]], [[SS_TY]]* %{{.+}}, i32 0, i32 1
118 // LAMBDA: store i8
119 // LAMBDA: getelementptr inbounds [[SS_TY]], [[SS_TY]]* %{{.+}}, i32 0, i32 2
120 // LAMBDA: getelementptr inbounds [[SS_TY]], [[SS_TY]]* %{{.+}}, i32 0, i32 0
121 // LAMBDA-NOT: getelementptr inbounds [[SS_TY]], [[SS_TY]]* %{{.+}}, i32 0, i32 1
122 // LAMBDA: getelementptr inbounds [[SS_TY]], [[SS_TY]]* %{{.+}}, i32 0, i32 2
123 // LAMBDA: call void (%{{.+}}*, i{{[0-9]+}}, void (i{{[0-9]+}}*, i{{[0-9]+}}*, ...)*, ...) @__kmpc_fork_call(%{{.+}}* @{{.+}}, i{{[0-9]+}} 4, void (i{{[0-9]+}}*, i{{[0-9]+}}*, ...)* bitcast (void (i{{[0-9]+}}*, i{{[0-9]+}}*, [[SS_TY]]*, i32*, i32*, i32*)* [[SS_MICROTASK:@.+]] to void
124 // LAMBDA: [[B_REF:%.+]] = getelementptr {{.*}}[[SS_TY]], [[SS_TY]]* %{{.*}}, i32 0, i32 1
125 // LAMBDA: store i8 %{{.+}}, i8* [[B_REF]],
126 // LAMBDA: ret
127
128 // LAMBDA: define internal void [[SS_MICROTASK]](i{{[0-9]+}}* noalias [[GTID_ADDR:%.+]], i{{[0-9]+}}* noalias %{{.+}}, [[SS_TY]]* %{{.+}}, i32* {{.+}}, i32* {{.+}}, i32* {{.+}})
129 // LAMBDA-NOT: getelementptr {{.*}}[[SS_TY]], [[SS_TY]]* %
130 // LAMBDA: call{{.*}} void
131 // LAMBDA: ret void
132
133 // LAMBDA: define internal void @{{.+}}(i{{[0-9]+}}* noalias [[GTID_ADDR:%.+]], i{{[0-9]+}}* noalias %{{.+}}, [[SS_TY]]*
134 // LAMBDA: [[A_PRIV:%.+]] = alloca i{{[0-9]+}},
135 // LAMBDA: [[B_PRIV:%.+]] = alloca i{{[0-9]+}},
136 // LAMBDA: [[C_PRIV:%.+]] = alloca i{{[0-9]+}},
137 // LAMBDA: store i{{[0-9]+}} -1, i{{[0-9]+}}* [[A_PRIV]],
138 // LAMBDA: store i{{[0-9]+}}* [[A_PRIV]], i{{[0-9]+}}** [[REFA:%.+]],
139 // LAMBDA: store i{{[0-9]+}} -1, i{{[0-9]+}}* [[B_PRIV]],
140 // LAMBDA: store i{{[0-9]+}} -1, i{{[0-9]+}}* [[C_PRIV]],
141 // LAMBDA: store i{{[0-9]+}}* [[C_PRIV]], i{{[0-9]+}}** [[REFC:%.+]],
142 // LAMBDA: [[A_PRIV:%.+]] = load i{{[0-9]+}}*, i{{[0-9]+}}** [[REFA]],
143 // LAMBDA-NEXT: [[A_VAL:%.+]] = load i{{[0-9]+}}, i{{[0-9]+}}* [[A_PRIV]],
144 // LAMBDA-NEXT: [[INC:%.+]] = add nsw i{{[0-9]+}} [[A_VAL]], 1
145 // LAMBDA-NEXT: store i{{[0-9]+}} [[INC]], i{{[0-9]+}}* [[A_PRIV]],
146 // LAMBDA-NEXT: [[B_VAL:%.+]] = load i{{[0-9]+}}, i{{[0-9]+}}* [[B_PRIV]],
147 // LAMBDA-NEXT: [[DEC:%.+]] = add nsw i{{[0-9]+}} [[B_VAL]], -1
148 // LAMBDA-NEXT: store i{{[0-9]+}} [[DEC]], i{{[0-9]+}}* [[B_PRIV]],
149 // LAMBDA-NEXT: [[C_PRIV:%.+]] = load i{{[0-9]+}}*, i{{[0-9]+}}** [[REFC]],
150 // LAMBDA-NEXT: [[C_VAL:%.+]] = load i{{[0-9]+}}, i{{[0-9]+}}* [[C_PRIV]],
151 // LAMBDA-NEXT: [[DIV:%.+]] = sdiv i{{[0-9]+}} [[C_VAL]], 1
152 // LAMBDA-NEXT: store i{{[0-9]+}} [[DIV]], i{{[0-9]+}}* [[C_PRIV]],
153 // LAMBDA: call i32 @__kmpc_reduce_nowait(
154 // LAMBDA: ret void
155
Alexey Bataev2377fe92015-09-10 08:12:02 +0000156 // LAMBDA: define{{.*}} internal{{.*}} void [[OMP_REGION]](i32* noalias %{{.+}}, i32* noalias %{{.+}}, i32* dereferenceable(4) %{{.+}})
Alexey Bataev794ba0d2015-04-10 10:43:45 +0000157 // LAMBDA: [[G_PRIVATE_ADDR:%.+]] = alloca i{{[0-9]+}},
158
159 // Reduction list for runtime.
160 // LAMBDA: [[RED_LIST:%.+]] = alloca [1 x i8*],
161
Alexey Bataev2377fe92015-09-10 08:12:02 +0000162 // LAMBDA: [[G_REF:%.+]] = load i{{[0-9]+}}*, i{{[0-9]+}}** [[G_REF_ADDR:%.+]]
Alexey Bataev1d7f0fa2015-09-10 09:48:30 +0000163 // LAMBDA: store i{{[0-9]+}} 0, i{{[0-9]+}}* [[G_PRIVATE_ADDR]], align 128
Alexey Bataev794ba0d2015-04-10 10:43:45 +0000164 g = 1;
Alexey Bataev1d7f0fa2015-09-10 09:48:30 +0000165 // LAMBDA: store i{{[0-9]+}} 1, i{{[0-9]+}}* [[G_PRIVATE_ADDR]], align 128
Alexey Bataev794ba0d2015-04-10 10:43:45 +0000166 // LAMBDA: [[G_PRIVATE_ADDR_REF:%.+]] = getelementptr inbounds %{{.+}}, %{{.+}}* [[ARG:%.+]], i{{[0-9]+}} 0, i{{[0-9]+}} 0
167 // LAMBDA: store i{{[0-9]+}}* [[G_PRIVATE_ADDR]], i{{[0-9]+}}** [[G_PRIVATE_ADDR_REF]]
168 // LAMBDA: call void [[INNER_LAMBDA:@.+]](%{{.+}}* [[ARG]])
169
John McCall7f416cc2015-09-08 08:05:57 +0000170 // LAMBDA: [[G_PRIV_REF:%.+]] = getelementptr inbounds [1 x i8*], [1 x i8*]* [[RED_LIST]], i64 0, i64 0
Alexey Bataev794ba0d2015-04-10 10:43:45 +0000171 // LAMBDA: [[BITCAST:%.+]] = bitcast i32* [[G_PRIVATE_ADDR]] to i8*
172 // LAMBDA: store i8* [[BITCAST]], i8** [[G_PRIV_REF]],
173 // LAMBDA: call i32 @__kmpc_reduce_nowait(
174 // LAMBDA: switch i32 %{{.+}}, label %[[REDUCTION_DONE:.+]] [
175 // LAMBDA: i32 1, label %[[CASE1:.+]]
176 // LAMBDA: i32 2, label %[[CASE2:.+]]
177 // LAMBDA: [[CASE1]]
178 // LAMBDA: [[G_VAL:%.+]] = load i32, i32* [[G_REF]]
179 // LAMBDA: [[G_PRIV_VAL:%.+]] = load i32, i32* [[G_PRIVATE_ADDR]]
180 // LAMBDA: [[ADD:%.+]] = add nsw i32 [[G_VAL]], [[G_PRIV_VAL]]
181 // LAMBDA: store i32 [[ADD]], i32* [[G_REF]]
182 // LAMBDA: call void @__kmpc_end_reduce_nowait(
183 // LAMBDA: br label %[[REDUCTION_DONE]]
184 // LAMBDA: [[CASE2]]
185 // LAMBDA: [[G_PRIV_VAL:%.+]] = load i32, i32* [[G_PRIVATE_ADDR]]
186 // LAMBDA: atomicrmw add i32* [[G_REF]], i32 [[G_PRIV_VAL]] monotonic
187 // LAMBDA: br label %[[REDUCTION_DONE]]
188 // LAMBDA: [[REDUCTION_DONE]]
189 // LAMBDA: ret void
190 [&]() {
191 // LAMBDA: define {{.+}} void [[INNER_LAMBDA]](%{{.+}}* [[ARG_PTR:%.+]])
192 // LAMBDA: store %{{.+}}* [[ARG_PTR]], %{{.+}}** [[ARG_PTR_REF:%.+]],
193 g = 2;
194 // LAMBDA: [[ARG_PTR:%.+]] = load %{{.+}}*, %{{.+}}** [[ARG_PTR_REF]]
195 // LAMBDA: [[G_PTR_REF:%.+]] = getelementptr inbounds %{{.+}}, %{{.+}}* [[ARG_PTR]], i{{[0-9]+}} 0, i{{[0-9]+}} 0
196 // LAMBDA: [[G_REF:%.+]] = load i{{[0-9]+}}*, i{{[0-9]+}}** [[G_PTR_REF]]
Alexey Bataevb44fdfc2015-07-14 10:32:29 +0000197 // LAMBDA: store i{{[0-9]+}} 2, i{{[0-9]+}}* [[G_REF]]
Alexey Bataev794ba0d2015-04-10 10:43:45 +0000198 }();
199 }
200 }();
201 return 0;
202#elif defined(BLOCKS)
203 // BLOCKS: [[G:@.+]] = global i{{[0-9]+}} 1212,
204 // BLOCKS-LABEL: @main
Alexey Bataev61205072016-03-02 04:57:40 +0000205 // BLOCKS: call
David Blaikied6c88ec2015-04-16 23:25:00 +0000206 // BLOCKS: call void {{%.+}}(i8
Alexey Bataev794ba0d2015-04-10 10:43:45 +0000207 ^{
208 // BLOCKS: define{{.*}} internal{{.*}} void {{.+}}(i8*
Alexey Bataev2377fe92015-09-10 08:12:02 +0000209 // BLOCKS: call void {{.+}} @__kmpc_fork_call({{.+}}, i32 1, {{.+}}* [[OMP_REGION:@.+]] to {{.+}}, i32* [[G]])
Alexey Bataev794ba0d2015-04-10 10:43:45 +0000210#pragma omp parallel reduction(-:g)
211 {
Alexey Bataev2377fe92015-09-10 08:12:02 +0000212 // BLOCKS: define{{.*}} internal{{.*}} void [[OMP_REGION]](i32* noalias %{{.+}}, i32* noalias %{{.+}}, i32* dereferenceable(4) %{{.+}})
Alexey Bataev794ba0d2015-04-10 10:43:45 +0000213 // BLOCKS: [[G_PRIVATE_ADDR:%.+]] = alloca i{{[0-9]+}},
214
215 // Reduction list for runtime.
216 // BLOCKS: [[RED_LIST:%.+]] = alloca [1 x i8*],
217
Alexey Bataev2377fe92015-09-10 08:12:02 +0000218 // BLOCKS: [[G_REF:%.+]] = load i{{[0-9]+}}*, i{{[0-9]+}}** [[G_REF_ADDR:%.+]]
Alexey Bataev1d7f0fa2015-09-10 09:48:30 +0000219 // BLOCKS: store i{{[0-9]+}} 0, i{{[0-9]+}}* [[G_PRIVATE_ADDR]], align 128
Alexey Bataev794ba0d2015-04-10 10:43:45 +0000220 g = 1;
Alexey Bataev1d7f0fa2015-09-10 09:48:30 +0000221 // BLOCKS: store i{{[0-9]+}} 1, i{{[0-9]+}}* [[G_PRIVATE_ADDR]], align 128
Alexey Bataev794ba0d2015-04-10 10:43:45 +0000222 // BLOCKS-NOT: [[G]]{{[[^:word:]]}}
223 // BLOCKS: i{{[0-9]+}}* [[G_PRIVATE_ADDR]]
224 // BLOCKS-NOT: [[G]]{{[[^:word:]]}}
David Blaikied6c88ec2015-04-16 23:25:00 +0000225 // BLOCKS: call void {{%.+}}(i8
Alexey Bataev794ba0d2015-04-10 10:43:45 +0000226
John McCall7f416cc2015-09-08 08:05:57 +0000227 // BLOCKS: [[G_PRIV_REF:%.+]] = getelementptr inbounds [1 x i8*], [1 x i8*]* [[RED_LIST]], i64 0, i64 0
Alexey Bataev794ba0d2015-04-10 10:43:45 +0000228 // BLOCKS: [[BITCAST:%.+]] = bitcast i32* [[G_PRIVATE_ADDR]] to i8*
229 // BLOCKS: store i8* [[BITCAST]], i8** [[G_PRIV_REF]],
230 // BLOCKS: call i32 @__kmpc_reduce_nowait(
231 // BLOCKS: switch i32 %{{.+}}, label %[[REDUCTION_DONE:.+]] [
232 // BLOCKS: i32 1, label %[[CASE1:.+]]
233 // BLOCKS: i32 2, label %[[CASE2:.+]]
234 // BLOCKS: [[CASE1]]
235 // BLOCKS: [[G_VAL:%.+]] = load i32, i32* [[G_REF]]
236 // BLOCKS: [[G_PRIV_VAL:%.+]] = load i32, i32* [[G_PRIVATE_ADDR]]
237 // BLOCKS: [[ADD:%.+]] = add nsw i32 [[G_VAL]], [[G_PRIV_VAL]]
238 // BLOCKS: store i32 [[ADD]], i32* [[G_REF]]
239 // BLOCKS: call void @__kmpc_end_reduce_nowait(
240 // BLOCKS: br label %[[REDUCTION_DONE]]
241 // BLOCKS: [[CASE2]]
242 // BLOCKS: [[G_PRIV_VAL:%.+]] = load i32, i32* [[G_PRIVATE_ADDR]]
243 // BLOCKS: atomicrmw add i32* [[G_REF]], i32 [[G_PRIV_VAL]] monotonic
244 // BLOCKS: br label %[[REDUCTION_DONE]]
245 // BLOCKS: [[REDUCTION_DONE]]
246 // BLOCKS: ret void
247 ^{
248 // BLOCKS: define {{.+}} void {{@.+}}(i8*
249 g = 2;
250 // BLOCKS-NOT: [[G]]{{[[^:word:]]}}
Alexey Bataevb44fdfc2015-07-14 10:32:29 +0000251 // BLOCKS: store i{{[0-9]+}} 2, i{{[0-9]+}}*
Alexey Bataev794ba0d2015-04-10 10:43:45 +0000252 // BLOCKS-NOT: [[G]]{{[[^:word:]]}}
253 // BLOCKS: ret
254 }();
255 }
256 }();
257 return 0;
Alexey Bataev61205072016-03-02 04:57:40 +0000258// BLOCKS: define {{.+}} @{{.+}}([[SS_TY]]*
259// BLOCKS: getelementptr inbounds [[SS_TY]], [[SS_TY]]* %{{.+}}, i32 0, i32 0
260// BLOCKS: store i{{[0-9]+}} 0, i{{[0-9]+}}* %
261// BLOCKS: getelementptr inbounds [[SS_TY]], [[SS_TY]]* %{{.+}}, i32 0, i32 1
262// BLOCKS: store i8
263// BLOCKS: getelementptr inbounds [[SS_TY]], [[SS_TY]]* %{{.+}}, i32 0, i32 2
264// BLOCKS: getelementptr inbounds [[SS_TY]], [[SS_TY]]* %{{.+}}, i32 0, i32 0
265// BLOCKS-NOT: getelementptr inbounds [[SS_TY]], [[SS_TY]]* %{{.+}}, i32 0, i32 1
266// BLOCKS: getelementptr inbounds [[SS_TY]], [[SS_TY]]* %{{.+}}, i32 0, i32 2
267// BLOCKS: call void (%{{.+}}*, i{{[0-9]+}}, void (i{{[0-9]+}}*, i{{[0-9]+}}*, ...)*, ...) @__kmpc_fork_call(%{{.+}}* @{{.+}}, i{{[0-9]+}} 4, void (i{{[0-9]+}}*, i{{[0-9]+}}*, ...)* bitcast (void (i{{[0-9]+}}*, i{{[0-9]+}}*, [[SS_TY]]*, i32*, i32*, i32*)* [[SS_MICROTASK:@.+]] to void
268// BLOCKS: [[B_REF:%.+]] = getelementptr {{.*}}[[SS_TY]], [[SS_TY]]* %{{.*}}, i32 0, i32 1
269// BLOCKS: store i8 %{{.+}}, i8* [[B_REF]],
270// BLOCKS: ret
271
272// BLOCKS: define internal void [[SS_MICROTASK]](i{{[0-9]+}}* noalias [[GTID_ADDR:%.+]], i{{[0-9]+}}* noalias %{{.+}}, [[SS_TY]]* %{{.+}}, i32* {{.+}}, i32* {{.+}}, i32* {{.+}})
273// BLOCKS-NOT: getelementptr {{.*}}[[SS_TY]], [[SS_TY]]* %
274// BLOCKS: call{{.*}} void
275// BLOCKS: ret void
276
277// BLOCKS: define internal void @{{.+}}(i{{[0-9]+}}* noalias [[GTID_ADDR:%.+]], i{{[0-9]+}}* noalias %{{.+}}, [[SS_TY]]* %{{.+}}, i32* {{.+}}, i32* {{.+}}, i32* {{.+}})
278// BLOCKS: [[A_PRIV:%.+]] = alloca i{{[0-9]+}},
279// BLOCKS: [[B_PRIV:%.+]] = alloca i{{[0-9]+}},
280// BLOCKS: [[C_PRIV:%.+]] = alloca i{{[0-9]+}},
281// BLOCKS: store i{{[0-9]+}} 0, i{{[0-9]+}}* [[A_PRIV]],
282// BLOCKS: store i{{[0-9]+}}* [[A_PRIV]], i{{[0-9]+}}** [[REFA:%.+]],
283// BLOCKS: store i{{[0-9]+}} 0, i{{[0-9]+}}* [[B_PRIV]],
284// BLOCKS: store i{{[0-9]+}} 0, i{{[0-9]+}}* [[C_PRIV]],
285// BLOCKS: store i{{[0-9]+}}* [[C_PRIV]], i{{[0-9]+}}** [[REFC:%.+]],
286// BLOCKS: [[A_PRIV:%.+]] = load i{{[0-9]+}}*, i{{[0-9]+}}** [[REFA]],
287// BLOCKS-NEXT: [[A_VAL:%.+]] = load i{{[0-9]+}}, i{{[0-9]+}}* [[A_PRIV]],
288// BLOCKS-NEXT: [[INC:%.+]] = add nsw i{{[0-9]+}} [[A_VAL]], 1
289// BLOCKS-NEXT: store i{{[0-9]+}} [[INC]], i{{[0-9]+}}* [[A_PRIV]],
290// BLOCKS-NEXT: [[B_VAL:%.+]] = load i{{[0-9]+}}, i{{[0-9]+}}* [[B_PRIV]],
291// BLOCKS-NEXT: [[DEC:%.+]] = add nsw i{{[0-9]+}} [[B_VAL]], -1
292// BLOCKS-NEXT: store i{{[0-9]+}} [[DEC]], i{{[0-9]+}}* [[B_PRIV]],
293// BLOCKS-NEXT: [[C_PRIV:%.+]] = load i{{[0-9]+}}*, i{{[0-9]+}}** [[REFC]],
294// BLOCKS-NEXT: [[C_VAL:%.+]] = load i{{[0-9]+}}, i{{[0-9]+}}* [[C_PRIV]],
295// BLOCKS-NEXT: [[DIV:%.+]] = sdiv i{{[0-9]+}} [[C_VAL]], 1
296// BLOCKS-NEXT: store i{{[0-9]+}} [[DIV]], i{{[0-9]+}}* [[C_PRIV]],
297// BLOCKS: call i32 @__kmpc_reduce_nowait(
298// BLOCKS: ret void
Alexey Bataev794ba0d2015-04-10 10:43:45 +0000299#else
300 S<float> test;
301 float t_var = 0, t_var1;
302 int vec[] = {1, 2};
303 S<float> s_arr[] = {1, 2};
304 S<float> var(3), var1;
Alexey Bataev8524d152016-01-21 12:35:58 +0000305 float _Complex cf;
Alexey Bataev794ba0d2015-04-10 10:43:45 +0000306#pragma omp parallel reduction(+:t_var) reduction(&:var) reduction(&& : var1) reduction(min: t_var1)
307 {
308 vec[0] = t_var;
309 s_arr[0] = var;
310 }
Alexey Bataev8ef31412015-12-18 07:58:25 +0000311 if (var1)
312#pragma omp parallel reduction(+ : t_var) reduction(& : var) reduction(&& : var1) reduction(min : t_var1)
313 while (1) {
314 vec[0] = t_var;
315 s_arr[0] = var;
316 }
Alexey Bataev8524d152016-01-21 12:35:58 +0000317#pragma omp parallel reduction(+ : cf)
318 ;
Alexey Bataev794ba0d2015-04-10 10:43:45 +0000319 return tmain<int>();
320#endif
321}
322
323// CHECK: define {{.*}}i{{[0-9]+}} @main()
324// CHECK: [[TEST:%.+]] = alloca [[S_FLOAT_TY]],
325// CHECK: call {{.*}} [[S_FLOAT_TY_CONSTR:@.+]]([[S_FLOAT_TY]]* [[TEST]])
Alexey Bataev2377fe92015-09-10 08:12:02 +0000326// CHECK: call void (%{{.+}}*, i{{[0-9]+}}, void (i{{[0-9]+}}*, i{{[0-9]+}}*, ...)*, ...) @__kmpc_fork_call(%{{.+}}* @{{.+}}, i{{[0-9]+}} 6, void (i{{[0-9]+}}*, i{{[0-9]+}}*, ...)* bitcast (void (i{{[0-9]+}}*, i{{[0-9]+}}*, [2 x i32]*, float*, [2 x [[S_FLOAT_TY]]]*, [[S_FLOAT_TY]]*, [[S_FLOAT_TY]]*, float*)* [[MAIN_MICROTASK:@.+]] to void
Alexey Bataev8ef31412015-12-18 07:58:25 +0000327// CHECK: call void (%{{.+}}*, i{{[0-9]+}}, void (i{{[0-9]+}}*, i{{[0-9]+}}*, ...)*, ...) @__kmpc_fork_call(%{{.+}}* @{{.+}}, i{{[0-9]+}} 6, void (i{{[0-9]+}}*, i{{[0-9]+}}*, ...)* bitcast (void (i{{[0-9]+}}*, i{{[0-9]+}}*, [2 x i32]*, float*, [2 x [[S_FLOAT_TY]]]*, [[S_FLOAT_TY]]*, [[S_FLOAT_TY]]*, float*)* [[MAIN_MICROTASK1:@.+]] to void
Alexey Bataev8524d152016-01-21 12:35:58 +0000328// CHECK: call void (%{{.+}}*, i{{[0-9]+}}, void (i{{[0-9]+}}*, i{{[0-9]+}}*, ...)*, ...) @__kmpc_fork_call(%{{.+}}* @{{.+}}, i{{[0-9]+}} 1, void (i{{[0-9]+}}*, i{{[0-9]+}}*, ...)* bitcast (void (i{{[0-9]+}}*, i{{[0-9]+}}*, { float, float }*)* [[MAIN_MICROTASK2:@.+]] to void
Alexey Bataev794ba0d2015-04-10 10:43:45 +0000329// CHECK: = call {{.*}}i{{.+}} [[TMAIN_INT:@.+]]()
330// CHECK: call {{.*}} [[S_FLOAT_TY_DESTR:@.+]]([[S_FLOAT_TY]]*
331// CHECK: ret
332//
Alexey Bataev2377fe92015-09-10 08:12:02 +0000333// CHECK: define internal void [[MAIN_MICROTASK]](i{{[0-9]+}}* noalias [[GTID_ADDR:%.+]], i{{[0-9]+}}* noalias %{{.+}},
Alexey Bataev794ba0d2015-04-10 10:43:45 +0000334// CHECK: [[T_VAR_PRIV:%.+]] = alloca float,
335// CHECK: [[VAR_PRIV:%.+]] = alloca [[S_FLOAT_TY]],
336// CHECK: [[VAR1_PRIV:%.+]] = alloca [[S_FLOAT_TY]],
337// CHECK: [[T_VAR1_PRIV:%.+]] = alloca float,
338
339// Reduction list for runtime.
340// CHECK: [[RED_LIST:%.+]] = alloca [4 x i8*],
341
342// CHECK: store i{{[0-9]+}}* [[GTID_ADDR]], i{{[0-9]+}}** [[GTID_ADDR_ADDR:%.+]],
343
Alexey Bataev2377fe92015-09-10 08:12:02 +0000344// CHECK: [[T_VAR_REF:%.+]] = load float*, float** %
345// CHECK: [[VAR_REF:%.+]] = load [[S_FLOAT_TY]]*, [[S_FLOAT_TY]]** %
346// CHECK: [[VAR1_REF:%.+]] = load [[S_FLOAT_TY]]*, [[S_FLOAT_TY]]** %
347// CHECK: [[T_VAR1_REF:%.+]] = load float*, float** %
348
Alexey Bataev794ba0d2015-04-10 10:43:45 +0000349// For + reduction operation initial value of private variable is 0.
350// CHECK: store float 0.0{{.+}}, float* [[T_VAR_PRIV]],
351
Alexey Bataev794ba0d2015-04-10 10:43:45 +0000352// For & reduction operation initial value of private variable is ones in all bits.
353// CHECK: call {{.*}} [[S_FLOAT_TY_CONSTR:@.+]]([[S_FLOAT_TY]]* [[VAR_PRIV]])
354
Alexey Bataev794ba0d2015-04-10 10:43:45 +0000355// For && reduction operation initial value of private variable is 1.0.
356// CHECK: call {{.*}} [[S_FLOAT_TY_CONSTR:@.+]]([[S_FLOAT_TY]]* [[VAR1_PRIV]])
357
Alexey Bataev794ba0d2015-04-10 10:43:45 +0000358// For min reduction operation initial value of private variable is largest repesentable value.
359// CHECK: store float 0x47EFFFFFE0000000, float* [[T_VAR1_PRIV]],
360
Alexey Bataev794ba0d2015-04-10 10:43:45 +0000361// Skip checks for internal operations.
362
363// void *RedList[<n>] = {<ReductionVars>[0], ..., <ReductionVars>[<n>-1]};
364
John McCall7f416cc2015-09-08 08:05:57 +0000365// CHECK: [[T_VAR_PRIV_REF:%.+]] = getelementptr inbounds [4 x i8*], [4 x i8*]* [[RED_LIST]], i64 0, i64 0
Alexey Bataev794ba0d2015-04-10 10:43:45 +0000366// CHECK: [[BITCAST:%.+]] = bitcast float* [[T_VAR_PRIV]] to i8*
367// CHECK: store i8* [[BITCAST]], i8** [[T_VAR_PRIV_REF]],
John McCall7f416cc2015-09-08 08:05:57 +0000368// CHECK: [[VAR_PRIV_REF:%.+]] = getelementptr inbounds [4 x i8*], [4 x i8*]* [[RED_LIST]], i64 0, i64 1
Alexey Bataev794ba0d2015-04-10 10:43:45 +0000369// CHECK: [[BITCAST:%.+]] = bitcast [[S_FLOAT_TY]]* [[VAR_PRIV]] to i8*
370// CHECK: store i8* [[BITCAST]], i8** [[VAR_PRIV_REF]],
John McCall7f416cc2015-09-08 08:05:57 +0000371// CHECK: [[VAR1_PRIV_REF:%.+]] = getelementptr inbounds [4 x i8*], [4 x i8*]* [[RED_LIST]], i64 0, i64 2
Alexey Bataev794ba0d2015-04-10 10:43:45 +0000372// CHECK: [[BITCAST:%.+]] = bitcast [[S_FLOAT_TY]]* [[VAR1_PRIV]] to i8*
373// CHECK: store i8* [[BITCAST]], i8** [[VAR1_PRIV_REF]],
John McCall7f416cc2015-09-08 08:05:57 +0000374// CHECK: [[T_VAR1_PRIV_REF:%.+]] = getelementptr inbounds [4 x i8*], [4 x i8*]* [[RED_LIST]], i64 0, i64 3
Alexey Bataev794ba0d2015-04-10 10:43:45 +0000375// CHECK: [[BITCAST:%.+]] = bitcast float* [[T_VAR1_PRIV]] to i8*
376// CHECK: store i8* [[BITCAST]], i8** [[T_VAR1_PRIV_REF]],
377
378// res = __kmpc_reduce_nowait(<loc>, <gtid>, <n>, sizeof(RedList), RedList, reduce_func, &<lock>);
379
Alexey Bataev69c62a92015-04-15 04:52:20 +0000380// CHECK: [[GTID_REF:%.+]] = load i{{[0-9]+}}*, i{{[0-9]+}}** [[GTID_ADDR_ADDR]]
381// CHECK: [[GTID:%.+]] = load i{{[0-9]+}}, i{{[0-9]+}}* [[GTID_REF]]
Alexey Bataev794ba0d2015-04-10 10:43:45 +0000382// CHECK: [[BITCAST:%.+]] = bitcast [4 x i8*]* [[RED_LIST]] to i8*
383// CHECK: [[RES:%.+]] = call i32 @__kmpc_reduce_nowait(%{{.+}}* [[REDUCTION_LOC]], i32 [[GTID]], i32 4, i64 32, i8* [[BITCAST]], void (i8*, i8*)* [[REDUCTION_FUNC:@.+]], [8 x i32]* [[REDUCTION_LOCK]])
384
385// switch(res)
386// CHECK: switch i32 [[RES]], label %[[RED_DONE:.+]] [
387// CHECK: i32 1, label %[[CASE1:.+]]
388// CHECK: i32 2, label %[[CASE2:.+]]
389// CHECK: ]
390
391// case 1:
392// t_var += t_var_reduction;
393// CHECK: [[T_VAR_VAL:%.+]] = load float, float* [[T_VAR_REF]],
394// CHECK: [[T_VAR_PRIV_VAL:%.+]] = load float, float* [[T_VAR_PRIV]],
395// CHECK: [[UP:%.+]] = fadd float [[T_VAR_VAL]], [[T_VAR_PRIV_VAL]]
396// CHECK: store float [[UP]], float* [[T_VAR_REF]],
397
398// var = var.operator &(var_reduction);
399// CHECK: [[UP:%.+]] = call dereferenceable(4) [[S_FLOAT_TY]]* @{{.+}}([[S_FLOAT_TY]]* [[VAR_REF]], [[S_FLOAT_TY]]* dereferenceable(4) [[VAR_PRIV]])
400// CHECK: [[BC1:%.+]] = bitcast [[S_FLOAT_TY]]* [[VAR_REF]] to i8*
401// CHECK: [[BC2:%.+]] = bitcast [[S_FLOAT_TY]]* [[UP]] to i8*
Pete Cooper3b39e882015-11-19 05:55:59 +0000402// CHECK: call void @llvm.memcpy.p0i8.p0i8.i64(i8* [[BC1]], i8* [[BC2]], i64 4, i32 4, i1 false)
Alexey Bataev794ba0d2015-04-10 10:43:45 +0000403
404// var1 = var1.operator &&(var1_reduction);
405// CHECK: [[TO_FLOAT:%.+]] = call float @{{.+}}([[S_FLOAT_TY]]* [[VAR1_REF]])
406// CHECK: [[VAR1_BOOL:%.+]] = fcmp une float [[TO_FLOAT]], 0.0
Alexey Bataev69a47792015-05-07 03:54:03 +0000407// CHECK: br i1 [[VAR1_BOOL]], label %[[TRUE:.+]], label %[[END2:.+]]
Alexey Bataev794ba0d2015-04-10 10:43:45 +0000408// CHECK: [[TRUE]]
409// CHECK: [[TO_FLOAT:%.+]] = call float @{{.+}}([[S_FLOAT_TY]]* [[VAR1_PRIV]])
410// CHECK: [[VAR1_REDUCTION_BOOL:%.+]] = fcmp une float [[TO_FLOAT]], 0.0
Alexey Bataev794ba0d2015-04-10 10:43:45 +0000411// CHECK: br label %[[END2]]
412// CHECK: [[END2]]
Alexey Bataev69a47792015-05-07 03:54:03 +0000413// CHECK: [[COND_LVALUE:%.+]] = phi i1 [ false, %{{.+}} ], [ [[VAR1_REDUCTION_BOOL]], %[[TRUE]] ]
414// CHECK: [[CONV:%.+]] = uitofp i1 [[COND_LVALUE]] to float
415// CHECK: call void @{{.+}}([[S_FLOAT_TY]]* [[COND_LVALUE:%.+]], float [[CONV]])
Alexey Bataev794ba0d2015-04-10 10:43:45 +0000416// CHECK: [[BC1:%.+]] = bitcast [[S_FLOAT_TY]]* [[VAR1_REF]] to i8*
417// CHECK: [[BC2:%.+]] = bitcast [[S_FLOAT_TY]]* [[COND_LVALUE]] to i8*
Pete Cooper3b39e882015-11-19 05:55:59 +0000418// CHECK: call void @llvm.memcpy.p0i8.p0i8.i64(i8* [[BC1]], i8* [[BC2]], i64 4, i32 4, i1 false)
Alexey Bataev794ba0d2015-04-10 10:43:45 +0000419
420// t_var1 = min(t_var1, t_var1_reduction);
421// CHECK: [[T_VAR1_VAL:%.+]] = load float, float* [[T_VAR1_REF]],
422// CHECK: [[T_VAR1_PRIV_VAL:%.+]] = load float, float* [[T_VAR1_PRIV]],
423// CHECK: [[CMP:%.+]] = fcmp olt float [[T_VAR1_VAL]], [[T_VAR1_PRIV_VAL]]
Alexey Bataev69a47792015-05-07 03:54:03 +0000424// CHECK: br i1 [[CMP]]
425// CHECK: [[UP:%.+]] = phi float
Alexey Bataev794ba0d2015-04-10 10:43:45 +0000426// CHECK: store float [[UP]], float* [[T_VAR1_REF]],
427
428// __kmpc_end_reduce_nowait(<loc>, <gtid>, &<lock>);
429// CHECK: call void @__kmpc_end_reduce_nowait(%{{.+}}* [[REDUCTION_LOC]], i32 [[GTID]], [8 x i32]* [[REDUCTION_LOCK]])
430
431// break;
432// CHECK: br label %[[RED_DONE]]
433
434// case 2:
435// t_var += t_var_reduction;
436// CHECK: load float, float* [[T_VAR_PRIV]]
437// CHECK: [[T_VAR_REF_INT:%.+]] = bitcast float* [[T_VAR_REF]] to i32*
Alexey Bataevf0ab5532015-05-15 08:36:34 +0000438// CHECK: [[OLD1:%.+]] = load atomic i32, i32* [[T_VAR_REF_INT]] monotonic,
Alexey Bataev794ba0d2015-04-10 10:43:45 +0000439// CHECK: br label %[[CONT:.+]]
440// CHECK: [[CONT]]
Alexey Bataevf0ab5532015-05-15 08:36:34 +0000441// CHECK: [[ORIG_OLD_INT:%.+]] = phi i32 [ [[OLD1]], %{{.+}} ], [ [[OLD2:%.+]], %[[CONT]] ]
442// CHECK: fadd float
443// CHECK: [[UP_INT:%.+]] = load i32
Alexey Bataev794ba0d2015-04-10 10:43:45 +0000444// CHECK: [[T_VAR_REF_INT:%.+]] = bitcast float* [[T_VAR_REF]] to i32*
445// CHECK: [[RES:%.+]] = cmpxchg i32* [[T_VAR_REF_INT]], i32 [[ORIG_OLD_INT]], i32 [[UP_INT]] monotonic monotonic
Alexey Bataevf0ab5532015-05-15 08:36:34 +0000446// CHECK: [[OLD2:%.+]] = extractvalue { i32, i1 } [[RES]], 0
Alexey Bataev794ba0d2015-04-10 10:43:45 +0000447// CHECK: [[SUCCESS_FAIL:%.+]] = extractvalue { i32, i1 } [[RES]], 1
Alexey Bataev794ba0d2015-04-10 10:43:45 +0000448// CHECK: br i1 [[SUCCESS_FAIL]], label %[[ATOMIC_DONE:.+]], label %[[CONT]]
449// CHECK: [[ATOMIC_DONE]]
450
451// var = var.operator &(var_reduction);
452// CHECK: call void @__kmpc_critical(
453// CHECK: [[UP:%.+]] = call dereferenceable(4) [[S_FLOAT_TY]]* @{{.+}}([[S_FLOAT_TY]]* [[VAR_REF]], [[S_FLOAT_TY]]* dereferenceable(4) [[VAR_PRIV]])
454// CHECK: [[BC1:%.+]] = bitcast [[S_FLOAT_TY]]* [[VAR_REF]] to i8*
455// CHECK: [[BC2:%.+]] = bitcast [[S_FLOAT_TY]]* [[UP]] to i8*
Pete Cooper3b39e882015-11-19 05:55:59 +0000456// CHECK: call void @llvm.memcpy.p0i8.p0i8.i64(i8* [[BC1]], i8* [[BC2]], i64 4, i32 4, i1 false)
Alexey Bataev794ba0d2015-04-10 10:43:45 +0000457// CHECK: call void @__kmpc_end_critical(
458
459// var1 = var1.operator &&(var1_reduction);
460// CHECK: call void @__kmpc_critical(
461// CHECK: [[TO_FLOAT:%.+]] = call float @{{.+}}([[S_FLOAT_TY]]* [[VAR1_REF]])
462// CHECK: [[VAR1_BOOL:%.+]] = fcmp une float [[TO_FLOAT]], 0.0
Alexey Bataev69a47792015-05-07 03:54:03 +0000463// CHECK: br i1 [[VAR1_BOOL]], label %[[TRUE:.+]], label %[[END2:.+]]
Alexey Bataev794ba0d2015-04-10 10:43:45 +0000464// CHECK: [[TRUE]]
465// CHECK: [[TO_FLOAT:%.+]] = call float @{{.+}}([[S_FLOAT_TY]]* [[VAR1_PRIV]])
466// CHECK: [[VAR1_REDUCTION_BOOL:%.+]] = fcmp une float [[TO_FLOAT]], 0.0
Alexey Bataev794ba0d2015-04-10 10:43:45 +0000467// CHECK: br label %[[END2]]
468// CHECK: [[END2]]
Alexey Bataev69a47792015-05-07 03:54:03 +0000469// CHECK: [[COND_LVALUE:%.+]] = phi i1 [ false, %{{.+}} ], [ [[VAR1_REDUCTION_BOOL]], %[[TRUE]] ]
470// CHECK: [[CONV:%.+]] = uitofp i1 [[COND_LVALUE]] to float
471// CHECK: call void @{{.+}}([[S_FLOAT_TY]]* [[COND_LVALUE:%.+]], float [[CONV]])
Alexey Bataev794ba0d2015-04-10 10:43:45 +0000472// CHECK: [[BC1:%.+]] = bitcast [[S_FLOAT_TY]]* [[VAR1_REF]] to i8*
473// CHECK: [[BC2:%.+]] = bitcast [[S_FLOAT_TY]]* [[COND_LVALUE]] to i8*
Pete Cooper3b39e882015-11-19 05:55:59 +0000474// CHECK: call void @llvm.memcpy.p0i8.p0i8.i64(i8* [[BC1]], i8* [[BC2]], i64 4, i32 4, i1 false)
Alexey Bataev794ba0d2015-04-10 10:43:45 +0000475// CHECK: call void @__kmpc_end_critical(
476
477// t_var1 = min(t_var1, t_var1_reduction);
478// CHECK: load float, float* [[T_VAR1_PRIV]]
479// CHECK: [[T_VAR1_REF_INT:%.+]] = bitcast float* [[T_VAR1_REF]] to i32*
Alexey Bataevf0ab5532015-05-15 08:36:34 +0000480// CHECK: [[OLD1:%.+]] = load atomic i32, i32* [[T_VAR1_REF_INT]] monotonic,
Alexey Bataev794ba0d2015-04-10 10:43:45 +0000481// CHECK: br label %[[CONT:.+]]
482// CHECK: [[CONT]]
Alexey Bataevf0ab5532015-05-15 08:36:34 +0000483// CHECK: [[ORIG_OLD_INT:%.+]] = phi i32 [ [[OLD1]], %{{.+}} ], [ [[OLD2:%.+]], %{{.+}} ]
Alexey Bataev794ba0d2015-04-10 10:43:45 +0000484// CHECK: [[CMP:%.+]] = fcmp olt float
Alexey Bataev69a47792015-05-07 03:54:03 +0000485// CHECK: br i1 [[CMP]]
486// CHECK: [[UP:%.+]] = phi float
Alexey Bataevf0ab5532015-05-15 08:36:34 +0000487// CHECK: [[UP_INT:%.+]] = load i32
Alexey Bataev794ba0d2015-04-10 10:43:45 +0000488// CHECK: [[T_VAR1_REF_INT:%.+]] = bitcast float* [[T_VAR1_REF]] to i32*
489// CHECK: [[RES:%.+]] = cmpxchg i32* [[T_VAR1_REF_INT]], i32 [[ORIG_OLD_INT]], i32 [[UP_INT]] monotonic monotonic
Alexey Bataevf0ab5532015-05-15 08:36:34 +0000490// CHECK: [[OLD2:%.+]] = extractvalue { i32, i1 } [[RES]], 0
Alexey Bataev794ba0d2015-04-10 10:43:45 +0000491// CHECK: [[SUCCESS_FAIL:%.+]] = extractvalue { i32, i1 } [[RES]], 1
Alexey Bataev794ba0d2015-04-10 10:43:45 +0000492// CHECK: br i1 [[SUCCESS_FAIL]], label %[[ATOMIC_DONE:.+]], label %[[CONT]]
493// CHECK: [[ATOMIC_DONE]]
494
495// break;
496// CHECK: br label %[[RED_DONE]]
497// CHECK: [[RED_DONE]]
Alexey Bataev794ba0d2015-04-10 10:43:45 +0000498
499// CHECK-DAG: call {{.*}} [[S_FLOAT_TY_DESTR]]([[S_FLOAT_TY]]* [[VAR_PRIV]])
500// CHECK-DAG: call {{.*}} [[S_FLOAT_TY_DESTR]]([[S_FLOAT_TY]]*
501// CHECK: ret void
502
503// void reduce_func(void *lhs[<n>], void *rhs[<n>]) {
504// *(Type0*)lhs[0] = ReductionOperation0(*(Type0*)lhs[0], *(Type0*)rhs[0]);
505// ...
506// *(Type<n>-1*)lhs[<n>-1] = ReductionOperation<n>-1(*(Type<n>-1*)lhs[<n>-1],
507// *(Type<n>-1*)rhs[<n>-1]);
508// }
509// CHECK: define internal void [[REDUCTION_FUNC]](i8*, i8*)
510// t_var_lhs = (float*)lhs[0];
John McCall7f416cc2015-09-08 08:05:57 +0000511// CHECK: [[T_VAR_RHS_REF:%.+]] = getelementptr inbounds [4 x i8*], [4 x i8*]* [[RED_LIST_RHS:%.+]], i64 0, i64 0
Alexey Bataev794ba0d2015-04-10 10:43:45 +0000512// CHECK: [[T_VAR_RHS_VOID:%.+]] = load i8*, i8** [[T_VAR_RHS_REF]],
513// CHECK: [[T_VAR_RHS:%.+]] = bitcast i8* [[T_VAR_RHS_VOID]] to float*
514// t_var_rhs = (float*)rhs[0];
John McCall7f416cc2015-09-08 08:05:57 +0000515// CHECK: [[T_VAR_LHS_REF:%.+]] = getelementptr inbounds [4 x i8*], [4 x i8*]* [[RED_LIST_LHS:%.+]], i64 0, i64 0
Alexey Bataev794ba0d2015-04-10 10:43:45 +0000516// CHECK: [[T_VAR_LHS_VOID:%.+]] = load i8*, i8** [[T_VAR_LHS_REF]],
517// CHECK: [[T_VAR_LHS:%.+]] = bitcast i8* [[T_VAR_LHS_VOID]] to float*
518
519// var_lhs = (S<float>*)lhs[1];
John McCall7f416cc2015-09-08 08:05:57 +0000520// CHECK: [[VAR_RHS_REF:%.+]] = getelementptr inbounds [4 x i8*], [4 x i8*]* [[RED_LIST_RHS]], i64 0, i64 1
Alexey Bataev794ba0d2015-04-10 10:43:45 +0000521// CHECK: [[VAR_RHS_VOID:%.+]] = load i8*, i8** [[VAR_RHS_REF]],
522// CHECK: [[VAR_RHS:%.+]] = bitcast i8* [[VAR_RHS_VOID]] to [[S_FLOAT_TY]]*
523// var_rhs = (S<float>*)rhs[1];
John McCall7f416cc2015-09-08 08:05:57 +0000524// CHECK: [[VAR_LHS_REF:%.+]] = getelementptr inbounds [4 x i8*], [4 x i8*]* [[RED_LIST_LHS]], i64 0, i64 1
Alexey Bataev794ba0d2015-04-10 10:43:45 +0000525// CHECK: [[VAR_LHS_VOID:%.+]] = load i8*, i8** [[VAR_LHS_REF]],
526// CHECK: [[VAR_LHS:%.+]] = bitcast i8* [[VAR_LHS_VOID]] to [[S_FLOAT_TY]]*
527
528// var1_lhs = (S<float>*)lhs[2];
John McCall7f416cc2015-09-08 08:05:57 +0000529// CHECK: [[VAR1_RHS_REF:%.+]] = getelementptr inbounds [4 x i8*], [4 x i8*]* [[RED_LIST_RHS]], i64 0, i64 2
Alexey Bataev794ba0d2015-04-10 10:43:45 +0000530// CHECK: [[VAR1_RHS_VOID:%.+]] = load i8*, i8** [[VAR1_RHS_REF]],
531// CHECK: [[VAR1_RHS:%.+]] = bitcast i8* [[VAR1_RHS_VOID]] to [[S_FLOAT_TY]]*
532// var1_rhs = (S<float>*)rhs[2];
John McCall7f416cc2015-09-08 08:05:57 +0000533// CHECK: [[VAR1_LHS_REF:%.+]] = getelementptr inbounds [4 x i8*], [4 x i8*]* [[RED_LIST_LHS]], i64 0, i64 2
Alexey Bataev794ba0d2015-04-10 10:43:45 +0000534// CHECK: [[VAR1_LHS_VOID:%.+]] = load i8*, i8** [[VAR1_LHS_REF]],
535// CHECK: [[VAR1_LHS:%.+]] = bitcast i8* [[VAR1_LHS_VOID]] to [[S_FLOAT_TY]]*
536
537// t_var1_lhs = (float*)lhs[3];
John McCall7f416cc2015-09-08 08:05:57 +0000538// CHECK: [[T_VAR1_RHS_REF:%.+]] = getelementptr inbounds [4 x i8*], [4 x i8*]* [[RED_LIST_RHS]], i64 0, i64 3
Alexey Bataev794ba0d2015-04-10 10:43:45 +0000539// CHECK: [[T_VAR1_RHS_VOID:%.+]] = load i8*, i8** [[T_VAR1_RHS_REF]],
540// CHECK: [[T_VAR1_RHS:%.+]] = bitcast i8* [[T_VAR1_RHS_VOID]] to float*
541// t_var1_rhs = (float*)rhs[3];
John McCall7f416cc2015-09-08 08:05:57 +0000542// CHECK: [[T_VAR1_LHS_REF:%.+]] = getelementptr inbounds [4 x i8*], [4 x i8*]* [[RED_LIST_LHS]], i64 0, i64 3
Alexey Bataev794ba0d2015-04-10 10:43:45 +0000543// CHECK: [[T_VAR1_LHS_VOID:%.+]] = load i8*, i8** [[T_VAR1_LHS_REF]],
544// CHECK: [[T_VAR1_LHS:%.+]] = bitcast i8* [[T_VAR1_LHS_VOID]] to float*
545
546// t_var_lhs += t_var_rhs;
547// CHECK: [[T_VAR_LHS_VAL:%.+]] = load float, float* [[T_VAR_LHS]],
548// CHECK: [[T_VAR_RHS_VAL:%.+]] = load float, float* [[T_VAR_RHS]],
549// CHECK: [[UP:%.+]] = fadd float [[T_VAR_LHS_VAL]], [[T_VAR_RHS_VAL]]
550// CHECK: store float [[UP]], float* [[T_VAR_LHS]],
551
552// var_lhs = var_lhs.operator &(var_rhs);
553// CHECK: [[UP:%.+]] = call dereferenceable(4) [[S_FLOAT_TY]]* @{{.+}}([[S_FLOAT_TY]]* [[VAR_LHS]], [[S_FLOAT_TY]]* dereferenceable(4) [[VAR_RHS]])
554// CHECK: [[BC1:%.+]] = bitcast [[S_FLOAT_TY]]* [[VAR_LHS]] to i8*
555// CHECK: [[BC2:%.+]] = bitcast [[S_FLOAT_TY]]* [[UP]] to i8*
Pete Cooper3b39e882015-11-19 05:55:59 +0000556// CHECK: call void @llvm.memcpy.p0i8.p0i8.i64(i8* [[BC1]], i8* [[BC2]], i64 4, i32 4, i1 false)
Alexey Bataev794ba0d2015-04-10 10:43:45 +0000557
558// var1_lhs = var1_lhs.operator &&(var1_rhs);
559// CHECK: [[TO_FLOAT:%.+]] = call float @{{.+}}([[S_FLOAT_TY]]* [[VAR1_LHS]])
560// CHECK: [[VAR1_BOOL:%.+]] = fcmp une float [[TO_FLOAT]], 0.0
Alexey Bataev69a47792015-05-07 03:54:03 +0000561// CHECK: br i1 [[VAR1_BOOL]], label %[[TRUE:.+]], label %[[END2:.+]]
Alexey Bataev794ba0d2015-04-10 10:43:45 +0000562// CHECK: [[TRUE]]
563// CHECK: [[TO_FLOAT:%.+]] = call float @{{.+}}([[S_FLOAT_TY]]* [[VAR1_RHS]])
564// CHECK: [[VAR1_REDUCTION_BOOL:%.+]] = fcmp une float [[TO_FLOAT]], 0.0
Alexey Bataev794ba0d2015-04-10 10:43:45 +0000565// CHECK: br label %[[END2]]
566// CHECK: [[END2]]
Alexey Bataev69a47792015-05-07 03:54:03 +0000567// CHECK: [[COND_LVALUE:%.+]] = phi i1 [ false, %{{.+}} ], [ [[VAR1_REDUCTION_BOOL]], %[[TRUE]] ]
568// CHECK: [[CONV:%.+]] = uitofp i1 [[COND_LVALUE]] to float
569// CHECK: call void @{{.+}}([[S_FLOAT_TY]]* [[COND_LVALUE:%.+]], float [[CONV]])
Alexey Bataev794ba0d2015-04-10 10:43:45 +0000570// CHECK: [[BC1:%.+]] = bitcast [[S_FLOAT_TY]]* [[VAR1_LHS]] to i8*
571// CHECK: [[BC2:%.+]] = bitcast [[S_FLOAT_TY]]* [[COND_LVALUE]] to i8*
Pete Cooper3b39e882015-11-19 05:55:59 +0000572// CHECK: call void @llvm.memcpy.p0i8.p0i8.i64(i8* [[BC1]], i8* [[BC2]], i64 4, i32 4, i1 false)
Alexey Bataev794ba0d2015-04-10 10:43:45 +0000573
574// t_var1_lhs = min(t_var1_lhs, t_var1_rhs);
575// CHECK: [[T_VAR1_LHS_VAL:%.+]] = load float, float* [[T_VAR1_LHS]],
576// CHECK: [[T_VAR1_RHS_VAL:%.+]] = load float, float* [[T_VAR1_RHS]],
577// CHECK: [[CMP:%.+]] = fcmp olt float [[T_VAR1_LHS_VAL]], [[T_VAR1_RHS_VAL]]
Alexey Bataev69a47792015-05-07 03:54:03 +0000578// CHECK: br i1 [[CMP]]
579// CHECK: [[UP:%.+]] = phi float
Alexey Bataev794ba0d2015-04-10 10:43:45 +0000580// CHECK: store float [[UP]], float* [[T_VAR1_LHS]],
581// CHECK: ret void
582
Alexey Bataev8ef31412015-12-18 07:58:25 +0000583// CHECK: define internal void [[MAIN_MICROTASK1]](i{{[0-9]+}}* noalias [[GTID_ADDR:%.+]], i{{[0-9]+}}* noalias %{{.+}},
584// CHECK: [[T_VAR_PRIV:%.+]] = alloca float,
585// CHECK: [[VAR_PRIV:%.+]] = alloca [[S_FLOAT_TY]],
586// CHECK: [[VAR1_PRIV:%.+]] = alloca [[S_FLOAT_TY]],
587// CHECK: [[T_VAR1_PRIV:%.+]] = alloca float,
588
589// CHECK: store i{{[0-9]+}}* [[GTID_ADDR]], i{{[0-9]+}}** [[GTID_ADDR_ADDR:%.+]],
590
591// CHECK: [[T_VAR_REF:%.+]] = load float*, float** %
592// CHECK: [[VAR_REF:%.+]] = load [[S_FLOAT_TY]]*, [[S_FLOAT_TY]]** %
593// CHECK: [[VAR1_REF:%.+]] = load [[S_FLOAT_TY]]*, [[S_FLOAT_TY]]** %
594// CHECK: [[T_VAR1_REF:%.+]] = load float*, float** %
595
596// For + reduction operation initial value of private variable is 0.
597// CHECK: store float 0.0{{.+}}, float* [[T_VAR_PRIV]],
598
599// For & reduction operation initial value of private variable is ones in all bits.
600// CHECK: call {{.*}} [[S_FLOAT_TY_CONSTR:@.+]]([[S_FLOAT_TY]]* [[VAR_PRIV]])
601
602// For && reduction operation initial value of private variable is 1.0.
603// CHECK: call {{.*}} [[S_FLOAT_TY_CONSTR:@.+]]([[S_FLOAT_TY]]* [[VAR1_PRIV]])
604
605// For min reduction operation initial value of private variable is largest repesentable value.
606// CHECK: store float 0x47EFFFFFE0000000, float* [[T_VAR1_PRIV]],
607
608// CHECK-NOT: call i32 @__kmpc_reduce
609
610// CHECK: ret void
611
Alexey Bataev794ba0d2015-04-10 10:43:45 +0000612// CHECK: define {{.*}} i{{[0-9]+}} [[TMAIN_INT]]()
613// CHECK: [[TEST:%.+]] = alloca [[S_INT_TY]],
614// CHECK: call {{.*}} [[S_INT_TY_CONSTR:@.+]]([[S_INT_TY]]* [[TEST]])
Alexey Bataev2377fe92015-09-10 08:12:02 +0000615// CHECK: call void (%{{.+}}*, i{{[0-9]+}}, void (i{{[0-9]+}}*, i{{[0-9]+}}*, ...)*, ...) @__kmpc_fork_call(%{{.+}}* @{{.+}}, i{{[0-9]+}} 6, void (i{{[0-9]+}}*, i{{[0-9]+}}*, ...)* bitcast (void (i{{[0-9]+}}*, i{{[0-9]+}}*, [2 x i32]*, i32*, [2 x [[S_INT_TY]]]*, [[S_INT_TY]]*, [[S_INT_TY]]*, i32*)* [[TMAIN_MICROTASK:@.+]] to void
Alexey Bataev794ba0d2015-04-10 10:43:45 +0000616// CHECK: call {{.*}} [[S_INT_TY_DESTR:@.+]]([[S_INT_TY]]*
617// CHECK: ret
618//
Alexey Bataev61205072016-03-02 04:57:40 +0000619// CHECK: define {{.+}} @{{.+}}([[SS_TY]]*
620// CHECK: getelementptr inbounds [[SS_TY]], [[SS_TY]]* %{{.+}}, i32 0, i32 0
621// CHECK: store i{{[0-9]+}} 0, i{{[0-9]+}}* %
622// CHECK: getelementptr inbounds [[SS_TY]], [[SS_TY]]* %{{.+}}, i32 0, i32 1
623// CHECK: store i8
624// CHECK: getelementptr inbounds [[SS_TY]], [[SS_TY]]* %{{.+}}, i32 0, i32 2
625// CHECK: getelementptr inbounds [[SS_TY]], [[SS_TY]]* %{{.+}}, i32 0, i32 0
626// CHECK-NOT: getelementptr inbounds [[SS_TY]], [[SS_TY]]* %{{.+}}, i32 0, i32 1
627// CHECK: getelementptr inbounds [[SS_TY]], [[SS_TY]]* %{{.+}}, i32 0, i32 2
628// CHECK: call void (%{{.+}}*, i{{[0-9]+}}, void (i{{[0-9]+}}*, i{{[0-9]+}}*, ...)*, ...) @__kmpc_fork_call(%{{.+}}* @{{.+}}, i{{[0-9]+}} 4, void (i{{[0-9]+}}*, i{{[0-9]+}}*, ...)* bitcast (void (i{{[0-9]+}}*, i{{[0-9]+}}*, [[SS_TY]]*, i{{[0-9]+}}*, i{{[0-9]+}}*, i{{[0-9]+}}*)* [[SS_MICROTASK:@.+]] to void
629// CHECK: [[B_REF:%.+]] = getelementptr {{.*}}[[SS_TY]], [[SS_TY]]* %{{.*}}, i32 0, i32 1
630// CHECK: store i8 %{{.+}}, i8* [[B_REF]],
631// CHECK: ret
632
633// CHECK: define internal void [[SS_MICROTASK]](i{{[0-9]+}}* noalias [[GTID_ADDR:%.+]], i{{[0-9]+}}* noalias %{{.+}}, [[SS_TY]]*
634// CHECK: [[A_PRIV:%.+]] = alloca i{{[0-9]+}},
635// CHECK: [[B_PRIV:%.+]] = alloca i{{[0-9]+}},
636// CHECK: [[C_PRIV:%.+]] = alloca i{{[0-9]+}},
637// CHECK: store i{{[0-9]+}} 0, i{{[0-9]+}}* [[A_PRIV]],
638// CHECK: store i{{[0-9]+}}* [[A_PRIV]], i{{[0-9]+}}** [[REFA:%.+]],
639// CHECK: store i{{[0-9]+}} 0, i{{[0-9]+}}* [[B_PRIV]],
640// CHECK: store i{{[0-9]+}} 0, i{{[0-9]+}}* [[C_PRIV]],
641// CHECK: store i{{[0-9]+}}* [[C_PRIV]], i{{[0-9]+}}** [[REFC:%.+]],
642// CHECK: [[A_PRIV:%.+]] = load i{{[0-9]+}}*, i{{[0-9]+}}** [[REFA]],
643// CHECK-NEXT: [[A_VAL:%.+]] = load i{{[0-9]+}}, i{{[0-9]+}}* [[A_PRIV]],
644// CHECK-NEXT: [[INC:%.+]] = add nsw i{{[0-9]+}} [[A_VAL]], 1
645// CHECK-NEXT: store i{{[0-9]+}} [[INC]], i{{[0-9]+}}* [[A_PRIV]],
646// CHECK-NEXT: [[B_VAL:%.+]] = load i{{[0-9]+}}, i{{[0-9]+}}* [[B_PRIV]],
647// CHECK-NEXT: [[DEC:%.+]] = add nsw i{{[0-9]+}} [[B_VAL]], -1
648// CHECK-NEXT: store i{{[0-9]+}} [[DEC]], i{{[0-9]+}}* [[B_PRIV]],
649// CHECK-NEXT: [[C_PRIV:%.+]] = load i{{[0-9]+}}*, i{{[0-9]+}}** [[REFC]],
650// CHECK-NEXT: [[C_VAL:%.+]] = load i{{[0-9]+}}, i{{[0-9]+}}* [[C_PRIV]],
651// CHECK-NEXT: [[DIV:%.+]] = sdiv i{{[0-9]+}} [[C_VAL]], 1
652// CHECK-NEXT: store i{{[0-9]+}} [[DIV]], i{{[0-9]+}}* [[C_PRIV]],
653// CHECK: call i32 @__kmpc_reduce_nowait(
654// CHECK: ret void
655
Alexey Bataev2377fe92015-09-10 08:12:02 +0000656// CHECK: define internal void [[TMAIN_MICROTASK]](i{{[0-9]+}}* noalias [[GTID_ADDR:%.+]], i{{[0-9]+}}* noalias %{{.+}},
Alexey Bataev1d7f0fa2015-09-10 09:48:30 +0000657// CHECK: [[T_VAR_PRIV:%.+]] = alloca i{{[0-9]+}}, align 128
658// CHECK: [[VAR_PRIV:%.+]] = alloca [[S_INT_TY]], align 128
659// CHECK: [[VAR1_PRIV:%.+]] = alloca [[S_INT_TY]], align 128
660// CHECK: [[T_VAR1_PRIV:%.+]] = alloca i{{[0-9]+}}, align 128
Alexey Bataev794ba0d2015-04-10 10:43:45 +0000661
662// Reduction list for runtime.
663// CHECK: [[RED_LIST:%.+]] = alloca [4 x i8*],
664
665// CHECK: store i{{[0-9]+}}* [[GTID_ADDR]], i{{[0-9]+}}** [[GTID_ADDR_ADDR:%.+]],
666
Alexey Bataev2377fe92015-09-10 08:12:02 +0000667// CHECK: [[T_VAR_REF:%.+]] = load i{{[0-9]+}}*, i{{[0-9]+}}** %
668// CHECK: [[VAR_REF:%.+]] = load [[S_INT_TY]]*, [[S_INT_TY]]** %
669// CHECK: [[VAR1_REF:%.+]] = load [[S_INT_TY]]*, [[S_INT_TY]]** %
670// CHECK: [[T_VAR1_REF:%.+]] = load i{{[0-9]+}}*, i{{[0-9]+}}** %
671
Alexey Bataev794ba0d2015-04-10 10:43:45 +0000672// For + reduction operation initial value of private variable is 0.
673// CHECK: store i{{[0-9]+}} 0, i{{[0-9]+}}* [[T_VAR_PRIV]],
674
Alexey Bataev794ba0d2015-04-10 10:43:45 +0000675// For & reduction operation initial value of private variable is ones in all bits.
676// CHECK: call {{.*}} [[S_INT_TY_CONSTR:@.+]]([[S_INT_TY]]* [[VAR_PRIV]])
677
Alexey Bataev794ba0d2015-04-10 10:43:45 +0000678// For && reduction operation initial value of private variable is 1.0.
679// CHECK: call {{.*}} [[S_INT_TY_CONSTR:@.+]]([[S_INT_TY]]* [[VAR1_PRIV]])
680
Alexey Bataev794ba0d2015-04-10 10:43:45 +0000681// For min reduction operation initial value of private variable is largest repesentable value.
682// CHECK: store i{{[0-9]+}} 2147483647, i{{[0-9]+}}* [[T_VAR1_PRIV]],
683
Alexey Bataev794ba0d2015-04-10 10:43:45 +0000684// Skip checks for internal operations.
685
686// void *RedList[<n>] = {<ReductionVars>[0], ..., <ReductionVars>[<n>-1]};
687
John McCall7f416cc2015-09-08 08:05:57 +0000688// CHECK: [[T_VAR_PRIV_REF:%.+]] = getelementptr inbounds [4 x i8*], [4 x i8*]* [[RED_LIST]], i64 0, i64 0
Alexey Bataev794ba0d2015-04-10 10:43:45 +0000689// CHECK: [[BITCAST:%.+]] = bitcast i{{[0-9]+}}* [[T_VAR_PRIV]] to i8*
690// CHECK: store i8* [[BITCAST]], i8** [[T_VAR_PRIV_REF]],
John McCall7f416cc2015-09-08 08:05:57 +0000691// CHECK: [[VAR_PRIV_REF:%.+]] = getelementptr inbounds [4 x i8*], [4 x i8*]* [[RED_LIST]], i64 0, i64 1
Alexey Bataev794ba0d2015-04-10 10:43:45 +0000692// CHECK: [[BITCAST:%.+]] = bitcast [[S_INT_TY]]* [[VAR_PRIV]] to i8*
693// CHECK: store i8* [[BITCAST]], i8** [[VAR_PRIV_REF]],
John McCall7f416cc2015-09-08 08:05:57 +0000694// CHECK: [[VAR1_PRIV_REF:%.+]] = getelementptr inbounds [4 x i8*], [4 x i8*]* [[RED_LIST]], i64 0, i64 2
Alexey Bataev794ba0d2015-04-10 10:43:45 +0000695// CHECK: [[BITCAST:%.+]] = bitcast [[S_INT_TY]]* [[VAR1_PRIV]] to i8*
696// CHECK: store i8* [[BITCAST]], i8** [[VAR1_PRIV_REF]],
John McCall7f416cc2015-09-08 08:05:57 +0000697// CHECK: [[T_VAR1_PRIV_REF:%.+]] = getelementptr inbounds [4 x i8*], [4 x i8*]* [[RED_LIST]], i64 0, i64 3
Alexey Bataev794ba0d2015-04-10 10:43:45 +0000698// CHECK: [[BITCAST:%.+]] = bitcast i{{[0-9]+}}* [[T_VAR1_PRIV]] to i8*
699// CHECK: store i8* [[BITCAST]], i8** [[T_VAR1_PRIV_REF]],
700
701// res = __kmpc_reduce_nowait(<loc>, <gtid>, <n>, sizeof(RedList), RedList, reduce_func, &<lock>);
702
Alexey Bataev69c62a92015-04-15 04:52:20 +0000703// CHECK: [[GTID_REF:%.+]] = load i{{[0-9]+}}*, i{{[0-9]+}}** [[GTID_ADDR_ADDR]]
704// CHECK: [[GTID:%.+]] = load i{{[0-9]+}}, i{{[0-9]+}}* [[GTID_REF]]
Alexey Bataev794ba0d2015-04-10 10:43:45 +0000705// CHECK: [[BITCAST:%.+]] = bitcast [4 x i8*]* [[RED_LIST]] to i8*
706// CHECK: [[RES:%.+]] = call i32 @__kmpc_reduce_nowait(%{{.+}}* [[REDUCTION_LOC]], i32 [[GTID]], i32 4, i64 32, i8* [[BITCAST]], void (i8*, i8*)* [[REDUCTION_FUNC:@.+]], [8 x i32]* [[REDUCTION_LOCK]])
707
708// switch(res)
709// CHECK: switch i32 [[RES]], label %[[RED_DONE:.+]] [
710// CHECK: i32 1, label %[[CASE1:.+]]
711// CHECK: i32 2, label %[[CASE2:.+]]
712// CHECK: ]
713
714// case 1:
715// t_var += t_var_reduction;
716// CHECK: [[T_VAR_VAL:%.+]] = load i{{[0-9]+}}, i{{[0-9]+}}* [[T_VAR_REF]],
717// CHECK: [[T_VAR_PRIV_VAL:%.+]] = load i{{[0-9]+}}, i{{[0-9]+}}* [[T_VAR_PRIV]],
718// CHECK: [[UP:%.+]] = add nsw i{{[0-9]+}} [[T_VAR_VAL]], [[T_VAR_PRIV_VAL]]
719// CHECK: store i{{[0-9]+}} [[UP]], i{{[0-9]+}}* [[T_VAR_REF]],
720
721// var = var.operator &(var_reduction);
722// CHECK: [[UP:%.+]] = call dereferenceable(4) [[S_INT_TY]]* @{{.+}}([[S_INT_TY]]* [[VAR_REF]], [[S_INT_TY]]* dereferenceable(4) [[VAR_PRIV]])
723// CHECK: [[BC1:%.+]] = bitcast [[S_INT_TY]]* [[VAR_REF]] to i8*
724// CHECK: [[BC2:%.+]] = bitcast [[S_INT_TY]]* [[UP]] to i8*
Pete Cooper3b39e882015-11-19 05:55:59 +0000725// CHECK: call void @llvm.memcpy.p0i8.p0i8.i64(i8* [[BC1]], i8* [[BC2]], i64 4, i32 4, i1 false)
Alexey Bataev794ba0d2015-04-10 10:43:45 +0000726
727// var1 = var1.operator &&(var1_reduction);
728// CHECK: [[TO_INT:%.+]] = call i{{[0-9]+}} @{{.+}}([[S_INT_TY]]* [[VAR1_REF]])
729// CHECK: [[VAR1_BOOL:%.+]] = icmp ne i{{[0-9]+}} [[TO_INT]], 0
Alexey Bataev69a47792015-05-07 03:54:03 +0000730// CHECK: br i1 [[VAR1_BOOL]], label %[[TRUE:.+]], label %[[END2:.+]]
Alexey Bataev794ba0d2015-04-10 10:43:45 +0000731// CHECK: [[TRUE]]
732// CHECK: [[TO_INT:%.+]] = call i{{[0-9]+}} @{{.+}}([[S_INT_TY]]* [[VAR1_PRIV]])
733// CHECK: [[VAR1_REDUCTION_BOOL:%.+]] = icmp ne i{{[0-9]+}} [[TO_INT]], 0
Alexey Bataev794ba0d2015-04-10 10:43:45 +0000734// CHECK: [[END2]]
Alexey Bataev69a47792015-05-07 03:54:03 +0000735// CHECK: [[COND_LVALUE:%.+]] = phi i1 [ false, %{{.+}} ], [ [[VAR1_REDUCTION_BOOL]], %[[TRUE]] ]
736// CHECK: [[CONV:%.+]] = zext i1 [[COND_LVALUE]] to i32
737// CHECK: call void @{{.+}}([[S_INT_TY]]* [[COND_LVALUE:%.+]], i32 [[CONV]])
Alexey Bataev794ba0d2015-04-10 10:43:45 +0000738// CHECK: [[BC1:%.+]] = bitcast [[S_INT_TY]]* [[VAR1_REF]] to i8*
739// CHECK: [[BC2:%.+]] = bitcast [[S_INT_TY]]* [[COND_LVALUE]] to i8*
Pete Cooper3b39e882015-11-19 05:55:59 +0000740// CHECK: call void @llvm.memcpy.p0i8.p0i8.i64(i8* [[BC1]], i8* [[BC2]], i64 4, i32 4, i1 false)
Alexey Bataev794ba0d2015-04-10 10:43:45 +0000741
742// t_var1 = min(t_var1, t_var1_reduction);
743// CHECK: [[T_VAR1_VAL:%.+]] = load i{{[0-9]+}}, i{{[0-9]+}}* [[T_VAR1_REF]],
744// CHECK: [[T_VAR1_PRIV_VAL:%.+]] = load i{{[0-9]+}}, i{{[0-9]+}}* [[T_VAR1_PRIV]],
745// CHECK: [[CMP:%.+]] = icmp slt i{{[0-9]+}} [[T_VAR1_VAL]], [[T_VAR1_PRIV_VAL]]
Alexey Bataev69a47792015-05-07 03:54:03 +0000746// CHECK: br i1 [[CMP]]
747// CHECK: [[UP:%.+]] = phi i32
Alexey Bataev794ba0d2015-04-10 10:43:45 +0000748// CHECK: store i{{[0-9]+}} [[UP]], i{{[0-9]+}}* [[T_VAR1_REF]],
749
750// __kmpc_end_reduce_nowait(<loc>, <gtid>, &<lock>);
751// CHECK: call void @__kmpc_end_reduce_nowait(%{{.+}}* [[REDUCTION_LOC]], i32 [[GTID]], [8 x i32]* [[REDUCTION_LOCK]])
752
753// break;
754// CHECK: br label %[[RED_DONE]]
755
756// case 2:
757// t_var += t_var_reduction;
758// CHECK: [[T_VAR_PRIV_VAL:%.+]] = load i{{[0-9]+}}, i{{[0-9]+}}* [[T_VAR_PRIV]]
759// CHECK: atomicrmw add i32* [[T_VAR_REF]], i32 [[T_VAR_PRIV_VAL]] monotonic
760
761// var = var.operator &(var_reduction);
762// CHECK: call void @__kmpc_critical(
763// CHECK: [[UP:%.+]] = call dereferenceable(4) [[S_INT_TY]]* @{{.+}}([[S_INT_TY]]* [[VAR_REF]], [[S_INT_TY]]* dereferenceable(4) [[VAR_PRIV]])
764// CHECK: [[BC1:%.+]] = bitcast [[S_INT_TY]]* [[VAR_REF]] to i8*
765// CHECK: [[BC2:%.+]] = bitcast [[S_INT_TY]]* [[UP]] to i8*
Pete Cooper3b39e882015-11-19 05:55:59 +0000766// CHECK: call void @llvm.memcpy.p0i8.p0i8.i64(i8* [[BC1]], i8* [[BC2]], i64 4, i32 4, i1 false)
Alexey Bataev794ba0d2015-04-10 10:43:45 +0000767// CHECK: call void @__kmpc_end_critical(
768
769// var1 = var1.operator &&(var1_reduction);
770// CHECK: call void @__kmpc_critical(
771// CHECK: [[TO_INT:%.+]] = call i{{[0-9]+}} @{{.+}}([[S_INT_TY]]* [[VAR1_REF]])
772// CHECK: [[VAR1_BOOL:%.+]] = icmp ne i{{[0-9]+}} [[TO_INT]], 0
Alexey Bataev69a47792015-05-07 03:54:03 +0000773// CHECK: br i1 [[VAR1_BOOL]], label %[[TRUE:.+]], label %[[END2:.+]]
Alexey Bataev794ba0d2015-04-10 10:43:45 +0000774// CHECK: [[TRUE]]
775// CHECK: [[TO_INT:%.+]] = call i{{[0-9]+}} @{{.+}}([[S_INT_TY]]* [[VAR1_PRIV]])
776// CHECK: [[VAR1_REDUCTION_BOOL:%.+]] = icmp ne i{{[0-9]+}} [[TO_INT]], 0
Alexey Bataev794ba0d2015-04-10 10:43:45 +0000777// CHECK: br label %[[END2]]
778// CHECK: [[END2]]
Alexey Bataev69a47792015-05-07 03:54:03 +0000779// CHECK: [[COND_LVALUE:%.+]] = phi i1 [ false, %{{.+}} ], [ [[VAR1_REDUCTION_BOOL]], %[[TRUE]] ]
780// CHECK: [[CONV:%.+]] = zext i1 [[COND_LVALUE]] to i32
781// CHECK: call void @{{.+}}([[S_INT_TY]]* [[COND_LVALUE:%.+]], i32 [[CONV]])
Alexey Bataev794ba0d2015-04-10 10:43:45 +0000782// CHECK: [[BC1:%.+]] = bitcast [[S_INT_TY]]* [[VAR1_REF]] to i8*
783// CHECK: [[BC2:%.+]] = bitcast [[S_INT_TY]]* [[COND_LVALUE]] to i8*
Pete Cooper3b39e882015-11-19 05:55:59 +0000784// CHECK: call void @llvm.memcpy.p0i8.p0i8.i64(i8* [[BC1]], i8* [[BC2]], i64 4, i32 4, i1 false)
Alexey Bataev794ba0d2015-04-10 10:43:45 +0000785// CHECK: call void @__kmpc_end_critical(
786
787// t_var1 = min(t_var1, t_var1_reduction);
788// CHECK: [[T_VAR1_PRIV_VAL:%.+]] = load i{{[0-9]+}}, i{{[0-9]+}}* [[T_VAR1_PRIV]]
789// CHECK: atomicrmw min i32* [[T_VAR1_REF]], i32 [[T_VAR1_PRIV_VAL]] monotonic
790
791// break;
792// CHECK: br label %[[RED_DONE]]
793// CHECK: [[RED_DONE]]
Alexey Bataev794ba0d2015-04-10 10:43:45 +0000794
795// CHECK-DAG: call {{.*}} [[S_INT_TY_DESTR]]([[S_INT_TY]]* [[VAR_PRIV]])
796// CHECK-DAG: call {{.*}} [[S_INT_TY_DESTR]]([[S_INT_TY]]*
797// CHECK: ret void
798
799// void reduce_func(void *lhs[<n>], void *rhs[<n>]) {
800// *(Type0*)lhs[0] = ReductionOperation0(*(Type0*)lhs[0], *(Type0*)rhs[0]);
801// ...
802// *(Type<n>-1*)lhs[<n>-1] = ReductionOperation<n>-1(*(Type<n>-1*)lhs[<n>-1],
803// *(Type<n>-1*)rhs[<n>-1]);
804// }
805// CHECK: define internal void [[REDUCTION_FUNC]](i8*, i8*)
806// t_var_lhs = (i{{[0-9]+}}*)lhs[0];
John McCall7f416cc2015-09-08 08:05:57 +0000807// CHECK: [[T_VAR_RHS_REF:%.+]] = getelementptr inbounds [4 x i8*], [4 x i8*]* [[RED_LIST_RHS:%.+]], i64 0, i64 0
Alexey Bataev794ba0d2015-04-10 10:43:45 +0000808// CHECK: [[T_VAR_RHS_VOID:%.+]] = load i8*, i8** [[T_VAR_RHS_REF]],
809// CHECK: [[T_VAR_RHS:%.+]] = bitcast i8* [[T_VAR_RHS_VOID]] to i{{[0-9]+}}*
810// t_var_rhs = (i{{[0-9]+}}*)rhs[0];
John McCall7f416cc2015-09-08 08:05:57 +0000811// CHECK: [[T_VAR_LHS_REF:%.+]] = getelementptr inbounds [4 x i8*], [4 x i8*]* [[RED_LIST_LHS:%.+]], i64 0, i64 0
Alexey Bataev794ba0d2015-04-10 10:43:45 +0000812// CHECK: [[T_VAR_LHS_VOID:%.+]] = load i8*, i8** [[T_VAR_LHS_REF]],
813// CHECK: [[T_VAR_LHS:%.+]] = bitcast i8* [[T_VAR_LHS_VOID]] to i{{[0-9]+}}*
814
815// var_lhs = (S<i{{[0-9]+}}>*)lhs[1];
John McCall7f416cc2015-09-08 08:05:57 +0000816// CHECK: [[VAR_RHS_REF:%.+]] = getelementptr inbounds [4 x i8*], [4 x i8*]* [[RED_LIST_RHS]], i64 0, i64 1
Alexey Bataev794ba0d2015-04-10 10:43:45 +0000817// CHECK: [[VAR_RHS_VOID:%.+]] = load i8*, i8** [[VAR_RHS_REF]],
818// CHECK: [[VAR_RHS:%.+]] = bitcast i8* [[VAR_RHS_VOID]] to [[S_INT_TY]]*
819// var_rhs = (S<i{{[0-9]+}}>*)rhs[1];
John McCall7f416cc2015-09-08 08:05:57 +0000820// CHECK: [[VAR_LHS_REF:%.+]] = getelementptr inbounds [4 x i8*], [4 x i8*]* [[RED_LIST_LHS]], i64 0, i64 1
Alexey Bataev794ba0d2015-04-10 10:43:45 +0000821// CHECK: [[VAR_LHS_VOID:%.+]] = load i8*, i8** [[VAR_LHS_REF]],
822// CHECK: [[VAR_LHS:%.+]] = bitcast i8* [[VAR_LHS_VOID]] to [[S_INT_TY]]*
823
824// var1_lhs = (S<i{{[0-9]+}}>*)lhs[2];
John McCall7f416cc2015-09-08 08:05:57 +0000825// CHECK: [[VAR1_RHS_REF:%.+]] = getelementptr inbounds [4 x i8*], [4 x i8*]* [[RED_LIST_RHS]], i64 0, i64 2
Alexey Bataev794ba0d2015-04-10 10:43:45 +0000826// CHECK: [[VAR1_RHS_VOID:%.+]] = load i8*, i8** [[VAR1_RHS_REF]],
827// CHECK: [[VAR1_RHS:%.+]] = bitcast i8* [[VAR1_RHS_VOID]] to [[S_INT_TY]]*
828// var1_rhs = (S<i{{[0-9]+}}>*)rhs[2];
John McCall7f416cc2015-09-08 08:05:57 +0000829// CHECK: [[VAR1_LHS_REF:%.+]] = getelementptr inbounds [4 x i8*], [4 x i8*]* [[RED_LIST_LHS]], i64 0, i64 2
Alexey Bataev794ba0d2015-04-10 10:43:45 +0000830// CHECK: [[VAR1_LHS_VOID:%.+]] = load i8*, i8** [[VAR1_LHS_REF]],
831// CHECK: [[VAR1_LHS:%.+]] = bitcast i8* [[VAR1_LHS_VOID]] to [[S_INT_TY]]*
832
833// t_var1_lhs = (i{{[0-9]+}}*)lhs[3];
John McCall7f416cc2015-09-08 08:05:57 +0000834// CHECK: [[T_VAR1_RHS_REF:%.+]] = getelementptr inbounds [4 x i8*], [4 x i8*]* [[RED_LIST_RHS]], i64 0, i64 3
Alexey Bataev794ba0d2015-04-10 10:43:45 +0000835// CHECK: [[T_VAR1_RHS_VOID:%.+]] = load i8*, i8** [[T_VAR1_RHS_REF]],
836// CHECK: [[T_VAR1_RHS:%.+]] = bitcast i8* [[T_VAR1_RHS_VOID]] to i{{[0-9]+}}*
837// t_var1_rhs = (i{{[0-9]+}}*)rhs[3];
John McCall7f416cc2015-09-08 08:05:57 +0000838// CHECK: [[T_VAR1_LHS_REF:%.+]] = getelementptr inbounds [4 x i8*], [4 x i8*]* [[RED_LIST_LHS]], i64 0, i64 3
Alexey Bataev794ba0d2015-04-10 10:43:45 +0000839// CHECK: [[T_VAR1_LHS_VOID:%.+]] = load i8*, i8** [[T_VAR1_LHS_REF]],
840// CHECK: [[T_VAR1_LHS:%.+]] = bitcast i8* [[T_VAR1_LHS_VOID]] to i{{[0-9]+}}*
841
842// t_var_lhs += t_var_rhs;
843// CHECK: [[T_VAR_LHS_VAL:%.+]] = load i{{[0-9]+}}, i{{[0-9]+}}* [[T_VAR_LHS]],
844// CHECK: [[T_VAR_RHS_VAL:%.+]] = load i{{[0-9]+}}, i{{[0-9]+}}* [[T_VAR_RHS]],
845// CHECK: [[UP:%.+]] = add nsw i{{[0-9]+}} [[T_VAR_LHS_VAL]], [[T_VAR_RHS_VAL]]
846// CHECK: store i{{[0-9]+}} [[UP]], i{{[0-9]+}}* [[T_VAR_LHS]],
847
848// var_lhs = var_lhs.operator &(var_rhs);
849// CHECK: [[UP:%.+]] = call dereferenceable(4) [[S_INT_TY]]* @{{.+}}([[S_INT_TY]]* [[VAR_LHS]], [[S_INT_TY]]* dereferenceable(4) [[VAR_RHS]])
850// CHECK: [[BC1:%.+]] = bitcast [[S_INT_TY]]* [[VAR_LHS]] to i8*
851// CHECK: [[BC2:%.+]] = bitcast [[S_INT_TY]]* [[UP]] to i8*
Pete Cooper3b39e882015-11-19 05:55:59 +0000852// CHECK: call void @llvm.memcpy.p0i8.p0i8.i64(i8* [[BC1]], i8* [[BC2]], i64 4, i32 4, i1 false)
Alexey Bataev794ba0d2015-04-10 10:43:45 +0000853
854// var1_lhs = var1_lhs.operator &&(var1_rhs);
855// CHECK: [[TO_INT:%.+]] = call i{{[0-9]+}} @{{.+}}([[S_INT_TY]]* [[VAR1_LHS]])
856// CHECK: [[VAR1_BOOL:%.+]] = icmp ne i{{[0-9]+}} [[TO_INT]], 0
Alexey Bataev69a47792015-05-07 03:54:03 +0000857// CHECK: br i1 [[VAR1_BOOL]], label %[[TRUE:.+]], label %[[END2:.+]]
Alexey Bataev794ba0d2015-04-10 10:43:45 +0000858// CHECK: [[TRUE]]
859// CHECK: [[TO_INT:%.+]] = call i{{[0-9]+}} @{{.+}}([[S_INT_TY]]* [[VAR1_RHS]])
860// CHECK: [[VAR1_REDUCTION_BOOL:%.+]] = icmp ne i{{[0-9]+}} [[TO_INT]], 0
Alexey Bataev794ba0d2015-04-10 10:43:45 +0000861// CHECK: br label %[[END2]]
862// CHECK: [[END2]]
Alexey Bataev69a47792015-05-07 03:54:03 +0000863// CHECK: [[COND_LVALUE:%.+]] = phi i1 [ false, %{{.+}} ], [ [[VAR1_REDUCTION_BOOL]], %[[TRUE]] ]
864// CHECK: [[CONV:%.+]] = zext i1 [[COND_LVALUE]] to i32
865// CHECK: call void @{{.+}}([[S_INT_TY]]* [[COND_LVALUE:%.+]], i32 [[CONV]])
Alexey Bataev794ba0d2015-04-10 10:43:45 +0000866// CHECK: [[BC1:%.+]] = bitcast [[S_INT_TY]]* [[VAR1_LHS]] to i8*
867// CHECK: [[BC2:%.+]] = bitcast [[S_INT_TY]]* [[COND_LVALUE]] to i8*
Pete Cooper3b39e882015-11-19 05:55:59 +0000868// CHECK: call void @llvm.memcpy.p0i8.p0i8.i64(i8* [[BC1]], i8* [[BC2]], i64 4, i32 4, i1 false)
Alexey Bataev794ba0d2015-04-10 10:43:45 +0000869
870// t_var1_lhs = min(t_var1_lhs, t_var1_rhs);
871// CHECK: [[T_VAR1_LHS_VAL:%.+]] = load i{{[0-9]+}}, i{{[0-9]+}}* [[T_VAR1_LHS]],
872// CHECK: [[T_VAR1_RHS_VAL:%.+]] = load i{{[0-9]+}}, i{{[0-9]+}}* [[T_VAR1_RHS]],
873// CHECK: [[CMP:%.+]] = icmp slt i{{[0-9]+}} [[T_VAR1_LHS_VAL]], [[T_VAR1_RHS_VAL]]
Alexey Bataev69a47792015-05-07 03:54:03 +0000874// CHECK: br i1 [[CMP]]
875// CHECK: [[UP:%.+]] = phi i32
Alexey Bataev794ba0d2015-04-10 10:43:45 +0000876// CHECK: store i{{[0-9]+}} [[UP]], i{{[0-9]+}}* [[T_VAR1_LHS]],
877// CHECK: ret void
878
879#endif
880