libunwind/test/unwind_scalable_vectors.pass.cpp

   1 // -*- C++ -*-
   2 //===----------------------------------------------------------------------===//
   3 //
   4 // Part of the LLVM Project, under the Apache License v2.0 with LLVM Exceptions.
   5 // See https://llvm.org/LICENSE.txt for license information.
   6 // SPDX-License-Identifier: Apache-2.0 WITH LLVM-exception
   7 //
   8 //===----------------------------------------------------------------------===//
   9
  10 // REQUIRES: linux && target={{riscv64-.+}}
  11
  12 #undef NDEBUG
  13 #include <assert.h>
  14 #include <libunwind.h>
  15
  16 #ifdef __riscv_vector
  17 __attribute__((noinline)) extern "C" void stepper() {
  18   unw_cursor_t cursor;
  19   unw_context_t uc;
  20   unw_getcontext(&uc);
  21   unw_init_local(&cursor, &uc);
  22   // Stepping into foo() should succeed.
  23   assert(unw_step(&cursor) > 0);
  24   // Stepping past foo() should succeed, too.
  25   assert(unw_step(&cursor) > 0);
  26 }
  27
  28 // Check correct unwinding of frame with VLENB-sized objects (vector registers).
  29 __attribute__((noinline)) static void foo() {
  30   __rvv_int32m1_t v;
  31   asm volatile("" : "=vr"(v)); // Dummy inline asm to def v.
  32   stepper();                   // def-use of v has cross the function, so that
  33                                // will triger spill/reload to/from the stack.
  34   asm volatile("" ::"vr"(v));  // Dummy inline asm to use v.
  35 }
  36
  37 int main() { foo(); }
  38 #else
  39 int main() { return 0; }
  40 #endif