1 // NOTE: Assertions have been autogenerated by utils/update_cc_test_checks.py 2 // RUN: %clang_cc1 -verify -fopenmp -fopenmp-enable-irbuilder -x c++ -emit-llvm %s -triple x86_64-unknown-unknown -fexceptions -fcxx-exceptions -o - | FileCheck --check-prefixes=CHECK %s 3 // RUN: %clang_cc1 -fopenmp -fopenmp-enable-irbuilder -x c++ -triple x86_64-unknown-unknown -fexceptions -fcxx-exceptions -debug-info-kind=limited -std=c++11 -verify %s -emit-llvm -o - | FileCheck --check-prefixes=CHECK-DEBUG %s 4 5 // expected-no-diagnostics 6 7 // TODO: Teach the update script to check new functions too. 8 9 #ifndef HEADER 10 #define HEADER 11 12 // CHECK-LABEL: @_Z14parallel_for_0v( 13 // CHECK-NEXT: entry: 14 // CHECK-NEXT: [[OMP_GLOBAL_THREAD_NUM:%.*]] = call i32 @__kmpc_global_thread_num(%struct.ident_t* [[GLOB1:@.*]]) 15 // CHECK-NEXT: br label [[OMP_PARALLEL:%.*]] 16 // CHECK: omp_parallel: 17 // CHECK-NEXT: call void (%struct.ident_t*, i32, void (i32*, i32*, ...)*, ...) @__kmpc_fork_call(%struct.ident_t* [[GLOB1]], i32 0, void (i32*, i32*, ...)* bitcast (void (i32*, i32*)* @_Z14parallel_for_0v..omp_par to void (i32*, i32*, ...)*)) 18 // CHECK-NEXT: br label [[OMP_PAR_OUTLINED_EXIT:%.*]] 19 // CHECK: omp.par.outlined.exit: 20 // CHECK-NEXT: br label [[OMP_PAR_EXIT_SPLIT:%.*]] 21 // CHECK: omp.par.exit.split: 22 // CHECK-NEXT: ret void 23 // 24 // CHECK-DEBUG-LABEL: @_Z14parallel_for_0v( 25 // CHECK-DEBUG-NEXT: entry: 26 // CHECK-DEBUG-NEXT: [[OMP_GLOBAL_THREAD_NUM:%.*]] = call i32 @__kmpc_global_thread_num(%struct.ident_t* [[GLOB1:@.*]]), [[DBG10:!dbg !.*]] 27 // CHECK-DEBUG-NEXT: br label [[OMP_PARALLEL:%.*]] 28 // CHECK-DEBUG: omp_parallel: 29 // CHECK-DEBUG-NEXT: call void (%struct.ident_t*, i32, void (i32*, i32*, ...)*, ...) @__kmpc_fork_call(%struct.ident_t* [[GLOB1]], i32 0, void (i32*, i32*, ...)* bitcast (void (i32*, i32*)* @_Z14parallel_for_0v..omp_par to void (i32*, i32*, ...)*)), [[DBG11:!dbg !.*]] 30 // CHECK-DEBUG-NEXT: br label [[OMP_PAR_OUTLINED_EXIT:%.*]] 31 // CHECK-DEBUG: omp.par.outlined.exit: 32 // CHECK-DEBUG-NEXT: br label [[OMP_PAR_EXIT_SPLIT:%.*]] 33 // CHECK-DEBUG: omp.par.exit.split: 34 // CHECK-DEBUG-NEXT: ret void, [[DBG14:!dbg !.*]] 35 // 36 void parallel_for_0(void) { 37 #pragma omp parallel 38 { 39 #pragma omp for 40 for (int i = 0; i < 100; ++i) { 41 } 42 } 43 } 44 45 // CHECK-LABEL: @_Z14parallel_for_1Pfid( 46 // CHECK-NEXT: entry: 47 // CHECK-NEXT: [[R_ADDR:%.*]] = alloca float*, align 8 48 // CHECK-NEXT: [[A_ADDR:%.*]] = alloca i32, align 4 49 // CHECK-NEXT: [[B_ADDR:%.*]] = alloca double, align 8 50 // CHECK-NEXT: store float* [[R:%.*]], float** [[R_ADDR]], align 8 51 // CHECK-NEXT: store i32 [[A:%.*]], i32* [[A_ADDR]], align 4 52 // CHECK-NEXT: store double [[B:%.*]], double* [[B_ADDR]], align 8 53 // CHECK-NEXT: [[OMP_GLOBAL_THREAD_NUM:%.*]] = call i32 @__kmpc_global_thread_num(%struct.ident_t* [[GLOB1]]) 54 // CHECK-NEXT: br label [[OMP_PARALLEL:%.*]] 55 // CHECK: omp_parallel: 56 // CHECK-NEXT: call void (%struct.ident_t*, i32, void (i32*, i32*, ...)*, ...) @__kmpc_fork_call(%struct.ident_t* [[GLOB1]], i32 3, void (i32*, i32*, ...)* bitcast (void (i32*, i32*, i32*, double*, float**)* @_Z14parallel_for_1Pfid..omp_par.1 to void (i32*, i32*, ...)*), i32* [[A_ADDR]], double* [[B_ADDR]], float** [[R_ADDR]]) 57 // CHECK-NEXT: br label [[OMP_PAR_OUTLINED_EXIT19:%.*]] 58 // CHECK: omp.par.outlined.exit19: 59 // CHECK-NEXT: br label [[OMP_PAR_EXIT_SPLIT:%.*]] 60 // CHECK: omp.par.exit.split: 61 // CHECK-NEXT: ret void 62 // 63 // CHECK-DEBUG-LABEL: @_Z14parallel_for_1Pfid( 64 // CHECK-DEBUG-NEXT: entry: 65 // CHECK-DEBUG-NEXT: [[R_ADDR:%.*]] = alloca float*, align 8 66 // CHECK-DEBUG-NEXT: [[A_ADDR:%.*]] = alloca i32, align 4 67 // CHECK-DEBUG-NEXT: [[B_ADDR:%.*]] = alloca double, align 8 68 // CHECK-DEBUG-NEXT: store float* [[R:%.*]], float** [[R_ADDR]], align 8 69 // CHECK-DEBUG-NEXT: call void @llvm.dbg.declare(metadata float** [[R_ADDR]], [[META41:metadata !.*]], metadata !DIExpression()), [[DBG42:!dbg !.*]] 70 // CHECK-DEBUG-NEXT: store i32 [[A:%.*]], i32* [[A_ADDR]], align 4 71 // CHECK-DEBUG-NEXT: call void @llvm.dbg.declare(metadata i32* [[A_ADDR]], [[META43:metadata !.*]], metadata !DIExpression()), [[DBG44:!dbg !.*]] 72 // CHECK-DEBUG-NEXT: store double [[B:%.*]], double* [[B_ADDR]], align 8 73 // CHECK-DEBUG-NEXT: call void @llvm.dbg.declare(metadata double* [[B_ADDR]], [[META45:metadata !.*]], metadata !DIExpression()), [[DBG46:!dbg !.*]] 74 // CHECK-DEBUG-NEXT: [[OMP_GLOBAL_THREAD_NUM:%.*]] = call i32 @__kmpc_global_thread_num(%struct.ident_t* [[GLOB10:@.*]]), [[DBG47:!dbg !.*]] 75 // CHECK-DEBUG-NEXT: br label [[OMP_PARALLEL:%.*]] 76 // CHECK-DEBUG: omp_parallel: 77 // CHECK-DEBUG-NEXT: call void (%struct.ident_t*, i32, void (i32*, i32*, ...)*, ...) @__kmpc_fork_call(%struct.ident_t* [[GLOB10]], i32 3, void (i32*, i32*, ...)* bitcast (void (i32*, i32*, i32*, double*, float**)* @_Z14parallel_for_1Pfid..omp_par.1 to void (i32*, i32*, ...)*), i32* [[A_ADDR]], double* [[B_ADDR]], float** [[R_ADDR]]), [[DBG48:!dbg !.*]] 78 // CHECK-DEBUG-NEXT: br label [[OMP_PAR_OUTLINED_EXIT19:%.*]] 79 // CHECK-DEBUG: omp.par.outlined.exit19: 80 // CHECK-DEBUG-NEXT: br label [[OMP_PAR_EXIT_SPLIT:%.*]] 81 // CHECK-DEBUG: omp.par.exit.split: 82 // CHECK-DEBUG-NEXT: ret void, [[DBG50:!dbg !.*]] 83 // 84 void parallel_for_1(float *r, int a, double b) { 85 #pragma omp parallel 86 { 87 #pragma omp parallel 88 { 89 #pragma omp for 90 for (int i = 0; i < 100; ++i) { 91 *r = a + b; 92 } 93 } 94 } 95 } 96 97 // CHECK-LABEL: @_Z14parallel_for_2Pfid( 98 // CHECK-NEXT: entry: 99 // CHECK-NEXT: [[R_ADDR:%.*]] = alloca float*, align 8 100 // CHECK-NEXT: [[A_ADDR:%.*]] = alloca i32, align 4 101 // CHECK-NEXT: [[B_ADDR:%.*]] = alloca double, align 8 102 // CHECK-NEXT: [[DOTOMP_IV212:%.*]] = alloca i32, align 4 103 // CHECK-NEXT: [[TMP213:%.*]] = alloca i32, align 4 104 // CHECK-NEXT: [[DOTOMP_LB214:%.*]] = alloca i32, align 4 105 // CHECK-NEXT: [[DOTOMP_UB215:%.*]] = alloca i32, align 4 106 // CHECK-NEXT: [[DOTOMP_STRIDE216:%.*]] = alloca i32, align 4 107 // CHECK-NEXT: [[DOTOMP_IS_LAST217:%.*]] = alloca i32, align 4 108 // CHECK-NEXT: [[I218:%.*]] = alloca i32, align 4 109 // CHECK-NEXT: store float* [[R:%.*]], float** [[R_ADDR]], align 8 110 // CHECK-NEXT: store i32 [[A:%.*]], i32* [[A_ADDR]], align 4 111 // CHECK-NEXT: store double [[B:%.*]], double* [[B_ADDR]], align 8 112 // CHECK-NEXT: [[OMP_GLOBAL_THREAD_NUM:%.*]] = call i32 @__kmpc_global_thread_num(%struct.ident_t* [[GLOB1]]) 113 // CHECK-NEXT: br label [[OMP_PARALLEL:%.*]] 114 // CHECK: omp_parallel: 115 // CHECK-NEXT: call void (%struct.ident_t*, i32, void (i32*, i32*, ...)*, ...) @__kmpc_fork_call(%struct.ident_t* [[GLOB1]], i32 3, void (i32*, i32*, ...)* bitcast (void (i32*, i32*, i32*, double*, float**)* @_Z14parallel_for_2Pfid..omp_par.4 to void (i32*, i32*, ...)*), i32* [[A_ADDR]], double* [[B_ADDR]], float** [[R_ADDR]]) 116 // CHECK-NEXT: br label [[OMP_PAR_OUTLINED_EXIT211:%.*]] 117 // CHECK: omp.par.outlined.exit211: 118 // CHECK-NEXT: br label [[OMP_PAR_EXIT_SPLIT:%.*]] 119 // CHECK: omp.par.exit.split: 120 // CHECK-NEXT: store i32 0, i32* [[DOTOMP_LB214]], align 4 121 // CHECK-NEXT: store i32 99, i32* [[DOTOMP_UB215]], align 4 122 // CHECK-NEXT: store i32 1, i32* [[DOTOMP_STRIDE216]], align 4 123 // CHECK-NEXT: store i32 0, i32* [[DOTOMP_IS_LAST217]], align 4 124 // CHECK-NEXT: [[OMP_GLOBAL_THREAD_NUM219:%.*]] = call i32 @__kmpc_global_thread_num(%struct.ident_t* [[GLOB41:@.*]]) 125 // CHECK-NEXT: call void @__kmpc_for_static_init_4(%struct.ident_t* [[GLOB2:@.*]], i32 [[OMP_GLOBAL_THREAD_NUM219]], i32 34, i32* [[DOTOMP_IS_LAST217]], i32* [[DOTOMP_LB214]], i32* [[DOTOMP_UB215]], i32* [[DOTOMP_STRIDE216]], i32 1, i32 1) 126 // CHECK-NEXT: [[TMP0:%.*]] = load i32, i32* [[DOTOMP_UB215]], align 4 127 // CHECK-NEXT: [[CMP220:%.*]] = icmp sgt i32 [[TMP0]], 99 128 // CHECK-NEXT: br i1 [[CMP220]], label [[COND_TRUE221:%.*]], label [[COND_FALSE222:%.*]] 129 // CHECK: cond.true221: 130 // CHECK-NEXT: br label [[COND_END223:%.*]] 131 // CHECK: cond.false222: 132 // CHECK-NEXT: [[TMP1:%.*]] = load i32, i32* [[DOTOMP_UB215]], align 4 133 // CHECK-NEXT: br label [[COND_END223]] 134 // CHECK: cond.end223: 135 // CHECK-NEXT: [[COND224:%.*]] = phi i32 [ 99, [[COND_TRUE221]] ], [ [[TMP1]], [[COND_FALSE222]] ] 136 // CHECK-NEXT: store i32 [[COND224]], i32* [[DOTOMP_UB215]], align 4 137 // CHECK-NEXT: [[TMP2:%.*]] = load i32, i32* [[DOTOMP_LB214]], align 4 138 // CHECK-NEXT: store i32 [[TMP2]], i32* [[DOTOMP_IV212]], align 4 139 // CHECK-NEXT: br label [[OMP_INNER_FOR_COND225:%.*]] 140 // CHECK: omp.inner.for.cond225: 141 // CHECK-NEXT: [[TMP3:%.*]] = load i32, i32* [[DOTOMP_IV212]], align 4 142 // CHECK-NEXT: [[TMP4:%.*]] = load i32, i32* [[DOTOMP_UB215]], align 4 143 // CHECK-NEXT: [[CMP226:%.*]] = icmp sle i32 [[TMP3]], [[TMP4]] 144 // CHECK-NEXT: br i1 [[CMP226]], label [[OMP_INNER_FOR_BODY227:%.*]], label [[OMP_INNER_FOR_END236:%.*]] 145 // CHECK: omp.inner.for.body227: 146 // CHECK-NEXT: [[TMP5:%.*]] = load i32, i32* [[DOTOMP_IV212]], align 4 147 // CHECK-NEXT: [[MUL228:%.*]] = mul nsw i32 [[TMP5]], 1 148 // CHECK-NEXT: [[ADD229:%.*]] = add nsw i32 0, [[MUL228]] 149 // CHECK-NEXT: store i32 [[ADD229]], i32* [[I218]], align 4 150 // CHECK-NEXT: [[TMP6:%.*]] = load i32, i32* [[A_ADDR]], align 4 151 // CHECK-NEXT: [[CONV230:%.*]] = sitofp i32 [[TMP6]] to double 152 // CHECK-NEXT: [[TMP7:%.*]] = load double, double* [[B_ADDR]], align 8 153 // CHECK-NEXT: [[ADD231:%.*]] = fadd double [[CONV230]], [[TMP7]] 154 // CHECK-NEXT: [[CONV232:%.*]] = fptrunc double [[ADD231]] to float 155 // CHECK-NEXT: [[TMP8:%.*]] = load float*, float** [[R_ADDR]], align 8 156 // CHECK-NEXT: store float [[CONV232]], float* [[TMP8]], align 4 157 // CHECK-NEXT: br label [[OMP_BODY_CONTINUE233:%.*]] 158 // CHECK: omp.body.continue233: 159 // CHECK-NEXT: br label [[OMP_INNER_FOR_INC234:%.*]] 160 // CHECK: omp.inner.for.inc234: 161 // CHECK-NEXT: [[TMP9:%.*]] = load i32, i32* [[DOTOMP_IV212]], align 4 162 // CHECK-NEXT: [[ADD235:%.*]] = add nsw i32 [[TMP9]], 1 163 // CHECK-NEXT: store i32 [[ADD235]], i32* [[DOTOMP_IV212]], align 4 164 // CHECK-NEXT: br label [[OMP_INNER_FOR_COND225]] 165 // CHECK: omp.inner.for.end236: 166 // CHECK-NEXT: br label [[OMP_LOOP_EXIT237:%.*]] 167 // CHECK: omp.loop.exit237: 168 // CHECK-NEXT: [[OMP_GLOBAL_THREAD_NUM238:%.*]] = call i32 @__kmpc_global_thread_num(%struct.ident_t* [[GLOB43:@.*]]) 169 // CHECK-NEXT: call void @__kmpc_for_static_fini(%struct.ident_t* [[GLOB2]], i32 [[OMP_GLOBAL_THREAD_NUM238]]) 170 // CHECK-NEXT: [[OMP_GLOBAL_THREAD_NUM239:%.*]] = call i32 @__kmpc_global_thread_num(%struct.ident_t* [[GLOB1]]) 171 // CHECK-NEXT: call void @__kmpc_barrier(%struct.ident_t* [[GLOB7:@.*]], i32 [[OMP_GLOBAL_THREAD_NUM239]]) 172 // CHECK-NEXT: ret void 173 // 174 // CHECK-DEBUG-LABEL: @_Z14parallel_for_2Pfid( 175 // CHECK-DEBUG-NEXT: entry: 176 // CHECK-DEBUG-NEXT: [[R_ADDR:%.*]] = alloca float*, align 8 177 // CHECK-DEBUG-NEXT: [[A_ADDR:%.*]] = alloca i32, align 4 178 // CHECK-DEBUG-NEXT: [[B_ADDR:%.*]] = alloca double, align 8 179 // CHECK-DEBUG-NEXT: [[DOTOMP_IV212:%.*]] = alloca i32, align 4 180 // CHECK-DEBUG-NEXT: [[TMP213:%.*]] = alloca i32, align 4 181 // CHECK-DEBUG-NEXT: [[DOTOMP_LB214:%.*]] = alloca i32, align 4 182 // CHECK-DEBUG-NEXT: [[DOTOMP_UB215:%.*]] = alloca i32, align 4 183 // CHECK-DEBUG-NEXT: [[DOTOMP_STRIDE216:%.*]] = alloca i32, align 4 184 // CHECK-DEBUG-NEXT: [[DOTOMP_IS_LAST217:%.*]] = alloca i32, align 4 185 // CHECK-DEBUG-NEXT: [[I218:%.*]] = alloca i32, align 4 186 // CHECK-DEBUG-NEXT: store float* [[R:%.*]], float** [[R_ADDR]], align 8 187 // CHECK-DEBUG-NEXT: call void @llvm.dbg.declare(metadata float** [[R_ADDR]], [[META77:metadata !.*]], metadata !DIExpression()), [[DBG78:!dbg !.*]] 188 // CHECK-DEBUG-NEXT: store i32 [[A:%.*]], i32* [[A_ADDR]], align 4 189 // CHECK-DEBUG-NEXT: call void @llvm.dbg.declare(metadata i32* [[A_ADDR]], [[META79:metadata !.*]], metadata !DIExpression()), [[DBG80:!dbg !.*]] 190 // CHECK-DEBUG-NEXT: store double [[B:%.*]], double* [[B_ADDR]], align 8 191 // CHECK-DEBUG-NEXT: call void @llvm.dbg.declare(metadata double* [[B_ADDR]], [[META81:metadata !.*]], metadata !DIExpression()), [[DBG82:!dbg !.*]] 192 // CHECK-DEBUG-NEXT: [[OMP_GLOBAL_THREAD_NUM:%.*]] = call i32 @__kmpc_global_thread_num(%struct.ident_t* [[GLOB21:@.*]]), [[DBG83:!dbg !.*]] 193 // CHECK-DEBUG-NEXT: br label [[OMP_PARALLEL:%.*]] 194 // CHECK-DEBUG: omp_parallel: 195 // CHECK-DEBUG-NEXT: call void (%struct.ident_t*, i32, void (i32*, i32*, ...)*, ...) @__kmpc_fork_call(%struct.ident_t* [[GLOB21]], i32 3, void (i32*, i32*, ...)* bitcast (void (i32*, i32*, i32*, double*, float**)* @_Z14parallel_for_2Pfid..omp_par.4 to void (i32*, i32*, ...)*), i32* [[A_ADDR]], double* [[B_ADDR]], float** [[R_ADDR]]), [[DBG84:!dbg !.*]] 196 // CHECK-DEBUG-NEXT: br label [[OMP_PAR_OUTLINED_EXIT211:%.*]] 197 // CHECK-DEBUG: omp.par.outlined.exit211: 198 // CHECK-DEBUG-NEXT: br label [[OMP_PAR_EXIT_SPLIT:%.*]] 199 // CHECK-DEBUG: omp.par.exit.split: 200 // CHECK-DEBUG-NEXT: call void @llvm.dbg.declare(metadata i32* [[DOTOMP_IV212]], [[META87:metadata !.*]], metadata !DIExpression()), [[DBG89:!dbg !.*]] 201 // CHECK-DEBUG-NEXT: call void @llvm.dbg.declare(metadata i32* [[DOTOMP_LB214]], [[META90:metadata !.*]], metadata !DIExpression()), [[DBG89]] 202 // CHECK-DEBUG-NEXT: store i32 0, i32* [[DOTOMP_LB214]], align 4, [[DBG91:!dbg !.*]] 203 // CHECK-DEBUG-NEXT: call void @llvm.dbg.declare(metadata i32* [[DOTOMP_UB215]], [[META92:metadata !.*]], metadata !DIExpression()), [[DBG89]] 204 // CHECK-DEBUG-NEXT: store i32 99, i32* [[DOTOMP_UB215]], align 4, [[DBG91]] 205 // CHECK-DEBUG-NEXT: call void @llvm.dbg.declare(metadata i32* [[DOTOMP_STRIDE216]], [[META93:metadata !.*]], metadata !DIExpression()), [[DBG89]] 206 // CHECK-DEBUG-NEXT: store i32 1, i32* [[DOTOMP_STRIDE216]], align 4, [[DBG91]] 207 // CHECK-DEBUG-NEXT: call void @llvm.dbg.declare(metadata i32* [[DOTOMP_IS_LAST217]], [[META94:metadata !.*]], metadata !DIExpression()), [[DBG89]] 208 // CHECK-DEBUG-NEXT: store i32 0, i32* [[DOTOMP_IS_LAST217]], align 4, [[DBG91]] 209 // CHECK-DEBUG-NEXT: call void @llvm.dbg.declare(metadata i32* [[I218]], [[META95:metadata !.*]], metadata !DIExpression()), [[DBG89]] 210 // CHECK-DEBUG-NEXT: [[OMP_GLOBAL_THREAD_NUM219:%.*]] = call i32 @__kmpc_global_thread_num(%struct.ident_t* [[GLOB79:@.*]]) 211 // CHECK-DEBUG-NEXT: call void @__kmpc_for_static_init_4(%struct.ident_t* [[GLOB78:@.*]], i32 [[OMP_GLOBAL_THREAD_NUM219]], i32 34, i32* [[DOTOMP_IS_LAST217]], i32* [[DOTOMP_LB214]], i32* [[DOTOMP_UB215]], i32* [[DOTOMP_STRIDE216]], i32 1, i32 1), [[DBG96:!dbg !.*]] 212 // CHECK-DEBUG-NEXT: [[TMP0:%.*]] = load i32, i32* [[DOTOMP_UB215]], align 4, [[DBG91]] 213 // CHECK-DEBUG-NEXT: [[CMP220:%.*]] = icmp sgt i32 [[TMP0]], 99, [[DBG91]] 214 // CHECK-DEBUG-NEXT: br i1 [[CMP220]], label [[COND_TRUE221:%.*]], label [[COND_FALSE222:%.*]], [[DBG91]] 215 // CHECK-DEBUG: cond.true221: 216 // CHECK-DEBUG-NEXT: br label [[COND_END223:%.*]], [[DBG91]] 217 // CHECK-DEBUG: cond.false222: 218 // CHECK-DEBUG-NEXT: [[TMP1:%.*]] = load i32, i32* [[DOTOMP_UB215]], align 4, [[DBG91]] 219 // CHECK-DEBUG-NEXT: br label [[COND_END223]], [[DBG91]] 220 // CHECK-DEBUG: cond.end223: 221 // CHECK-DEBUG-NEXT: [[COND224:%.*]] = phi i32 [ 99, [[COND_TRUE221]] ], [ [[TMP1]], [[COND_FALSE222]] ], [[DBG91]] 222 // CHECK-DEBUG-NEXT: store i32 [[COND224]], i32* [[DOTOMP_UB215]], align 4, [[DBG91]] 223 // CHECK-DEBUG-NEXT: [[TMP2:%.*]] = load i32, i32* [[DOTOMP_LB214]], align 4, [[DBG91]] 224 // CHECK-DEBUG-NEXT: store i32 [[TMP2]], i32* [[DOTOMP_IV212]], align 4, [[DBG91]] 225 // CHECK-DEBUG-NEXT: br label [[OMP_INNER_FOR_COND225:%.*]], [[DBG97:!dbg !.*]] 226 // CHECK-DEBUG: omp.inner.for.cond225: 227 // CHECK-DEBUG-NEXT: [[TMP3:%.*]] = load i32, i32* [[DOTOMP_IV212]], align 4, [[DBG91]] 228 // CHECK-DEBUG-NEXT: [[TMP4:%.*]] = load i32, i32* [[DOTOMP_UB215]], align 4, [[DBG91]] 229 // CHECK-DEBUG-NEXT: [[CMP226:%.*]] = icmp sle i32 [[TMP3]], [[TMP4]], [[DBG98:!dbg !.*]] 230 // CHECK-DEBUG-NEXT: br i1 [[CMP226]], label [[OMP_INNER_FOR_BODY227:%.*]], label [[OMP_INNER_FOR_END236:%.*]], [[DBG97]] 231 // CHECK-DEBUG: omp.inner.for.body227: 232 // CHECK-DEBUG-NEXT: [[TMP5:%.*]] = load i32, i32* [[DOTOMP_IV212]], align 4, [[DBG91]] 233 // CHECK-DEBUG-NEXT: [[MUL228:%.*]] = mul nsw i32 [[TMP5]], 1, [[DBG99:!dbg !.*]] 234 // CHECK-DEBUG-NEXT: [[ADD229:%.*]] = add nsw i32 0, [[MUL228]], [[DBG99]] 235 // CHECK-DEBUG-NEXT: store i32 [[ADD229]], i32* [[I218]], align 4, [[DBG99]] 236 // CHECK-DEBUG-NEXT: [[TMP6:%.*]] = load i32, i32* [[A_ADDR]], align 4, [[DBG100:!dbg !.*]] 237 // CHECK-DEBUG-NEXT: [[CONV230:%.*]] = sitofp i32 [[TMP6]] to double, [[DBG100]] 238 // CHECK-DEBUG-NEXT: [[TMP7:%.*]] = load double, double* [[B_ADDR]], align 8, [[DBG101:!dbg !.*]] 239 // CHECK-DEBUG-NEXT: [[ADD231:%.*]] = fadd double [[CONV230]], [[TMP7]], [[DBG102:!dbg !.*]] 240 // CHECK-DEBUG-NEXT: [[CONV232:%.*]] = fptrunc double [[ADD231]] to float, [[DBG100]] 241 // CHECK-DEBUG-NEXT: [[TMP8:%.*]] = load float*, float** [[R_ADDR]], align 8, [[DBG103:!dbg !.*]] 242 // CHECK-DEBUG-NEXT: store float [[CONV232]], float* [[TMP8]], align 4, [[DBG104:!dbg !.*]] 243 // CHECK-DEBUG-NEXT: br label [[OMP_BODY_CONTINUE233:%.*]], [[DBG105:!dbg !.*]] 244 // CHECK-DEBUG: omp.body.continue233: 245 // CHECK-DEBUG-NEXT: br label [[OMP_INNER_FOR_INC234:%.*]], [[DBG96]] 246 // CHECK-DEBUG: omp.inner.for.inc234: 247 // CHECK-DEBUG-NEXT: [[TMP9:%.*]] = load i32, i32* [[DOTOMP_IV212]], align 4, [[DBG91]] 248 // CHECK-DEBUG-NEXT: [[ADD235:%.*]] = add nsw i32 [[TMP9]], 1, [[DBG98]] 249 // CHECK-DEBUG-NEXT: store i32 [[ADD235]], i32* [[DOTOMP_IV212]], align 4, [[DBG98]] 250 // CHECK-DEBUG-NEXT: br label [[OMP_INNER_FOR_COND225]], [[DBG96]], [[LOOP106:!llvm.loop !.*]] 251 // CHECK-DEBUG: omp.inner.for.end236: 252 // CHECK-DEBUG-NEXT: br label [[OMP_LOOP_EXIT237:%.*]], [[DBG96]] 253 // CHECK-DEBUG: omp.loop.exit237: 254 // CHECK-DEBUG-NEXT: [[OMP_GLOBAL_THREAD_NUM238:%.*]] = call i32 @__kmpc_global_thread_num(%struct.ident_t* [[GLOB82:@.*]]) 255 // CHECK-DEBUG-NEXT: call void @__kmpc_for_static_fini(%struct.ident_t* [[GLOB81:@.*]], i32 [[OMP_GLOBAL_THREAD_NUM238]]), [[DBG107:!dbg !.*]] 256 // CHECK-DEBUG-NEXT: [[OMP_GLOBAL_THREAD_NUM239:%.*]] = call i32 @__kmpc_global_thread_num(%struct.ident_t* [[GLOB82]]), [[DBG107]] 257 // CHECK-DEBUG-NEXT: call void @__kmpc_barrier(%struct.ident_t* [[GLOB83:@.*]], i32 [[OMP_GLOBAL_THREAD_NUM239]]), [[DBG107]] 258 // CHECK-DEBUG-NEXT: ret void, [[DBG108:!dbg !.*]] 259 // 260 void parallel_for_2(float *r, int a, double b) { 261 #pragma omp parallel 262 { 263 #pragma omp for 264 for (int i = 0; i < 100; ++i) 265 *r = a + b; 266 #pragma omp parallel 267 { 268 #pragma omp for 269 for (int i = 0; i < 100; ++i) 270 *r = a + b; 271 #pragma omp parallel 272 { 273 #pragma omp for 274 for (int i = 0; i < 100; ++i) 275 *r = a + b; 276 } 277 #pragma omp for 278 for (int i = 0; i < 100; ++i) 279 *r = a + b; 280 #pragma omp parallel 281 { 282 #pragma omp for 283 for (int i = 0; i < 100; ++i) 284 *r = a + b; 285 } 286 #pragma omp for 287 for (int i = 0; i < 100; ++i) 288 *r = a + b; 289 } 290 #pragma omp for 291 for (int i = 0; i < 100; ++i) 292 *r = a + b; 293 } 294 #pragma omp for 295 for (int i = 0; i < 100; ++i) 296 *r = a + b; 297 } 298 299 #endif 300