xref: /freebsd/contrib/llvm-project/libunwind/src/cet_unwind.h (revision 5ca8e32633c4ffbbcd6762e5888b6a4ba0708c6c)
1 //===----------------------------------------------------------------------===//
2 //
3 // Part of the LLVM Project, under the Apache License v2.0 with LLVM Exceptions.
4 // See https://llvm.org/LICENSE.txt for license information.
5 // SPDX-License-Identifier: Apache-2.0 WITH LLVM-exception
6 //
7 //
8 //===----------------------------------------------------------------------===//
9 
10 #ifndef LIBUNWIND_CET_UNWIND_H
11 #define LIBUNWIND_CET_UNWIND_H
12 
13 #include "libunwind.h"
14 
15 // Currently, CET is implemented on Linux x86 platforms.
16 #if defined(_LIBUNWIND_TARGET_LINUX) && defined(__CET__) && defined(__SHSTK__)
17 #define _LIBUNWIND_USE_CET 1
18 #endif
19 
20 #if defined(_LIBUNWIND_USE_CET)
21 #include <cet.h>
22 #include <immintrin.h>
23 
24 #define _LIBUNWIND_POP_CET_SSP(x)                                              \
25   do {                                                                         \
26     unsigned long ssp = _get_ssp();                                            \
27     if (ssp != 0) {                                                            \
28       unsigned int tmp = (x);                                                  \
29       while (tmp > 255) {                                                      \
30         _inc_ssp(255);                                                         \
31         tmp -= 255;                                                            \
32       }                                                                        \
33       _inc_ssp(tmp);                                                           \
34     }                                                                          \
35   } while (0)
36 #endif
37 
38 extern void *__libunwind_cet_get_registers(unw_cursor_t *);
39 extern void *__libunwind_cet_get_jump_target(void);
40 
41 #endif
42