| // -*- C++ -*- |
| //===----------------------------------------------------------------------===// |
| // |
| // Part of the LLVM Project, under the Apache License v2.0 with LLVM Exceptions. |
| // See https://llvm.org/LICENSE.txt for license information. |
| // SPDX-License-Identifier: Apache-2.0 WITH LLVM-exception |
| // |
| //===----------------------------------------------------------------------===// |
| |
| // REQUIRES: linux && target={{riscv64-.+}} |
| |
| #undef NDEBUG |
| #include <assert.h> |
| #include <libunwind.h> |
| |
| #ifdef __riscv_vector |
| __attribute__((noinline)) extern "C" void stepper() { |
| unw_cursor_t cursor; |
| unw_context_t uc; |
| unw_getcontext(&uc); |
| unw_init_local(&cursor, &uc); |
| // Stepping into foo() should succeed. |
| assert(unw_step(&cursor) > 0); |
| // Stepping past foo() should succeed, too. |
| assert(unw_step(&cursor) > 0); |
| } |
| |
| // Check correct unwinding of frame with VLENB-sized objects (vector registers). |
| __attribute__((noinline)) static void foo() { |
| __rvv_int32m1_t v; |
| asm volatile("" : "=vr"(v)); // Dummy inline asm to def v. |
| stepper(); // def-use of v has cross the function, so that |
| // will triger spill/reload to/from the stack. |
| asm volatile("" ::"vr"(v)); // Dummy inline asm to use v. |
| } |
| |
| int main() { foo(); } |
| #else |
| int main() { return 0; } |
| #endif |
