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:@.*]]), [[DBG12:!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*, ...)*)), [[DBG13:!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, [[DBG17:!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.4 to void (i32*, i32*, ...)*), i32* [[A_ADDR]], double* [[B_ADDR]], float** [[R_ADDR]]) 57 // CHECK-NEXT: br label [[OMP_PAR_OUTLINED_EXIT16:%.*]] 58 // CHECK: omp.par.outlined.exit16: 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]], [[META72:metadata !.*]], metadata !DIExpression()), [[DBG73:!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]], [[META74:metadata !.*]], metadata !DIExpression()), [[DBG75:!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]], [[META76:metadata !.*]], metadata !DIExpression()), [[DBG77:!dbg !.*]] 74 // CHECK-DEBUG-NEXT: [[OMP_GLOBAL_THREAD_NUM:%.*]] = call i32 @__kmpc_global_thread_num(%struct.ident_t* [[GLOB6:@.*]]), [[DBG78:!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* [[GLOB6]], i32 3, void (i32*, i32*, ...)* bitcast (void (i32*, i32*, i32*, double*, float**)* @_Z14parallel_for_1Pfid..omp_par.4 to void (i32*, i32*, ...)*), i32* [[A_ADDR]], double* [[B_ADDR]], float** [[R_ADDR]]), [[DBG79:!dbg !.*]] 78 // CHECK-DEBUG-NEXT: br label [[OMP_PAR_OUTLINED_EXIT16:%.*]] 79 // CHECK-DEBUG: omp.par.outlined.exit16: 80 // CHECK-DEBUG-NEXT: br label [[OMP_PAR_EXIT_SPLIT:%.*]] 81 // CHECK-DEBUG: omp.par.exit.split: 82 // CHECK-DEBUG-NEXT: ret void, [[DBG81:!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: [[I185:%.*]] = alloca i32, align 4 103 // CHECK-NEXT: [[AGG_CAPTURED186:%.*]] = alloca [[STRUCT_ANON_17:%.*]], align 8 104 // CHECK-NEXT: [[AGG_CAPTURED187:%.*]] = alloca [[STRUCT_ANON_18:%.*]], align 4 105 // CHECK-NEXT: [[DOTCOUNT_ADDR188:%.*]] = alloca i32, align 4 106 // CHECK-NEXT: [[P_LASTITER203:%.*]] = alloca i32, align 4 107 // CHECK-NEXT: [[P_LOWERBOUND204:%.*]] = alloca i32, align 4 108 // CHECK-NEXT: [[P_UPPERBOUND205:%.*]] = alloca i32, align 4 109 // CHECK-NEXT: [[P_STRIDE206:%.*]] = alloca i32, align 4 110 // CHECK-NEXT: store float* [[R:%.*]], float** [[R_ADDR]], align 8 111 // CHECK-NEXT: store i32 [[A:%.*]], i32* [[A_ADDR]], align 4 112 // CHECK-NEXT: store double [[B:%.*]], double* [[B_ADDR]], align 8 113 // CHECK-NEXT: [[OMP_GLOBAL_THREAD_NUM:%.*]] = call i32 @__kmpc_global_thread_num(%struct.ident_t* [[GLOB1]]) 114 // CHECK-NEXT: br label [[OMP_PARALLEL:%.*]] 115 // CHECK: omp_parallel: 116 // 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.23 to void (i32*, i32*, ...)*), i32* [[A_ADDR]], double* [[B_ADDR]], float** [[R_ADDR]]) 117 // CHECK-NEXT: br label [[OMP_PAR_OUTLINED_EXIT184:%.*]] 118 // CHECK: omp.par.outlined.exit184: 119 // CHECK-NEXT: br label [[OMP_PAR_EXIT_SPLIT:%.*]] 120 // CHECK: omp.par.exit.split: 121 // CHECK-NEXT: store i32 0, i32* [[I185]], align 4 122 // CHECK-NEXT: [[TMP0:%.*]] = getelementptr inbounds [[STRUCT_ANON_17]], %struct.anon.17* [[AGG_CAPTURED186]], i32 0, i32 0 123 // CHECK-NEXT: store i32* [[I185]], i32** [[TMP0]], align 8 124 // CHECK-NEXT: [[TMP1:%.*]] = getelementptr inbounds [[STRUCT_ANON_18]], %struct.anon.18* [[AGG_CAPTURED187]], i32 0, i32 0 125 // CHECK-NEXT: [[TMP2:%.*]] = load i32, i32* [[I185]], align 4 126 // CHECK-NEXT: store i32 [[TMP2]], i32* [[TMP1]], align 4 127 // CHECK-NEXT: call void @__captured_stmt.19(i32* [[DOTCOUNT_ADDR188]], %struct.anon.17* [[AGG_CAPTURED186]]) 128 // CHECK-NEXT: [[DOTCOUNT189:%.*]] = load i32, i32* [[DOTCOUNT_ADDR188]], align 4 129 // CHECK-NEXT: br label [[OMP_LOOP_PREHEADER190:%.*]] 130 // CHECK: omp_loop.preheader190: 131 // CHECK-NEXT: store i32 0, i32* [[P_LOWERBOUND204]], align 4 132 // CHECK-NEXT: [[TMP3:%.*]] = sub i32 [[DOTCOUNT189]], 1 133 // CHECK-NEXT: store i32 [[TMP3]], i32* [[P_UPPERBOUND205]], align 4 134 // CHECK-NEXT: store i32 1, i32* [[P_STRIDE206]], align 4 135 // CHECK-NEXT: [[OMP_GLOBAL_THREAD_NUM207:%.*]] = call i32 @__kmpc_global_thread_num(%struct.ident_t* [[GLOB1]]) 136 // CHECK-NEXT: call void @__kmpc_for_static_init_4u(%struct.ident_t* [[GLOB1]], i32 [[OMP_GLOBAL_THREAD_NUM207]], i32 34, i32* [[P_LASTITER203]], i32* [[P_LOWERBOUND204]], i32* [[P_UPPERBOUND205]], i32* [[P_STRIDE206]], i32 1, i32 1) 137 // CHECK-NEXT: [[TMP4:%.*]] = load i32, i32* [[P_LOWERBOUND204]], align 4 138 // CHECK-NEXT: [[TMP5:%.*]] = load i32, i32* [[P_UPPERBOUND205]], align 4 139 // CHECK-NEXT: [[TMP6:%.*]] = sub i32 [[TMP5]], [[TMP4]] 140 // CHECK-NEXT: [[TMP7:%.*]] = add i32 [[TMP6]], 1 141 // CHECK-NEXT: br label [[OMP_LOOP_HEADER191:%.*]] 142 // CHECK: omp_loop.header191: 143 // CHECK-NEXT: [[OMP_LOOP_IV197:%.*]] = phi i32 [ 0, [[OMP_LOOP_PREHEADER190]] ], [ [[OMP_LOOP_NEXT199:%.*]], [[OMP_LOOP_INC194:%.*]] ] 144 // CHECK-NEXT: br label [[OMP_LOOP_COND192:%.*]] 145 // CHECK: omp_loop.cond192: 146 // CHECK-NEXT: [[OMP_LOOP_CMP198:%.*]] = icmp ult i32 [[OMP_LOOP_IV197]], [[TMP7]] 147 // CHECK-NEXT: br i1 [[OMP_LOOP_CMP198]], label [[OMP_LOOP_BODY193:%.*]], label [[OMP_LOOP_EXIT195:%.*]] 148 // CHECK: omp_loop.body193: 149 // CHECK-NEXT: [[TMP8:%.*]] = add i32 [[OMP_LOOP_IV197]], [[TMP4]] 150 // CHECK-NEXT: call void @__captured_stmt.20(i32* [[I185]], i32 [[TMP8]], %struct.anon.18* [[AGG_CAPTURED187]]) 151 // CHECK-NEXT: [[TMP9:%.*]] = load i32, i32* [[A_ADDR]], align 4 152 // CHECK-NEXT: [[CONV200:%.*]] = sitofp i32 [[TMP9]] to double 153 // CHECK-NEXT: [[TMP10:%.*]] = load double, double* [[B_ADDR]], align 8 154 // CHECK-NEXT: [[ADD201:%.*]] = fadd double [[CONV200]], [[TMP10]] 155 // CHECK-NEXT: [[CONV202:%.*]] = fptrunc double [[ADD201]] to float 156 // CHECK-NEXT: [[TMP11:%.*]] = load float*, float** [[R_ADDR]], align 8 157 // CHECK-NEXT: store float [[CONV202]], float* [[TMP11]], align 4 158 // CHECK-NEXT: br label [[OMP_LOOP_INC194]] 159 // CHECK: omp_loop.inc194: 160 // CHECK-NEXT: [[OMP_LOOP_NEXT199]] = add nuw i32 [[OMP_LOOP_IV197]], 1 161 // CHECK-NEXT: br label [[OMP_LOOP_HEADER191]] 162 // CHECK: omp_loop.exit195: 163 // CHECK-NEXT: call void @__kmpc_for_static_fini(%struct.ident_t* [[GLOB1]], i32 [[OMP_GLOBAL_THREAD_NUM207]]) 164 // CHECK-NEXT: [[OMP_GLOBAL_THREAD_NUM208:%.*]] = call i32 @__kmpc_global_thread_num(%struct.ident_t* [[GLOB1]]) 165 // CHECK-NEXT: call void @__kmpc_barrier(%struct.ident_t* [[GLOB2:@.*]], i32 [[OMP_GLOBAL_THREAD_NUM208]]) 166 // CHECK-NEXT: br label [[OMP_LOOP_AFTER196:%.*]] 167 // CHECK: omp_loop.after196: 168 // CHECK-NEXT: ret void 169 // 170 // CHECK-DEBUG-LABEL: @_Z14parallel_for_2Pfid( 171 // CHECK-DEBUG-NEXT: entry: 172 // CHECK-DEBUG-NEXT: [[R_ADDR:%.*]] = alloca float*, align 8 173 // CHECK-DEBUG-NEXT: [[A_ADDR:%.*]] = alloca i32, align 4 174 // CHECK-DEBUG-NEXT: [[B_ADDR:%.*]] = alloca double, align 8 175 // CHECK-DEBUG-NEXT: [[I185:%.*]] = alloca i32, align 4 176 // CHECK-DEBUG-NEXT: [[AGG_CAPTURED186:%.*]] = alloca [[STRUCT_ANON_17:%.*]], align 8 177 // CHECK-DEBUG-NEXT: [[AGG_CAPTURED187:%.*]] = alloca [[STRUCT_ANON_18:%.*]], align 4 178 // CHECK-DEBUG-NEXT: [[DOTCOUNT_ADDR188:%.*]] = alloca i32, align 4 179 // CHECK-DEBUG-NEXT: [[P_LASTITER203:%.*]] = alloca i32, align 4 180 // CHECK-DEBUG-NEXT: [[P_LOWERBOUND204:%.*]] = alloca i32, align 4 181 // CHECK-DEBUG-NEXT: [[P_UPPERBOUND205:%.*]] = alloca i32, align 4 182 // CHECK-DEBUG-NEXT: [[P_STRIDE206:%.*]] = alloca i32, align 4 183 // CHECK-DEBUG-NEXT: store float* [[R:%.*]], float** [[R_ADDR]], align 8 184 // CHECK-DEBUG-NEXT: call void @llvm.dbg.declare(metadata float** [[R_ADDR]], [[META133:metadata !.*]], metadata !DIExpression()), [[DBG134:!dbg !.*]] 185 // CHECK-DEBUG-NEXT: store i32 [[A:%.*]], i32* [[A_ADDR]], align 4 186 // CHECK-DEBUG-NEXT: call void @llvm.dbg.declare(metadata i32* [[A_ADDR]], [[META135:metadata !.*]], metadata !DIExpression()), [[DBG136:!dbg !.*]] 187 // CHECK-DEBUG-NEXT: store double [[B:%.*]], double* [[B_ADDR]], align 8 188 // CHECK-DEBUG-NEXT: call void @llvm.dbg.declare(metadata double* [[B_ADDR]], [[META137:metadata !.*]], metadata !DIExpression()), [[DBG138:!dbg !.*]] 189 // CHECK-DEBUG-NEXT: [[OMP_GLOBAL_THREAD_NUM:%.*]] = call i32 @__kmpc_global_thread_num(%struct.ident_t* [[GLOB13:@.*]]), [[DBG139:!dbg !.*]] 190 // CHECK-DEBUG-NEXT: br label [[OMP_PARALLEL:%.*]] 191 // CHECK-DEBUG: omp_parallel: 192 // CHECK-DEBUG-NEXT: call void (%struct.ident_t*, i32, void (i32*, i32*, ...)*, ...) @__kmpc_fork_call(%struct.ident_t* [[GLOB13]], i32 3, void (i32*, i32*, ...)* bitcast (void (i32*, i32*, i32*, double*, float**)* @_Z14parallel_for_2Pfid..omp_par.23 to void (i32*, i32*, ...)*), i32* [[A_ADDR]], double* [[B_ADDR]], float** [[R_ADDR]]), [[DBG140:!dbg !.*]] 193 // CHECK-DEBUG-NEXT: br label [[OMP_PAR_OUTLINED_EXIT184:%.*]] 194 // CHECK-DEBUG: omp.par.outlined.exit184: 195 // CHECK-DEBUG-NEXT: br label [[OMP_PAR_EXIT_SPLIT:%.*]] 196 // CHECK-DEBUG: omp.par.exit.split: 197 // CHECK-DEBUG-NEXT: call void @llvm.dbg.declare(metadata i32* [[I185]], [[META144:metadata !.*]], metadata !DIExpression()), [[DBG147:!dbg !.*]] 198 // CHECK-DEBUG-NEXT: store i32 0, i32* [[I185]], align 4, [[DBG147]] 199 // CHECK-DEBUG-NEXT: [[TMP0:%.*]] = getelementptr inbounds [[STRUCT_ANON_17]], %struct.anon.17* [[AGG_CAPTURED186]], i32 0, i32 0, [[DBG148:!dbg !.*]] 200 // CHECK-DEBUG-NEXT: store i32* [[I185]], i32** [[TMP0]], align 8, [[DBG148]] 201 // CHECK-DEBUG-NEXT: [[TMP1:%.*]] = getelementptr inbounds [[STRUCT_ANON_18]], %struct.anon.18* [[AGG_CAPTURED187]], i32 0, i32 0, [[DBG148]] 202 // CHECK-DEBUG-NEXT: [[TMP2:%.*]] = load i32, i32* [[I185]], align 4, [[DBG149:!dbg !.*]] 203 // CHECK-DEBUG-NEXT: store i32 [[TMP2]], i32* [[TMP1]], align 4, [[DBG148]] 204 // CHECK-DEBUG-NEXT: call void @__captured_stmt.19(i32* [[DOTCOUNT_ADDR188]], %struct.anon.17* [[AGG_CAPTURED186]]), [[DBG148]] 205 // CHECK-DEBUG-NEXT: [[DOTCOUNT189:%.*]] = load i32, i32* [[DOTCOUNT_ADDR188]], align 4, [[DBG148]] 206 // CHECK-DEBUG-NEXT: br label [[OMP_LOOP_PREHEADER190:%.*]], [[DBG148]] 207 // CHECK-DEBUG: omp_loop.preheader190: 208 // CHECK-DEBUG-NEXT: store i32 0, i32* [[P_LOWERBOUND204]], align 4, [[DBG148]] 209 // CHECK-DEBUG-NEXT: [[TMP3:%.*]] = sub i32 [[DOTCOUNT189]], 1, [[DBG148]] 210 // CHECK-DEBUG-NEXT: store i32 [[TMP3]], i32* [[P_UPPERBOUND205]], align 4, [[DBG148]] 211 // CHECK-DEBUG-NEXT: store i32 1, i32* [[P_STRIDE206]], align 4, [[DBG148]] 212 // CHECK-DEBUG-NEXT: [[OMP_GLOBAL_THREAD_NUM207:%.*]] = call i32 @__kmpc_global_thread_num(%struct.ident_t* [[GLOB42:@.*]]), [[DBG148]] 213 // CHECK-DEBUG-NEXT: call void @__kmpc_for_static_init_4u(%struct.ident_t* [[GLOB42]], i32 [[OMP_GLOBAL_THREAD_NUM207]], i32 34, i32* [[P_LASTITER203]], i32* [[P_LOWERBOUND204]], i32* [[P_UPPERBOUND205]], i32* [[P_STRIDE206]], i32 1, i32 1), [[DBG148]] 214 // CHECK-DEBUG-NEXT: [[TMP4:%.*]] = load i32, i32* [[P_LOWERBOUND204]], align 4, [[DBG148]] 215 // CHECK-DEBUG-NEXT: [[TMP5:%.*]] = load i32, i32* [[P_UPPERBOUND205]], align 4, [[DBG148]] 216 // CHECK-DEBUG-NEXT: [[TMP6:%.*]] = sub i32 [[TMP5]], [[TMP4]], [[DBG148]] 217 // CHECK-DEBUG-NEXT: [[TMP7:%.*]] = add i32 [[TMP6]], 1, [[DBG148]] 218 // CHECK-DEBUG-NEXT: br label [[OMP_LOOP_HEADER191:%.*]], [[DBG148]] 219 // CHECK-DEBUG: omp_loop.header191: 220 // CHECK-DEBUG-NEXT: [[OMP_LOOP_IV197:%.*]] = phi i32 [ 0, [[OMP_LOOP_PREHEADER190]] ], [ [[OMP_LOOP_NEXT199:%.*]], [[OMP_LOOP_INC194:%.*]] ], [[DBG148]] 221 // CHECK-DEBUG-NEXT: br label [[OMP_LOOP_COND192:%.*]], [[DBG148]] 222 // CHECK-DEBUG: omp_loop.cond192: 223 // CHECK-DEBUG-NEXT: [[OMP_LOOP_CMP198:%.*]] = icmp ult i32 [[OMP_LOOP_IV197]], [[TMP7]], [[DBG148]] 224 // CHECK-DEBUG-NEXT: br i1 [[OMP_LOOP_CMP198]], label [[OMP_LOOP_BODY193:%.*]], label [[OMP_LOOP_EXIT195:%.*]], [[DBG148]] 225 // CHECK-DEBUG: omp_loop.body193: 226 // CHECK-DEBUG-NEXT: [[TMP8:%.*]] = add i32 [[OMP_LOOP_IV197]], [[TMP4]], [[DBG148]] 227 // CHECK-DEBUG-NEXT: call void @__captured_stmt.20(i32* [[I185]], i32 [[TMP8]], %struct.anon.18* [[AGG_CAPTURED187]]), [[DBG148]] 228 // CHECK-DEBUG-NEXT: [[TMP9:%.*]] = load i32, i32* [[A_ADDR]], align 4, [[DBG150:!dbg !.*]] 229 // CHECK-DEBUG-NEXT: [[CONV200:%.*]] = sitofp i32 [[TMP9]] to double, [[DBG150]] 230 // CHECK-DEBUG-NEXT: [[TMP10:%.*]] = load double, double* [[B_ADDR]], align 8, [[DBG151:!dbg !.*]] 231 // CHECK-DEBUG-NEXT: [[ADD201:%.*]] = fadd double [[CONV200]], [[TMP10]], [[DBG152:!dbg !.*]] 232 // CHECK-DEBUG-NEXT: [[CONV202:%.*]] = fptrunc double [[ADD201]] to float, [[DBG150]] 233 // CHECK-DEBUG-NEXT: [[TMP11:%.*]] = load float*, float** [[R_ADDR]], align 8, [[DBG153:!dbg !.*]] 234 // CHECK-DEBUG-NEXT: store float [[CONV202]], float* [[TMP11]], align 4, [[DBG154:!dbg !.*]] 235 // CHECK-DEBUG-NEXT: br label [[OMP_LOOP_INC194]], [[DBG148]] 236 // CHECK-DEBUG: omp_loop.inc194: 237 // CHECK-DEBUG-NEXT: [[OMP_LOOP_NEXT199]] = add nuw i32 [[OMP_LOOP_IV197]], 1, [[DBG148]] 238 // CHECK-DEBUG-NEXT: br label [[OMP_LOOP_HEADER191]], [[DBG148]] 239 // CHECK-DEBUG: omp_loop.exit195: 240 // CHECK-DEBUG-NEXT: call void @__kmpc_for_static_fini(%struct.ident_t* [[GLOB42]], i32 [[OMP_GLOBAL_THREAD_NUM207]]), [[DBG148]] 241 // CHECK-DEBUG-NEXT: [[OMP_GLOBAL_THREAD_NUM208:%.*]] = call i32 @__kmpc_global_thread_num(%struct.ident_t* [[GLOB42]]), [[DBG151]] 242 // CHECK-DEBUG-NEXT: call void @__kmpc_barrier(%struct.ident_t* [[GLOB43:@.*]], i32 [[OMP_GLOBAL_THREAD_NUM208]]), [[DBG151]] 243 // CHECK-DEBUG-NEXT: br label [[OMP_LOOP_AFTER196:%.*]], [[DBG148]] 244 // CHECK-DEBUG: omp_loop.after196: 245 // CHECK-DEBUG-NEXT: ret void, [[DBG155:!dbg !.*]] 246 // 247 void parallel_for_2(float *r, int a, double b) { 248 #pragma omp parallel 249 { 250 #pragma omp for 251 for (int i = 0; i < 100; ++i) 252 *r = a + b; 253 #pragma omp parallel 254 { 255 #pragma omp for 256 for (int i = 0; i < 100; ++i) 257 *r = a + b; 258 #pragma omp parallel 259 { 260 #pragma omp for 261 for (int i = 0; i < 100; ++i) 262 *r = a + b; 263 } 264 #pragma omp for 265 for (int i = 0; i < 100; ++i) 266 *r = a + b; 267 #pragma omp parallel 268 { 269 #pragma omp for 270 for (int i = 0; i < 100; ++i) 271 *r = a + b; 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 } 281 #pragma omp for 282 for (int i = 0; i < 100; ++i) 283 *r = a + b; 284 } 285 286 #endif 287