003 File Manager
Current Path:
/usr/lib/clang/11.0.1/include
usr
/
lib
/
clang
/
11.0.1
/
include
/
📁
..
📄
__clang_cuda_builtin_vars.h
(4.56 KB)
📄
__clang_cuda_cmath.h
(16.37 KB)
📄
__clang_cuda_complex_builtins.h
(8.5 KB)
📄
__clang_cuda_device_functions.h
(55.59 KB)
📄
__clang_cuda_intrinsics.h
(21.59 KB)
📄
__clang_cuda_libdevice_declares.h
(21.73 KB)
📄
__clang_cuda_math.h
(15.91 KB)
📄
__clang_cuda_math_forward_declares.h
(8.21 KB)
📄
__clang_cuda_runtime_wrapper.h
(14.85 KB)
📄
__clang_hip_libdevice_declares.h
(19.19 KB)
📄
__clang_hip_math.h
(35.41 KB)
📄
__clang_hip_runtime_wrapper.h
(1.79 KB)
📄
__stddef_max_align_t.h
(857 B)
📄
__wmmintrin_aes.h
(5.14 KB)
📄
__wmmintrin_pclmul.h
(2.01 KB)
📄
adxintrin.h
(2.32 KB)
📄
altivec.h
(609.12 KB)
📄
ammintrin.h
(7.42 KB)
📄
amxintrin.h
(8.24 KB)
📄
arm64intr.h
(993 B)
📄
arm_acle.h
(21.87 KB)
📄
arm_bf16.h
(548 B)
📄
arm_cde.h
(32.67 KB)
📄
arm_cmse.h
(6.21 KB)
📄
arm_fp16.h
(16.97 KB)
📄
arm_mve.h
(1.48 MB)
📄
arm_neon.h
(2.31 MB)
📄
arm_sve.h
(1.14 MB)
📄
armintr.h
(843 B)
📄
avx2intrin.h
(38.11 KB)
📄
avx512bf16intrin.h
(10.45 KB)
📄
avx512bitalgintrin.h
(2.41 KB)
📄
avx512bwintrin.h
(75.17 KB)
📄
avx512cdintrin.h
(4.12 KB)
📄
avx512dqintrin.h
(58.3 KB)
📄
avx512erintrin.h
(11.7 KB)
📄
avx512fintrin.h
(377.18 KB)
📄
avx512ifmaintrin.h
(2.49 KB)
📄
avx512ifmavlintrin.h
(4.44 KB)
📄
avx512pfintrin.h
(4.53 KB)
📄
avx512vbmi2intrin.h
(13.1 KB)
📄
avx512vbmiintrin.h
(3.72 KB)
📄
avx512vbmivlintrin.h
(6.94 KB)
📄
avx512vlbf16intrin.h
(17.88 KB)
📄
avx512vlbitalgintrin.h
(4.23 KB)
📄
avx512vlbwintrin.h
(110.39 KB)
📄
avx512vlcdintrin.h
(7.66 KB)
📄
avx512vldqintrin.h
(46.24 KB)
📄
avx512vlintrin.h
(322.04 KB)
📄
avx512vlvbmi2intrin.h
(25.59 KB)
📄
avx512vlvnniintrin.h
(7.87 KB)
📄
avx512vlvp2intersectintrin.h
(4.44 KB)
📄
avx512vnniintrin.h
(4.21 KB)
📄
avx512vp2intersectintrin.h
(2.9 KB)
📄
avx512vpopcntdqintrin.h
(2 KB)
📄
avx512vpopcntdqvlintrin.h
(3.31 KB)
📄
avxintrin.h
(193.62 KB)
📄
bmi2intrin.h
(2.25 KB)
📄
bmiintrin.h
(14.02 KB)
📄
cet.h
(1.49 KB)
📄
cetintrin.h
(2.78 KB)
📄
cldemoteintrin.h
(1.18 KB)
📄
clflushoptintrin.h
(861 B)
📄
clwbintrin.h
(1.2 KB)
📄
clzerointrin.h
(1.13 KB)
📄
cpuid.h
(10.42 KB)
📁
cuda_wrappers
📄
emmintrin.h
(180.78 KB)
📄
enqcmdintrin.h
(2.12 KB)
📄
f16cintrin.h
(5.37 KB)
📄
fma4intrin.h
(6.82 KB)
📄
fmaintrin.h
(6.83 KB)
📁
fuzzer
📄
fxsrintrin.h
(2.82 KB)
📄
gfniintrin.h
(7.66 KB)
📄
htmintrin.h
(6.14 KB)
📄
htmxlintrin.h
(9.01 KB)
📄
ia32intrin.h
(12.65 KB)
📄
immintrin.h
(18.38 KB)
📄
invpcidintrin.h
(764 B)
📄
lwpintrin.h
(5 KB)
📄
lzcntintrin.h
(3.18 KB)
📄
mm3dnow.h
(4.5 KB)
📄
mm_malloc.h
(1.7 KB)
📄
mmintrin.h
(55.85 KB)
📄
module.modulemap
(3.33 KB)
📄
movdirintrin.h
(1.57 KB)
📄
msa.h
(25.01 KB)
📄
mwaitxintrin.h
(1.07 KB)
📄
nmmintrin.h
(580 B)
📄
opencl-c-base.h
(20.83 KB)
📄
opencl-c.h
(835.47 KB)
📁
openmp_wrappers
📄
pconfigintrin.h
(1.19 KB)
📄
pkuintrin.h
(934 B)
📄
pmmintrin.h
(10.09 KB)
📄
popcntintrin.h
(1.58 KB)
📁
ppc_wrappers
📄
prfchwintrin.h
(1.93 KB)
📁
profile
📄
ptwriteintrin.h
(1.05 KB)
📄
rdseedintrin.h
(1.16 KB)
📄
rtmintrin.h
(1.24 KB)
📄
s390intrin.h
(604 B)
📁
sanitizer
📄
serializeintrin.h
(881 B)
📄
sgxintrin.h
(1.77 KB)
📄
shaintrin.h
(1.87 KB)
📄
smmintrin.h
(98.76 KB)
📄
tbmintrin.h
(3.15 KB)
📄
tmmintrin.h
(29.37 KB)
📄
tsxldtrkintrin.h
(1.97 KB)
📄
vadefs.h
(1.39 KB)
📄
vaesintrin.h
(2.39 KB)
📄
vecintrin.h
(356.66 KB)
📄
vpclmulqdqintrin.h
(1 KB)
📄
waitpkgintrin.h
(1.33 KB)
📄
wasm_simd128.h
(45.99 KB)
📄
wbnoinvdintrin.h
(749 B)
📄
wmmintrin.h
(530 B)
📄
x86intrin.h
(1.67 KB)
📄
xmmintrin.h
(106.24 KB)
📄
xopintrin.h
(19.91 KB)
📁
xray
📄
xsavecintrin.h
(1010 B)
📄
xsaveintrin.h
(1.64 KB)
📄
xsaveoptintrin.h
(1 KB)
📄
xsavesintrin.h
(1.24 KB)
📄
xtestintrin.h
(873 B)
Editing: arm_cmse.h
//===---- arm_cmse.h - Arm CMSE support -----------------------------------===// // // 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 // //===----------------------------------------------------------------------===// #ifndef __ARM_CMSE_H #define __ARM_CMSE_H #if (__ARM_FEATURE_CMSE & 0x1) #include <stddef.h> #include <stdint.h> #define __ARM_CMSE_SECURE_MODE (__ARM_FEATURE_CMSE & 0x2) #define CMSE_MPU_READWRITE 1 /* checks if readwrite_ok field is set */ #define CMSE_AU_NONSECURE 2 /* checks if permissions have secure field unset */ #define CMSE_MPU_UNPRIV 4 /* sets T flag on TT insrtuction */ #define CMSE_MPU_READ 8 /* checks if read_ok field is set */ #define CMSE_MPU_NONSECURE 16 /* sets A flag, checks if secure field unset */ #define CMSE_NONSECURE (CMSE_AU_NONSECURE | CMSE_MPU_NONSECURE) #define cmse_check_pointed_object(p, f) \ cmse_check_address_range((p), sizeof(*(p)), (f)) #if defined(__cplusplus) extern "C" { #endif typedef union { struct cmse_address_info { #ifdef __ARM_BIG_ENDIAN /* __ARM_BIG_ENDIAN */ #if (__ARM_CMSE_SECURE_MODE) unsigned idau_region : 8; unsigned idau_region_valid : 1; unsigned secure : 1; unsigned nonsecure_readwrite_ok : 1; unsigned nonsecure_read_ok : 1; #else unsigned : 12; #endif unsigned readwrite_ok : 1; unsigned read_ok : 1; #if (__ARM_CMSE_SECURE_MODE) unsigned sau_region_valid : 1; #else unsigned : 1; #endif unsigned mpu_region_valid : 1; #if (__ARM_CMSE_SECURE_MODE) unsigned sau_region : 8; #else unsigned : 8; #endif unsigned mpu_region : 8; #else /* __ARM_LITTLE_ENDIAN */ unsigned mpu_region : 8; #if (__ARM_CMSE_SECURE_MODE) unsigned sau_region : 8; #else unsigned : 8; #endif unsigned mpu_region_valid : 1; #if (__ARM_CMSE_SECURE_MODE) unsigned sau_region_valid : 1; #else unsigned : 1; #endif unsigned read_ok : 1; unsigned readwrite_ok : 1; #if (__ARM_CMSE_SECURE_MODE) unsigned nonsecure_read_ok : 1; unsigned nonsecure_readwrite_ok : 1; unsigned secure : 1; unsigned idau_region_valid : 1; unsigned idau_region : 8; #else unsigned : 12; #endif #endif /*__ARM_LITTLE_ENDIAN */ } flags; unsigned value; } cmse_address_info_t; static cmse_address_info_t __attribute__((__always_inline__, __nodebug__)) cmse_TT(void *__p) { cmse_address_info_t __u; __u.value = __builtin_arm_cmse_TT(__p); return __u; } static cmse_address_info_t __attribute__((__always_inline__, __nodebug__)) cmse_TTT(void *__p) { cmse_address_info_t __u; __u.value = __builtin_arm_cmse_TTT(__p); return __u; } #if __ARM_CMSE_SECURE_MODE static cmse_address_info_t __attribute__((__always_inline__, __nodebug__)) cmse_TTA(void *__p) { cmse_address_info_t __u; __u.value = __builtin_arm_cmse_TTA(__p); return __u; } static cmse_address_info_t __attribute__((__always_inline__, __nodebug__)) cmse_TTAT(void *__p) { cmse_address_info_t __u; __u.value = __builtin_arm_cmse_TTAT(__p); return __u; } #endif #define cmse_TT_fptr(p) cmse_TT(__builtin_bit_cast(void *, (p))) #define cmse_TTT_fptr(p) cmse_TTT(__builtin_bit_cast(void *, (p))) #if __ARM_CMSE_SECURE_MODE #define cmse_TTA_fptr(p) cmse_TTA(__builtin_bit_cast(void *, (p))) #define cmse_TTAT_fptr(p) cmse_TTAT(__builtin_bit_cast(void *, (p))) #endif static void *__attribute__((__always_inline__)) cmse_check_address_range(void *__pb, size_t __s, int __flags) { uintptr_t __begin = (uintptr_t)__pb; uintptr_t __end = __begin + __s - 1; if (__end < __begin) return NULL; /* wrap around check */ /* Check whether the range crosses a 32-bytes aligned address */ const int __single_check = (__begin ^ __end) < 0x20u; /* execute the right variant of the TT instructions */ void *__pe = (void *)__end; cmse_address_info_t __permb, __perme; switch (__flags & (CMSE_MPU_UNPRIV | CMSE_MPU_NONSECURE)) { case 0: __permb = cmse_TT(__pb); __perme = __single_check ? __permb : cmse_TT(__pe); break; case CMSE_MPU_UNPRIV: __permb = cmse_TTT(__pb); __perme = __single_check ? __permb : cmse_TTT(__pe); break; #if __ARM_CMSE_SECURE_MODE case CMSE_MPU_NONSECURE: __permb = cmse_TTA(__pb); __perme = __single_check ? __permb : cmse_TTA(__pe); break; case CMSE_MPU_UNPRIV | CMSE_MPU_NONSECURE: __permb = cmse_TTAT(__pb); __perme = __single_check ? __permb : cmse_TTAT(__pe); break; #endif /* if CMSE_NONSECURE is specified w/o __ARM_CMSE_SECURE_MODE */ default: return NULL; } /* check that the range does not cross MPU, SAU, or IDAU region boundaries */ if (__permb.value != __perme.value) return NULL; #if !(__ARM_CMSE_SECURE_MODE) /* CMSE_AU_NONSECURE is only supported when __ARM_FEATURE_CMSE & 0x2 */ if (__flags & CMSE_AU_NONSECURE) return NULL; #endif /* check the permission on the range */ switch (__flags & ~(CMSE_MPU_UNPRIV | CMSE_MPU_NONSECURE)) { #if (__ARM_CMSE_SECURE_MODE) case CMSE_MPU_READ | CMSE_MPU_READWRITE | CMSE_AU_NONSECURE: case CMSE_MPU_READWRITE | CMSE_AU_NONSECURE: return __permb.flags.nonsecure_readwrite_ok ? __pb : NULL; case CMSE_MPU_READ | CMSE_AU_NONSECURE: return __permb.flags.nonsecure_read_ok ? __pb : NULL; case CMSE_AU_NONSECURE: return __permb.flags.secure ? NULL : __pb; #endif case CMSE_MPU_READ | CMSE_MPU_READWRITE: case CMSE_MPU_READWRITE: return __permb.flags.readwrite_ok ? __pb : NULL; case CMSE_MPU_READ: return __permb.flags.read_ok ? __pb : NULL; default: return NULL; } } #if __ARM_CMSE_SECURE_MODE static int __attribute__((__always_inline__, __nodebug__)) cmse_nonsecure_caller(void) { return !((uintptr_t)__builtin_return_address(0) & 1); } #define cmse_nsfptr_create(p) \ __builtin_bit_cast(__typeof__(p), \ (__builtin_bit_cast(uintptr_t, p) & ~(uintptr_t)1)) #define cmse_is_nsfptr(p) ((__builtin_bit_cast(uintptr_t, p) & 1) == 0) #endif /* __ARM_CMSE_SECURE_MODE */ void __attribute__((__noreturn__)) cmse_abort(void); #if defined(__cplusplus) } #endif #endif /* (__ARM_FEATURE_CMSE & 0x1) */ #endif /* __ARM_CMSE_H */
Upload File
Create Folder