1 // RUN: %clang_cc1 -verify -fopenmp -x c++ -triple x86_64-unknown-unknown -emit-llvm %s -o - | FileCheck %s
2 // RUN: %clang_cc1 -fopenmp -x c++ -std=c++11 -triple x86_64-unknown-unknown -emit-pch -o %t %s
3 // RUN: %clang_cc1 -fopenmp -x c++ -triple x86_64-unknown-unknown -std=c++11 -include-pch %t -verify %s -emit-llvm -o - | FileCheck %s
4
5 // RUN: %clang_cc1 -verify -fopenmp-simd -x c++ -triple x86_64-unknown-unknown -emit-llvm %s -o - | FileCheck --check-prefix SIMD-ONLY0 %s
6 // RUN: %clang_cc1 -fopenmp-simd -x c++ -std=c++11 -triple x86_64-unknown-unknown -emit-pch -o %t %s
7 // RUN: %clang_cc1 -fopenmp-simd -x c++ -triple x86_64-unknown-unknown -std=c++11 -include-pch %t -verify %s -emit-llvm -o - | FileCheck --check-prefix SIMD-ONLY0 %s
8 // SIMD-ONLY0-NOT: {{__kmpc|__tgt}}
9 // expected-no-diagnostics
10 #ifndef HEADER
11 #define HEADER
12
13 void foo();
14 void bar();
15
16 // CHECK: define{{.*}} void @{{.*}}baz{{.*}}(i32 %n)
baz(int n)17 void baz(int n) {
18 static float a[10];
19 static double b;
20
21 // CHECK: call i8* @llvm.stacksave()
22 // CHECK: [[A_BUF_SIZE:%.+]] = mul nuw i64 10, [[NUM_ELEMS:%[^,]+]]
23
24 // float a_buffer[10][n];
25 // CHECK: [[A_BUF:%.+]] = alloca float, i64 [[A_BUF_SIZE]],
26 // CHECK: [[B_BUF:%.+]] = alloca double, i64 10,
27
28 // CHECK: call void (%struct.ident_t*, i32, void (i32*, i32*, ...)*, ...) @__kmpc_fork_call(
29
30 // CHECK: [[A_BUF_SIZE:%.+]] = mul nuw i64 10, [[NUM_ELEMS:%[^,]+]]
31
32 // float a_buffer[10][n];
33 // CHECK: [[A_BUF:%.+]] = alloca float, i64 [[A_BUF_SIZE]],
34
35 // double b_buffer[10];
36 // CHECK: [[B_BUF:%.+]] = alloca double, i64 10,
37 // CHECK: call void (%struct.ident_t*, i32, void (i32*, i32*, ...)*, ...) @__kmpc_fork_call(
38 // CHECK: call void @llvm.stackrestore(i8*
39
40 #pragma omp parallel for simd reduction(inscan, +:a[:n], b)
41 for (int i = 0; i < 10; ++i) {
42 // CHECK: call void @__kmpc_for_static_init_4(
43 // CHECK: call i8* @llvm.stacksave()
44 // CHECK: store float 0.000000e+00, float* %
45 // CHECK: store double 0.000000e+00, double* [[B_PRIV_ADDR:%.+]],
46 // CHECK: br label %[[DISPATCH:[^,]+]]
47 // CHECK: [[INPUT_PHASE:.+]]:
48 // CHECK: call void @{{.+}}foo{{.+}}()
49
50 // a_buffer[i][0..n] = a_priv[[0..n];
51 // CHECK: [[BASE_IDX_I:%.+]] = load i32, i32* [[IV_ADDR:%.+]],
52 // CHECK: [[BASE_IDX:%.+]] = zext i32 [[BASE_IDX_I]] to i64
53 // CHECK: [[IDX:%.+]] = mul nsw i64 [[BASE_IDX]], [[NUM_ELEMS:%.+]]
54 // CHECK: [[A_BUF_IDX:%.+]] = getelementptr inbounds float, float* [[A_BUF:%.+]], i64 [[IDX]]
55 // CHECK: [[A_PRIV:%.+]] = getelementptr inbounds [10 x float], [10 x float]* [[A_PRIV_ADDR:%.+]], i64 0, i64 0
56 // CHECK: [[BYTES:%.+]] = mul nuw i64 [[NUM_ELEMS:%.+]], 4
57 // CHECK: [[DEST:%.+]] = bitcast float* [[A_BUF_IDX]] to i8*
58 // CHECK: [[SRC:%.+]] = bitcast float* [[A_PRIV]] to i8*
59 // CHECK: call void @llvm.memcpy.p0i8.p0i8.i64(i8* {{.*}}[[DEST]], i8* {{.*}}[[SRC]], i64 [[BYTES]], i1 false)
60
61 // b_buffer[i] = b_priv;
62 // CHECK: [[B_BUF_IDX:%.+]] = getelementptr inbounds double, double* [[B_BUF:%.+]], i64 [[BASE_IDX]]
63 // CHECK: [[B_PRIV:%.+]] = load double, double* [[B_PRIV_ADDR]],
64 // CHECK: store double [[B_PRIV]], double* [[B_BUF_IDX]],
65 // CHECK: br label %[[LOOP_CONTINUE:.+]]
66
67 // CHECK: [[DISPATCH]]:
68 // CHECK: br label %[[INPUT_PHASE]]
69 // CHECK: [[LOOP_CONTINUE]]:
70 // CHECK: call void @llvm.stackrestore(i8* %
71 // CHECK: call void @__kmpc_for_static_fini(
72 // CHECK: call void @__kmpc_barrier(
73 foo();
74 #pragma omp scan inclusive(a[:n], b)
75 // CHECK: [[LOG2_10:%.+]] = call double @llvm.log2.f64(double 1.000000e+01)
76 // CHECK: [[CEIL_LOG2_10:%.+]] = call double @llvm.ceil.f64(double [[LOG2_10]])
77 // CHECK: [[CEIL_LOG2_10_INT:%.+]] = fptoui double [[CEIL_LOG2_10]] to i32
78 // CHECK: br label %[[OUTER_BODY:[^,]+]]
79 // CHECK: [[OUTER_BODY]]:
80 // CHECK: [[K:%.+]] = phi i32 [ 0, %{{.+}} ], [ [[K_NEXT:%.+]], %{{.+}} ]
81 // CHECK: [[K2POW:%.+]] = phi i64 [ 1, %{{.+}} ], [ [[K2POW_NEXT:%.+]], %{{.+}} ]
82 // CHECK: [[CMP:%.+]] = icmp uge i64 9, [[K2POW]]
83 // CHECK: br i1 [[CMP]], label %[[INNER_BODY:[^,]+]], label %[[INNER_EXIT:[^,]+]]
84 // CHECK: [[INNER_BODY]]:
85 // CHECK: [[I:%.+]] = phi i64 [ 9, %[[OUTER_BODY]] ], [ [[I_PREV:%.+]], %{{.+}} ]
86
87 // a_buffer[i] += a_buffer[i-pow(2, k)];
88 // CHECK: [[IDX:%.+]] = mul nsw i64 [[I]], [[NUM_ELEMS]]
89 // CHECK: [[A_BUF_IDX:%.+]] = getelementptr inbounds float, float* [[A_BUF]], i64 [[IDX]]
90 // CHECK: [[IDX_SUB_K2POW:%.+]] = sub nuw i64 [[I]], [[K2POW]]
91 // CHECK: [[IDX:%.+]] = mul nsw i64 [[IDX_SUB_K2POW]], [[NUM_ELEMS]]
92 // CHECK: [[A_BUF_IDX_SUB_K2POW:%.+]] = getelementptr inbounds float, float* [[A_BUF]], i64 [[IDX]]
93 // CHECK: [[B_BUF_IDX:%.+]] = getelementptr inbounds double, double* [[B_BUF]], i64 [[I]]
94 // CHECK: [[IDX_SUB_K2POW:%.+]] = sub nuw i64 [[I]], [[K2POW]]
95 // CHECK: [[B_BUF_IDX_SUB_K2POW:%.+]] = getelementptr inbounds double, double* [[B_BUF]], i64 [[IDX_SUB_K2POW]]
96 // CHECK: [[A_BUF_END:%.+]] = getelementptr float, float* [[A_BUF_IDX]], i64 [[NUM_ELEMS]]
97 // CHECK: [[ISEMPTY:%.+]] = icmp eq float* [[A_BUF_IDX]], [[A_BUF_END]]
98 // CHECK: br i1 [[ISEMPTY]], label %[[RED_DONE:[^,]+]], label %[[RED_BODY:[^,]+]]
99 // CHECK: [[RED_BODY]]:
100 // CHECK: [[A_BUF_IDX_SUB_K2POW_ELEM:%.+]] = phi float* [ [[A_BUF_IDX_SUB_K2POW]], %[[INNER_BODY]] ], [ [[A_BUF_IDX_SUB_K2POW_NEXT:%.+]], %[[RED_BODY]] ]
101 // CHECK: [[A_BUF_IDX_ELEM:%.+]] = phi float* [ [[A_BUF_IDX]], %[[INNER_BODY]] ], [ [[A_BUF_IDX_NEXT:%.+]], %[[RED_BODY]] ]
102 // CHECK: [[A_BUF_IDX_VAL:%.+]] = load float, float* [[A_BUF_IDX_ELEM]],
103 // CHECK: [[A_BUF_IDX_SUB_K2POW_VAL:%.+]] = load float, float* [[A_BUF_IDX_SUB_K2POW_ELEM]],
104 // CHECK: [[RED:%.+]] = fadd float [[A_BUF_IDX_VAL]], [[A_BUF_IDX_SUB_K2POW_VAL]]
105 // CHECK: store float [[RED]], float* [[A_BUF_IDX_ELEM]],
106 // CHECK: [[A_BUF_IDX_NEXT]] = getelementptr float, float* [[A_BUF_IDX_ELEM]], i32 1
107 // CHECK: [[A_BUF_IDX_SUB_K2POW_NEXT]] = getelementptr float, float* [[A_BUF_IDX_SUB_K2POW_ELEM]], i32 1
108 // CHECK: [[DONE:%.+]] = icmp eq float* [[A_BUF_IDX_NEXT]], [[A_BUF_END]]
109 // CHECK: br i1 [[DONE]], label %[[RED_DONE]], label %[[RED_BODY]]
110 // CHECK: [[RED_DONE]]:
111
112 // b_buffer[i] += b_buffer[i-pow(2, k)];
113 // CHECK: [[B_BUF_IDX_VAL:%.+]] = load double, double* [[B_BUF_IDX]],
114 // CHECK: [[B_BUF_IDX_SUB_K2POW_VAL:%.+]] = load double, double* [[B_BUF_IDX_SUB_K2POW]],
115 // CHECK: [[RED:%.+]] = fadd double [[B_BUF_IDX_VAL]], [[B_BUF_IDX_SUB_K2POW_VAL]]
116 // CHECK: store double [[RED]], double* [[B_BUF_IDX]],
117
118 // --i;
119 // CHECK: [[I_PREV:%.+]] = sub nuw i64 [[I]], 1
120 // CHECK: [[CMP:%.+]] = icmp uge i64 [[I_PREV]], [[K2POW]]
121 // CHECK: br i1 [[CMP]], label %[[INNER_BODY]], label %[[INNER_EXIT]]
122 // CHECK: [[INNER_EXIT]]:
123
124 // ++k;
125 // CHECK: [[K_NEXT]] = add nuw i32 [[K]], 1
126 // k2pow <<= 1;
127 // CHECK: [[K2POW_NEXT]] = shl nuw i64 [[K2POW]], 1
128 // CHECK: [[CMP:%.+]] = icmp ne i32 [[K_NEXT]], [[CEIL_LOG2_10_INT]]
129 // CHECK: br i1 [[CMP]], label %[[OUTER_BODY]], label %[[OUTER_EXIT:[^,]+]]
130 // CHECK: [[OUTER_EXIT]]:
131 bar();
132 // CHECK: call void @__kmpc_for_static_init_4(
133 // CHECK: call i8* @llvm.stacksave()
134 // CHECK: store float 0.000000e+00, float* %
135 // CHECK: store double 0.000000e+00, double* [[B_PRIV_ADDR:%.+]],
136 // CHECK: br label %[[DISPATCH:[^,]+]]
137
138 // Skip the before scan body.
139 // CHECK: call void @{{.+}}foo{{.+}}()
140
141 // CHECK: [[EXIT_INSCAN:[^,]+]]:
142 // CHECK: br label %[[LOOP_CONTINUE:[^,]+]]
143
144 // CHECK: [[DISPATCH]]:
145 // a_priv[[0..n] = a_buffer[i][0..n];
146 // CHECK: [[BASE_IDX_I:%.+]] = load i32, i32* [[IV_ADDR:%.+]],
147 // CHECK: [[BASE_IDX:%.+]] = zext i32 [[BASE_IDX_I]] to i64
148 // CHECK: [[IDX:%.+]] = mul nsw i64 [[BASE_IDX]], [[NUM_ELEMS]]
149 // CHECK: [[A_BUF_IDX:%.+]] = getelementptr inbounds float, float* [[A_BUF]], i64 [[IDX]]
150 // CHECK: [[A_PRIV:%.+]] = getelementptr inbounds [10 x float], [10 x float]* [[A_PRIV_ADDR:%.+]], i64 0, i64 0
151 // CHECK: [[BYTES:%.+]] = mul nuw i64 [[NUM_ELEMS:%.+]], 4
152 // CHECK: [[DEST:%.+]] = bitcast float* [[A_PRIV]] to i8*
153 // CHECK: [[SRC:%.+]] = bitcast float* [[A_BUF_IDX]] to i8*
154 // CHECK: call void @llvm.memcpy.p0i8.p0i8.i64(i8* {{.*}}[[DEST]], i8* {{.*}}[[SRC]], i64 [[BYTES]], i1 false)
155
156 // b_priv = b_buffer[i];
157 // CHECK: [[B_BUF_IDX:%.+]] = getelementptr inbounds double, double* [[B_BUF]], i64 [[BASE_IDX]]
158 // CHECK: [[B_BUF_IDX_VAL:%.+]] = load double, double* [[B_BUF_IDX]],
159 // CHECK: store double [[B_BUF_IDX_VAL]], double* [[B_PRIV_ADDR]],
160 // CHECK: br label %[[SCAN_PHASE:[^,]+]]
161
162 // CHECK: [[SCAN_PHASE]]:
163 // CHECK: call void @{{.+}}bar{{.+}}()
164 // CHECK: br label %[[EXIT_INSCAN]]
165
166 // CHECK: [[LOOP_CONTINUE]]:
167 // CHECK: call void @llvm.stackrestore(i8* %
168 // CHECK: call void @__kmpc_for_static_fini(
169 }
170
171 #pragma omp parallel for simd reduction(inscan, +:a[:n], b)
172 for (int i = 0; i < 10; ++i) {
173 // CHECK: call void @__kmpc_for_static_init_4(
174 // CHECK: call i8* @llvm.stacksave()
175 // CHECK: store float 0.000000e+00, float* %
176 // CHECK: store double 0.000000e+00, double* [[B_PRIV_ADDR:%.+]],
177 // CHECK: br label %[[DISPATCH:[^,]+]]
178
179 // Skip the before scan body.
180 // CHECK: call void @{{.+}}foo{{.+}}()
181
182 // CHECK: [[EXIT_INSCAN:[^,]+]]:
183
184 // a_buffer[i][0..n] = a_priv[[0..n];
185 // CHECK: [[BASE_IDX_I:%.+]] = load i32, i32* [[IV_ADDR:%.+]],
186 // CHECK: [[BASE_IDX:%.+]] = zext i32 [[BASE_IDX_I]] to i64
187 // CHECK: [[IDX:%.+]] = mul nsw i64 [[BASE_IDX]], [[NUM_ELEMS:%.+]]
188 // CHECK: [[A_BUF_IDX:%.+]] = getelementptr inbounds float, float* [[A_BUF:%.+]], i64 [[IDX]]
189 // CHECK: [[A_PRIV:%.+]] = getelementptr inbounds [10 x float], [10 x float]* [[A_PRIV_ADDR:%.+]], i64 0, i64 0
190 // CHECK: [[BYTES:%.+]] = mul nuw i64 [[NUM_ELEMS:%.+]], 4
191 // CHECK: [[DEST:%.+]] = bitcast float* [[A_BUF_IDX]] to i8*
192 // CHECK: [[SRC:%.+]] = bitcast float* [[A_PRIV]] to i8*
193 // CHECK: call void @llvm.memcpy.p0i8.p0i8.i64(i8* {{.*}}[[DEST]], i8* {{.*}}[[SRC]], i64 [[BYTES]], i1 false)
194
195 // b_buffer[i] = b_priv;
196 // CHECK: [[B_BUF_IDX:%.+]] = getelementptr inbounds double, double* [[B_BUF:%.+]], i64 [[BASE_IDX]]
197 // CHECK: [[B_PRIV:%.+]] = load double, double* [[B_PRIV_ADDR]],
198 // CHECK: store double [[B_PRIV]], double* [[B_BUF_IDX]],
199 // CHECK: br label %[[LOOP_CONTINUE:[^,]+]]
200
201 // CHECK: [[DISPATCH]]:
202 // CHECK: br label %[[INPUT_PHASE:[^,]+]]
203
204 // CHECK: [[INPUT_PHASE]]:
205 // CHECK: call void @{{.+}}bar{{.+}}()
206 // CHECK: br label %[[EXIT_INSCAN]]
207
208 // CHECK: [[LOOP_CONTINUE]]:
209 // CHECK: call void @llvm.stackrestore(i8* %
210 // CHECK: call void @__kmpc_for_static_fini(
211 // CHECK: call void @__kmpc_barrier(
212 foo();
213 #pragma omp scan exclusive(a[:n], b)
214 // CHECK: [[LOG2_10:%.+]] = call double @llvm.log2.f64(double 1.000000e+01)
215 // CHECK: [[CEIL_LOG2_10:%.+]] = call double @llvm.ceil.f64(double [[LOG2_10]])
216 // CHECK: [[CEIL_LOG2_10_INT:%.+]] = fptoui double [[CEIL_LOG2_10]] to i32
217 // CHECK: br label %[[OUTER_BODY:[^,]+]]
218 // CHECK: [[OUTER_BODY]]:
219 // CHECK: [[K:%.+]] = phi i32 [ 0, %{{.+}} ], [ [[K_NEXT:%.+]], %{{.+}} ]
220 // CHECK: [[K2POW:%.+]] = phi i64 [ 1, %{{.+}} ], [ [[K2POW_NEXT:%.+]], %{{.+}} ]
221 // CHECK: [[CMP:%.+]] = icmp uge i64 9, [[K2POW]]
222 // CHECK: br i1 [[CMP]], label %[[INNER_BODY:[^,]+]], label %[[INNER_EXIT:[^,]+]]
223 // CHECK: [[INNER_BODY]]:
224 // CHECK: [[I:%.+]] = phi i64 [ 9, %[[OUTER_BODY]] ], [ [[I_PREV:%.+]], %{{.+}} ]
225
226 // a_buffer[i] += a_buffer[i-pow(2, k)];
227 // CHECK: [[IDX:%.+]] = mul nsw i64 [[I]], [[NUM_ELEMS]]
228 // CHECK: [[A_BUF_IDX:%.+]] = getelementptr inbounds float, float* [[A_BUF]], i64 [[IDX]]
229 // CHECK: [[IDX_SUB_K2POW:%.+]] = sub nuw i64 [[I]], [[K2POW]]
230 // CHECK: [[IDX:%.+]] = mul nsw i64 [[IDX_SUB_K2POW]], [[NUM_ELEMS]]
231 // CHECK: [[A_BUF_IDX_SUB_K2POW:%.+]] = getelementptr inbounds float, float* [[A_BUF]], i64 [[IDX]]
232 // CHECK: [[B_BUF_IDX:%.+]] = getelementptr inbounds double, double* [[B_BUF]], i64 [[I]]
233 // CHECK: [[IDX_SUB_K2POW:%.+]] = sub nuw i64 [[I]], [[K2POW]]
234 // CHECK: [[B_BUF_IDX_SUB_K2POW:%.+]] = getelementptr inbounds double, double* [[B_BUF]], i64 [[IDX_SUB_K2POW]]
235 // CHECK: [[A_BUF_END:%.+]] = getelementptr float, float* [[A_BUF_IDX]], i64 [[NUM_ELEMS]]
236 // CHECK: [[ISEMPTY:%.+]] = icmp eq float* [[A_BUF_IDX]], [[A_BUF_END]]
237 // CHECK: br i1 [[ISEMPTY]], label %[[RED_DONE:[^,]+]], label %[[RED_BODY:[^,]+]]
238 // CHECK: [[RED_BODY]]:
239 // CHECK: [[A_BUF_IDX_SUB_K2POW_ELEM:%.+]] = phi float* [ [[A_BUF_IDX_SUB_K2POW]], %[[INNER_BODY]] ], [ [[A_BUF_IDX_SUB_K2POW_NEXT:%.+]], %[[RED_BODY]] ]
240 // CHECK: [[A_BUF_IDX_ELEM:%.+]] = phi float* [ [[A_BUF_IDX]], %[[INNER_BODY]] ], [ [[A_BUF_IDX_NEXT:%.+]], %[[RED_BODY]] ]
241 // CHECK: [[A_BUF_IDX_VAL:%.+]] = load float, float* [[A_BUF_IDX_ELEM]],
242 // CHECK: [[A_BUF_IDX_SUB_K2POW_VAL:%.+]] = load float, float* [[A_BUF_IDX_SUB_K2POW_ELEM]],
243 // CHECK: [[RED:%.+]] = fadd float [[A_BUF_IDX_VAL]], [[A_BUF_IDX_SUB_K2POW_VAL]]
244 // CHECK: store float [[RED]], float* [[A_BUF_IDX_ELEM]],
245 // CHECK: [[A_BUF_IDX_NEXT]] = getelementptr float, float* [[A_BUF_IDX_ELEM]], i32 1
246 // CHECK: [[A_BUF_IDX_SUB_K2POW_NEXT]] = getelementptr float, float* [[A_BUF_IDX_SUB_K2POW_ELEM]], i32 1
247 // CHECK: [[DONE:%.+]] = icmp eq float* [[A_BUF_IDX_NEXT]], [[A_BUF_END]]
248 // CHECK: br i1 [[DONE]], label %[[RED_DONE]], label %[[RED_BODY]]
249 // CHECK: [[RED_DONE]]:
250
251 // b_buffer[i] += b_buffer[i-pow(2, k)];
252 // CHECK: [[B_BUF_IDX_VAL:%.+]] = load double, double* [[B_BUF_IDX]],
253 // CHECK: [[B_BUF_IDX_SUB_K2POW_VAL:%.+]] = load double, double* [[B_BUF_IDX_SUB_K2POW]],
254 // CHECK: [[RED:%.+]] = fadd double [[B_BUF_IDX_VAL]], [[B_BUF_IDX_SUB_K2POW_VAL]]
255 // CHECK: store double [[RED]], double* [[B_BUF_IDX]],
256
257 // --i;
258 // CHECK: [[I_PREV:%.+]] = sub nuw i64 [[I]], 1
259 // CHECK: [[CMP:%.+]] = icmp uge i64 [[I_PREV]], [[K2POW]]
260 // CHECK: br i1 [[CMP]], label %[[INNER_BODY]], label %[[INNER_EXIT]]
261 // CHECK: [[INNER_EXIT]]:
262
263 // ++k;
264 // CHECK: [[K_NEXT]] = add nuw i32 [[K]], 1
265 // k2pow <<= 1;
266 // CHECK: [[K2POW_NEXT]] = shl nuw i64 [[K2POW]], 1
267 // CHECK: [[CMP:%.+]] = icmp ne i32 [[K_NEXT]], [[CEIL_LOG2_10_INT]]
268 // CHECK: br i1 [[CMP]], label %[[OUTER_BODY]], label %[[OUTER_EXIT:[^,]+]]
269 // CHECK: [[OUTER_EXIT]]:
270 bar();
271 // CHECK: call void @__kmpc_for_static_init_4(
272 // CHECK: call i8* @llvm.stacksave()
273 // CHECK: store float 0.000000e+00, float* %
274 // CHECK: store double 0.000000e+00, double* [[B_PRIV_ADDR:%.+]],
275 // CHECK: br label %[[DISPATCH:[^,]+]]
276
277 // CHECK: [[SCAN_PHASE:.+]]:
278 // CHECK: call void @{{.+}}foo{{.+}}()
279 // CHECK: br label %[[LOOP_CONTINUE:.+]]
280
281 // CHECK: [[DISPATCH]]:
282 // if (i >0)
283 // a_priv[[0..n] = a_buffer[i-1][0..n];
284 // CHECK: [[BASE_IDX_I:%.+]] = load i32, i32* [[IV_ADDR:%.+]],
285 // CHECK: [[BASE_IDX:%.+]] = zext i32 [[BASE_IDX_I]] to i64
286 // CHECK: [[CMP:%.+]] = icmp eq i64 [[BASE_IDX]], 0
287 // CHECK: br i1 [[CMP]], label %[[IF_DONE:[^,]+]], label %[[IF_THEN:[^,]+]]
288 // CHECK: [[IF_THEN]]:
289 // CHECK: [[BASE_IDX_SUB_1:%.+]] = sub nuw i64 [[BASE_IDX]], 1
290 // CHECK: [[IDX:%.+]] = mul nsw i64 [[BASE_IDX_SUB_1]], [[NUM_ELEMS]]
291 // CHECK: [[A_BUF_IDX:%.+]] = getelementptr inbounds float, float* [[A_BUF]], i64 [[IDX]]
292 // CHECK: [[A_PRIV:%.+]] = getelementptr inbounds [10 x float], [10 x float]* [[A_PRIV_ADDR:%.+]], i64 0, i64 0
293 // CHECK: [[BYTES:%.+]] = mul nuw i64 [[NUM_ELEMS:%.+]], 4
294 // CHECK: [[DEST:%.+]] = bitcast float* [[A_PRIV]] to i8*
295 // CHECK: [[SRC:%.+]] = bitcast float* [[A_BUF_IDX]] to i8*
296 // CHECK: call void @llvm.memcpy.p0i8.p0i8.i64(i8* {{.*}}[[DEST]], i8* {{.*}}[[SRC]], i64 [[BYTES]], i1 false)
297
298 // b_priv = b_buffer[i];
299 // CHECK: [[B_BUF_IDX:%.+]] = getelementptr inbounds double, double* [[B_BUF]], i64 [[BASE_IDX_SUB_1]]
300 // CHECK: [[B_BUF_IDX_VAL:%.+]] = load double, double* [[B_BUF_IDX]],
301 // CHECK: store double [[B_BUF_IDX_VAL]], double* [[B_PRIV_ADDR]],
302 // CHECK: br label %[[SCAN_PHASE]]
303
304 // CHECK: [[LOOP_CONTINUE]]:
305 // CHECK: call void @llvm.stackrestore(i8* %
306 // CHECK: call void @__kmpc_for_static_fini(
307 }
308 }
309
310 // CHECK: !{!"llvm.loop.vectorize.enable", i1 true}
311
312 #endif
313
314