1*9efdca87SJoseph Huber // NOTE: Assertions have been autogenerated by utils/update_cc_test_checks.py UTC_ARGS: --check-globals --global-value-regex "__omp_rtl_" 2*9efdca87SJoseph Huber // Test target codegen - host bc file has to be created first. 3*9efdca87SJoseph Huber // RUN: %clang_cc1 -verify -fopenmp -x c++ -triple powerpc64le-unknown-unknown -fopenmp-targets=nvptx64-nvidia-cuda -emit-llvm-bc %s -o %t-ppc-host.bc 4*9efdca87SJoseph Huber // RUN: %clang_cc1 -verify -fopenmp -x c++ -triple nvptx64-unknown-unknown -fopenmp-targets=nvptx64-nvidia-cuda -emit-llvm %s -fopenmp-target-new-runtime -fopenmp-target-debug -fopenmp-is-device -fopenmp-host-ir-file-path %t-ppc-host.bc -o - | FileCheck %s --check-prefix=CHECK 5*9efdca87SJoseph Huber // RUN: %clang_cc1 -verify -fopenmp -x c++ -triple nvptx64-unknown-unknown -fopenmp-targets=nvptx64-nvidia-cuda -emit-llvm %s -fopenmp-target-new-runtime -fopenmp-target-debug=111 -fopenmp-is-device -fopenmp-host-ir-file-path %t-ppc-host.bc -o - | FileCheck %s --check-prefix=CHECK-EQ 6*9efdca87SJoseph Huber // RUN: %clang_cc1 -verify -fopenmp -x c++ -triple nvptx64-unknown-unknown -fopenmp-targets=nvptx64-nvidia-cuda -emit-llvm %s -fopenmp-target-new-runtime -fopenmp-is-device -fopenmp-host-ir-file-path %t-ppc-host.bc -o - | FileCheck %s --check-prefix=CHECK-DEFAULT 7*9efdca87SJoseph Huber // RUN: %clang_cc1 -verify -fopenmp -x c++ -triple nvptx64-unknown-unknown -fopenmp-targets=nvptx64-nvidia-cuda -emit-llvm %s -fopenmp-target-new-runtime -fopenmp-assume-threads-oversubscription -fopenmp-is-device -fopenmp-host-ir-file-path %t-ppc-host.bc -o - | FileCheck %s --check-prefix=CHECK-THREADS 8*9efdca87SJoseph Huber // RUN: %clang_cc1 -verify -fopenmp -x c++ -triple nvptx64-unknown-unknown -fopenmp-targets=nvptx64-nvidia-cuda -emit-llvm %s -fopenmp-target-new-runtime -fopenmp-assume-teams-oversubscription -fopenmp-is-device -fopenmp-host-ir-file-path %t-ppc-host.bc -o - | FileCheck %s --check-prefix=CHECK-TEAMS 9*9efdca87SJoseph Huber // expected-no-diagnostics 10*9efdca87SJoseph Huber 11*9efdca87SJoseph Huber #ifndef HEADER 12*9efdca87SJoseph Huber #define HEADER 13*9efdca87SJoseph Huber 14*9efdca87SJoseph Huber //. 15*9efdca87SJoseph Huber // CHECK: @__omp_rtl_debug_kind = weak_odr constant i32 1 16*9efdca87SJoseph Huber // CHECK: @__omp_rtl_assume_teams_oversubscription = weak_odr constant i32 0 17*9efdca87SJoseph Huber // CHECK: @__omp_rtl_assume_threads_oversubscription = weak_odr constant i32 0 18*9efdca87SJoseph Huber //. 19*9efdca87SJoseph Huber // CHECK-EQ: @__omp_rtl_debug_kind = weak_odr constant i32 111 20*9efdca87SJoseph Huber // CHECK-EQ: @__omp_rtl_assume_teams_oversubscription = weak_odr constant i32 0 21*9efdca87SJoseph Huber // CHECK-EQ: @__omp_rtl_assume_threads_oversubscription = weak_odr constant i32 0 22*9efdca87SJoseph Huber //. 23*9efdca87SJoseph Huber // CHECK-DEFAULT: @__omp_rtl_debug_kind = weak_odr constant i32 0 24*9efdca87SJoseph Huber // CHECK-DEFAULT: @__omp_rtl_assume_teams_oversubscription = weak_odr constant i32 0 25*9efdca87SJoseph Huber // CHECK-DEFAULT: @__omp_rtl_assume_threads_oversubscription = weak_odr constant i32 0 26*9efdca87SJoseph Huber //. 27*9efdca87SJoseph Huber // CHECK-THREADS: @__omp_rtl_debug_kind = weak_odr constant i32 0 28*9efdca87SJoseph Huber // CHECK-THREADS: @__omp_rtl_assume_teams_oversubscription = weak_odr constant i32 0 29*9efdca87SJoseph Huber // CHECK-THREADS: @__omp_rtl_assume_threads_oversubscription = weak_odr constant i32 1 30*9efdca87SJoseph Huber //. 31*9efdca87SJoseph Huber // CHECK-TEAMS: @__omp_rtl_debug_kind = weak_odr constant i32 0 32*9efdca87SJoseph Huber // CHECK-TEAMS: @__omp_rtl_assume_teams_oversubscription = weak_odr constant i32 1 33*9efdca87SJoseph Huber // CHECK-TEAMS: @__omp_rtl_assume_threads_oversubscription = weak_odr constant i32 0 34*9efdca87SJoseph Huber //. 35*9efdca87SJoseph Huber void foo() { 36*9efdca87SJoseph Huber #pragma omp target 37*9efdca87SJoseph Huber { } 38*9efdca87SJoseph Huber } 39*9efdca87SJoseph Huber 40*9efdca87SJoseph Huber #endif 41