1
2
3
4
5
6
7
8
9
10
11
12
13
14
15
16
17
18
19
20
21
22
23
24
25
26
27
28
29
30
31
32
33
34
35
36
37
38
39
40
|
// -*- 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
|
