llvm-project

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
41