17af287d0SJohannes Doerfert // NOTE: Assertions have been autogenerated by utils/update_cc_test_checks.py
2*532dc62bSNikita Popov // RUN: %clang_cc1 -no-opaque-pointers -verify -fopenmp -fopenmp-enable-irbuilder -x c++ -emit-llvm %s -triple x86_64-unknown-unknown -fexceptions -fcxx-exceptions -o - | FileCheck %s --check-prefixes=ALL,IRBUILDER
3*532dc62bSNikita Popov // %clang_cc1 -no-opaque-pointers -fopenmp -fopenmp-enable-irbuilder -x c++ -std=c++11 -triple x86_64-unknown-unknown -fexceptions -fcxx-exceptions -emit-pch -o /tmp/t1 %s
4*532dc62bSNikita Popov // %clang_cc1 -no-opaque-pointers -fopenmp -fopenmp-enable-irbuilder -x c++ -triple x86_64-unknown-unknown -fexceptions -fcxx-exceptions -debug-info-kind=limited -std=c++11 -include-pch /tmp/t1 -verify %s -emit-llvm -o - | FileCheck --check-prefixes=ALL-DEBUG,IRBUILDER-DEBUG %s
57af287d0SJohannes Doerfert
67af287d0SJohannes Doerfert // expected-no-diagnostics
77af287d0SJohannes Doerfert
87af287d0SJohannes Doerfert // TODO: Teach the update script to check new functions too.
97af287d0SJohannes Doerfert
107af287d0SJohannes Doerfert #ifndef HEADER
117af287d0SJohannes Doerfert #define HEADER
127af287d0SJohannes Doerfert
137af287d0SJohannes Doerfert // ALL-LABEL: @_Z17nested_parallel_0v(
147af287d0SJohannes Doerfert // ALL-NEXT: entry:
15df729e2bSJohannes Doerfert // ALL-NEXT: [[OMP_GLOBAL_THREAD_NUM:%.*]] = call i32 @__kmpc_global_thread_num(%struct.ident_t* @[[GLOB1:[0-9]+]])
167af287d0SJohannes Doerfert // ALL-NEXT: br label [[OMP_PARALLEL:%.*]]
177af287d0SJohannes Doerfert // ALL: omp_parallel:
18df729e2bSJohannes Doerfert // ALL-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*)* @_Z17nested_parallel_0v..omp_par.1 to void (i32*, i32*, ...)*))
197af287d0SJohannes Doerfert // ALL-NEXT: br label [[OMP_PAR_OUTLINED_EXIT12:%.*]]
207af287d0SJohannes Doerfert // ALL: omp.par.outlined.exit12:
217af287d0SJohannes Doerfert // ALL-NEXT: br label [[OMP_PAR_EXIT_SPLIT:%.*]]
227af287d0SJohannes Doerfert // ALL: omp.par.exit.split:
237af287d0SJohannes Doerfert // ALL-NEXT: ret void
247af287d0SJohannes Doerfert //
nested_parallel_0(void)257af287d0SJohannes Doerfert void nested_parallel_0(void) {
267af287d0SJohannes Doerfert #pragma omp parallel
277af287d0SJohannes Doerfert {
287af287d0SJohannes Doerfert #pragma omp parallel
297af287d0SJohannes Doerfert {
307af287d0SJohannes Doerfert }
317af287d0SJohannes Doerfert }
327af287d0SJohannes Doerfert }
337af287d0SJohannes Doerfert
347af287d0SJohannes Doerfert // ALL-LABEL: @_Z17nested_parallel_1Pfid(
357af287d0SJohannes Doerfert // ALL-NEXT: entry:
3687ec6f41SWilliam S. Moses // ALL-NEXT: [[STRUCTARG14:%.*]] = alloca { i32*, double*, float** }, align 8
377af287d0SJohannes Doerfert // ALL-NEXT: [[R_ADDR:%.*]] = alloca float*, align 8
387af287d0SJohannes Doerfert // ALL-NEXT: [[A_ADDR:%.*]] = alloca i32, align 4
397af287d0SJohannes Doerfert // ALL-NEXT: [[B_ADDR:%.*]] = alloca double, align 8
407af287d0SJohannes Doerfert // ALL-NEXT: store float* [[R:%.*]], float** [[R_ADDR]], align 8
417af287d0SJohannes Doerfert // ALL-NEXT: store i32 [[A:%.*]], i32* [[A_ADDR]], align 4
427af287d0SJohannes Doerfert // ALL-NEXT: store double [[B:%.*]], double* [[B_ADDR]], align 8
43df729e2bSJohannes Doerfert // ALL-NEXT: [[OMP_GLOBAL_THREAD_NUM:%.*]] = call i32 @__kmpc_global_thread_num(%struct.ident_t* @[[GLOB1]])
447af287d0SJohannes Doerfert // ALL-NEXT: br label [[OMP_PARALLEL:%.*]]
457af287d0SJohannes Doerfert // ALL: omp_parallel:
4687ec6f41SWilliam S. Moses // ALL-NEXT: [[GEP_A_ADDR15:%.*]] = getelementptr { i32*, double*, float** }, { i32*, double*, float** }* [[STRUCTARG14]], i32 0, i32 0
477cb4c261SGiorgis Georgakoudis // ALL-NEXT: store i32* [[A_ADDR]], i32** [[GEP_A_ADDR15]], align 8
4887ec6f41SWilliam S. Moses // ALL-NEXT: [[GEP_B_ADDR16:%.*]] = getelementptr { i32*, double*, float** }, { i32*, double*, float** }* [[STRUCTARG14]], i32 0, i32 1
497cb4c261SGiorgis Georgakoudis // ALL-NEXT: store double* [[B_ADDR]], double** [[GEP_B_ADDR16]], align 8
5087ec6f41SWilliam S. Moses // ALL-NEXT: [[GEP_R_ADDR17:%.*]] = getelementptr { i32*, double*, float** }, { i32*, double*, float** }* [[STRUCTARG14]], i32 0, i32 2
517cb4c261SGiorgis Georgakoudis // ALL-NEXT: store float** [[R_ADDR]], float*** [[GEP_R_ADDR17]], align 8
5287ec6f41SWilliam S. Moses // ALL-NEXT: call void (%struct.ident_t*, i32, void (i32*, i32*, ...)*, ...) @__kmpc_fork_call(%struct.ident_t* @[[GLOB1]], i32 1, void (i32*, i32*, ...)* bitcast (void (i32*, i32*, { i32*, double*, float** }*)* @_Z17nested_parallel_1Pfid..omp_par.2 to void (i32*, i32*, ...)*), { i32*, double*, float** }* [[STRUCTARG14]])
537af287d0SJohannes Doerfert // ALL-NEXT: br label [[OMP_PAR_OUTLINED_EXIT13:%.*]]
547af287d0SJohannes Doerfert // ALL: omp.par.outlined.exit13:
557af287d0SJohannes Doerfert // ALL-NEXT: br label [[OMP_PAR_EXIT_SPLIT:%.*]]
567af287d0SJohannes Doerfert // ALL: omp.par.exit.split:
577af287d0SJohannes Doerfert // ALL-NEXT: ret void
587af287d0SJohannes Doerfert //
nested_parallel_1(float * r,int a,double b)597af287d0SJohannes Doerfert void nested_parallel_1(float *r, int a, double b) {
607af287d0SJohannes Doerfert #pragma omp parallel
617af287d0SJohannes Doerfert {
627af287d0SJohannes Doerfert #pragma omp parallel
637af287d0SJohannes Doerfert {
647af287d0SJohannes Doerfert *r = a + b;
657af287d0SJohannes Doerfert }
667af287d0SJohannes Doerfert }
677af287d0SJohannes Doerfert }
687af287d0SJohannes Doerfert
697af287d0SJohannes Doerfert // ALL-LABEL: @_Z17nested_parallel_2Pfid(
707af287d0SJohannes Doerfert // ALL-NEXT: entry:
717cb4c261SGiorgis Georgakoudis // ALL-NEXT: [[STRUCTARG:%.*]] = alloca { i32*, double*, float** }, align 8
727af287d0SJohannes Doerfert // ALL-NEXT: [[R_ADDR:%.*]] = alloca float*, align 8
737af287d0SJohannes Doerfert // ALL-NEXT: [[A_ADDR:%.*]] = alloca i32, align 4
747af287d0SJohannes Doerfert // ALL-NEXT: [[B_ADDR:%.*]] = alloca double, align 8
757af287d0SJohannes Doerfert // ALL-NEXT: store float* [[R:%.*]], float** [[R_ADDR]], align 8
767af287d0SJohannes Doerfert // ALL-NEXT: store i32 [[A:%.*]], i32* [[A_ADDR]], align 4
777af287d0SJohannes Doerfert // ALL-NEXT: store double [[B:%.*]], double* [[B_ADDR]], align 8
78df729e2bSJohannes Doerfert // ALL-NEXT: [[OMP_GLOBAL_THREAD_NUM:%.*]] = call i32 @__kmpc_global_thread_num(%struct.ident_t* @[[GLOB1]])
797af287d0SJohannes Doerfert // ALL-NEXT: br label [[OMP_PARALLEL:%.*]]
807af287d0SJohannes Doerfert // ALL: omp_parallel:
8187ec6f41SWilliam S. Moses // ALL-NEXT: [[GEP_A_ADDR:%.*]] = getelementptr { i32*, double*, float** }, { i32*, double*, float** }* [[STRUCTARG]], i32 0, i32 0
827cb4c261SGiorgis Georgakoudis // ALL-NEXT: store i32* [[A_ADDR]], i32** [[GEP_A_ADDR]], align 8
8387ec6f41SWilliam S. Moses // ALL-NEXT: [[GEP_B_ADDR:%.*]] = getelementptr { i32*, double*, float** }, { i32*, double*, float** }* [[STRUCTARG]], i32 0, i32 1
847cb4c261SGiorgis Georgakoudis // ALL-NEXT: store double* [[B_ADDR]], double** [[GEP_B_ADDR]], align 8
8587ec6f41SWilliam S. Moses // ALL-NEXT: [[GEP_R_ADDR:%.*]] = getelementptr { i32*, double*, float** }, { i32*, double*, float** }* [[STRUCTARG]], i32 0, i32 2
867cb4c261SGiorgis Georgakoudis // ALL-NEXT: store float** [[R_ADDR]], float*** [[GEP_R_ADDR]], align 8
8787ec6f41SWilliam S. Moses // ALL-NEXT: call void (%struct.ident_t*, i32, void (i32*, i32*, ...)*, ...) @__kmpc_fork_call(%struct.ident_t* @[[GLOB1]], i32 1, void (i32*, i32*, ...)* bitcast (void (i32*, i32*, { i32*, double*, float** }*)* @_Z17nested_parallel_2Pfid..omp_par.5 to void (i32*, i32*, ...)*), { i32*, double*, float** }* [[STRUCTARG]])
887af287d0SJohannes Doerfert // ALL-NEXT: br label [[OMP_PAR_OUTLINED_EXIT55:%.*]]
897af287d0SJohannes Doerfert // ALL: omp.par.outlined.exit55:
907af287d0SJohannes Doerfert // ALL-NEXT: br label [[OMP_PAR_EXIT_SPLIT:%.*]]
917af287d0SJohannes Doerfert // ALL: omp.par.exit.split:
927af287d0SJohannes Doerfert // ALL-NEXT: [[TMP0:%.*]] = load i32, i32* [[A_ADDR]], align 4
937af287d0SJohannes Doerfert // ALL-NEXT: [[CONV56:%.*]] = sitofp i32 [[TMP0]] to double
947af287d0SJohannes Doerfert // ALL-NEXT: [[TMP1:%.*]] = load double, double* [[B_ADDR]], align 8
957af287d0SJohannes Doerfert // ALL-NEXT: [[ADD57:%.*]] = fadd double [[CONV56]], [[TMP1]]
967af287d0SJohannes Doerfert // ALL-NEXT: [[CONV58:%.*]] = fptrunc double [[ADD57]] to float
977af287d0SJohannes Doerfert // ALL-NEXT: [[TMP2:%.*]] = load float*, float** [[R_ADDR]], align 8
987af287d0SJohannes Doerfert // ALL-NEXT: store float [[CONV58]], float* [[TMP2]], align 4
997af287d0SJohannes Doerfert // ALL-NEXT: ret void
1007af287d0SJohannes Doerfert //
nested_parallel_2(float * r,int a,double b)1017af287d0SJohannes Doerfert void nested_parallel_2(float *r, int a, double b) {
1027af287d0SJohannes Doerfert #pragma omp parallel
1037af287d0SJohannes Doerfert {
1047af287d0SJohannes Doerfert *r = a + b;
1057af287d0SJohannes Doerfert #pragma omp parallel
1067af287d0SJohannes Doerfert {
1077af287d0SJohannes Doerfert *r = a + b;
1087af287d0SJohannes Doerfert #pragma omp parallel
1097af287d0SJohannes Doerfert {
1107af287d0SJohannes Doerfert *r = a + b;
1117af287d0SJohannes Doerfert }
1127af287d0SJohannes Doerfert *r = a + b;
1137af287d0SJohannes Doerfert #pragma omp parallel
1147af287d0SJohannes Doerfert {
1157af287d0SJohannes Doerfert *r = a + b;
1167af287d0SJohannes Doerfert }
1177af287d0SJohannes Doerfert *r = a + b;
1187af287d0SJohannes Doerfert }
1197af287d0SJohannes Doerfert *r = a + b;
1207af287d0SJohannes Doerfert }
1217af287d0SJohannes Doerfert *r = a + b;
1227af287d0SJohannes Doerfert }
1237af287d0SJohannes Doerfert
1247af287d0SJohannes Doerfert #endif
125