diff options
| author | Alexey Bataev <a.bataev@hotmail.com> | 2015-03-11 04:48:56 +0000 |
|---|---|---|
| committer | Alexey Bataev <a.bataev@hotmail.com> | 2015-03-11 04:48:56 +0000 |
| commit | 10fec57e5a4508eb0fee4cc76c4cc68e21ddf345 (patch) | |
| tree | add4768d94937730fbacd523637fd9aef740e9eb /clang/test/OpenMP/atomic_codegen.cpp | |
| parent | 23562fcfe971131a0545e51c1a77cc1179c10736 (diff) | |
| download | bcm5719-llvm-10fec57e5a4508eb0fee4cc76c4cc68e21ddf345.tar.gz bcm5719-llvm-10fec57e5a4508eb0fee4cc76c4cc68e21ddf345.zip | |
[OPENMP] Fix for ExprWithCleanups in 'omp atomic' constructs.
This patch allows using of ExprWithCleanups expressions and other complex expressions in 'omp atomic' construct
Differential Revision: http://reviews.llvm.org/D8200
llvm-svn: 231905
Diffstat (limited to 'clang/test/OpenMP/atomic_codegen.cpp')
| -rw-r--r-- | clang/test/OpenMP/atomic_codegen.cpp | 36 |
1 files changed, 33 insertions, 3 deletions
diff --git a/clang/test/OpenMP/atomic_codegen.cpp b/clang/test/OpenMP/atomic_codegen.cpp index b80726f75be..e78720db666 100644 --- a/clang/test/OpenMP/atomic_codegen.cpp +++ b/clang/test/OpenMP/atomic_codegen.cpp @@ -1,7 +1,37 @@ +// RUN: %clang_cc1 -verify -triple x86_64-apple-darwin10 -fopenmp=libiomp5 -fexceptions -fcxx-exceptions -x c++ -emit-llvm %s -o - | FileCheck %s // RUN: %clang_cc1 -verify -triple x86_64-apple-darwin10 -fopenmp=libiomp5 -fexceptions -fcxx-exceptions -gline-tables-only -x c++ -emit-llvm %s -o - | FileCheck %s --check-prefix=TERM_DEBUG // expected-no-diagnostics int a; +int b; + +struct St { + St() {} + ~St() {} + int &get() { return a; } +}; + +// CHECK-LABEL: parallel_atomic_ewc +void parallel_atomic_ewc() { +#pragma omp parallel + { + // CHECK: invoke void @_ZN2StC1Ev(%struct.St* [[TEMP_ST_ADDR:%.+]]) + // CHECK: [[SCALAR_ADDR:%.+]] = invoke dereferenceable(4) i32* @_ZN2St3getEv(%struct.St* [[TEMP_ST_ADDR]]) + // CHECK: [[SCALAR_VAL:%.+]] = load atomic i32, i32* [[SCALAR_ADDR]] monotonic + // CHECK: store i32 [[SCALAR_VAL]], i32* @b + // CHECK: invoke void @_ZN2StD1Ev(%struct.St* [[TEMP_ST_ADDR]]) +#pragma omp atomic read + b = St().get(); + // CHECK: invoke void @_ZN2StC1Ev(%struct.St* [[TEMP_ST_ADDR:%.+]]) + // CHECK: [[SCALAR_ADDR:%.+]] = invoke dereferenceable(4) i32* @_ZN2St3getEv(%struct.St* [[TEMP_ST_ADDR]]) + // CHECK: [[B_VAL:%.+]] = load i32, i32* @b + // CHECK: store atomic i32 [[B_VAL]], i32* [[SCALAR_ADDR]] monotonic + // CHECK: invoke void @_ZN2StD1Ev(%struct.St* [[TEMP_ST_ADDR]]) +#pragma omp atomic write + St().get() = b; + } +} + int &foo() { return a; } // TERM_DEBUG-LABEL: parallel_atomic @@ -12,7 +42,7 @@ void parallel_atomic() { // TERM_DEBUG-NOT: __kmpc_global_thread_num // TERM_DEBUG: invoke {{.*}}foo{{.*}}() // TERM_DEBUG: unwind label %[[TERM_LPAD:.+]], - // TERM_DEBUG: load atomic i32, i32* @{{.+}} monotonic, {{.*}}!dbg [[READ_LOC:![0-9]+]] + // TERM_DEBUG: load atomic i32, i32* @{{.+}} monotonic, {{.*}}!dbg [[READ_LOC:![0-9]+]] foo() = a; #pragma omp atomic write // TERM_DEBUG-NOT: __kmpc_global_thread_num @@ -26,5 +56,5 @@ void parallel_atomic() { a = foo(); } } -// TERM_DEBUG-DAG: [[READ_LOC]] = !MDLocation(line: 11, -// TERM_DEBUG-DAG: [[WRITE_LOC]] = !MDLocation(line: 17, +// TERM_DEBUG-DAG: [[READ_LOC]] = !MDLocation(line: 41, +// TERM_DEBUG-DAG: [[WRITE_LOC]] = !MDLocation(line: 47, |
