offload/test/sanitizer/kernel_crash_single.c

   1 // clang-format off
   2 // RUN: %libomptarget-compile-generic
   3 // RUN: %not --crash env -u LLVM_DISABLE_SYMBOLIZATION OFFLOAD_TRACK_NUM_KERNEL_LAUNCH_TRACES=1 %libomptarget-run-generic 2>&1 | %fcheck-generic --check-prefixes=TRACE,NDEBG
   4 // RUN: %not --crash %libomptarget-run-generic 2>&1 | %fcheck-generic --check-prefixes=CHECK
   5 // RUN: %libomptarget-compile-generic -g
   6 // RUN: %not --crash env -u LLVM_DISABLE_SYMBOLIZATION OFFLOAD_TRACK_NUM_KERNEL_LAUNCH_TRACES=1 %libomptarget-run-generic 2>&1 | %fcheck-generic --check-prefixes=TRACE,DEBUG
   7 // RUN: %not --crash %libomptarget-run-generic 2>&1 | %fcheck-generic --check-prefixes=CHECK
   8 // clang-format on
   9
  10 // UNSUPPORTED: nvptx64-nvidia-cuda
  11 // UNSUPPORTED: nvptx64-nvidia-cuda-LTO
  12 // UNSUPPORTED: aarch64-unknown-linux-gnu
  13 // UNSUPPORTED: aarch64-unknown-linux-gnu-LTO
  14 // UNSUPPORTED: x86_64-unknown-linux-gnu
  15 // UNSUPPORTED: x86_64-unknown-linux-gnu-LTO
  16 // UNSUPPORTED: s390x-ibm-linux-gnu
  17 // UNSUPPORTED: s390x-ibm-linux-gnu-LTO
  18
  19 #include <omp.h>
  20
  21 int main(void) {
  22   int *A = 0;
  23 #pragma omp target
  24   {
  25     *A = 42;
  26   }
  27 }
  28 // TRACE: Display kernel launch trace
  29 // TRACE: Kernel {{.*}} (__omp_offloading_{{.*}}_main_l23)
  30 // TRACE:     launchKernel
  31 // NDEBG:     main
  32 // DEBUG:     main {{.*}}kernel_crash_single.c:23
  33 //
  34 // CHECK: Display only launched kernel:
  35 // CHECK: Kernel {{.*}} (__omp_offloading_{{.*}}_main_l23)