File Manager

003 File Manager

Current Path: /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 */

003 File Manager

Editing: arm_cmse.h

Upload File

Create Folder