arm_acle.h File Reference

#include <stdint.h>

Go to the source code of this file.

Macros
#define	__pld(addr)
#define	__pldx(access_kind, cache_level, retention_policy, addr)
#define	__pli(addr)
#define	__plix(cache_level, retention_policy, addr)
#define	__arm_rsr(sysreg)
#define	__arm_rsr64(sysreg)
#define	__arm_rsr128(sysreg)
#define	__arm_rsrp(sysreg)
#define	__arm_rsrf(sysreg)
#define	__arm_rsrf64(sysreg)
#define	__arm_wsr(sysreg, v)
#define	__arm_wsr64(sysreg, v)
#define	__arm_wsr128(sysreg, v)
#define	__arm_wsrp(sysreg, v)
#define	__arm_wsrf(sysreg, v)
#define	__arm_wsrf64(sysreg, v)

Functions
void	__dmb (unsigned int)
void	__dsb (unsigned int)
void	__isb (unsigned int)
void	__wfi (void)
void	__wfe (void)
void	__sev (void)
void	__sevl (void)
void	__yield (void)
static __inline__ uint32_t	__attribute__ ((__always_inline__, __nodebug__)) __swp(uint32_t __x
	__asm__ ("swp %0, %1, [%2]" :"=r"(__v) :"r"(__x), "r"(__p) :"memory")
	if (__y==0) return __x
	return (__x > > __y)|(__x<<(32 - __y))
static __inline__ uint32_t	__attribute__ ((__always_inline__, __nodebug__, target("crc"))) __crc32b(uint32_t __a

Variables
static __inline__ uint32_t volatile uint32_t *	__p
return	__v = __builtin_bswap32((unsigned int)__D)
static __inline__ uint32_t uint32_t	__y
static __inline__ uint32_t uint8_t	__b

Macro Definition Documentation

__arm_rsr

#define __arm_rsr

(

sysreg

)

Value:

__builtin_arm_rsr(sysreg)

Definition at line 738 of file arm_acle.h.

__arm_rsr128

#define __arm_rsr128

(

sysreg

)

Value:

__builtin_arm_rsr128(sysreg)

Definition at line 740 of file arm_acle.h.

__arm_rsr64

#define __arm_rsr64

(

sysreg

)

Value:

__builtin_arm_rsr64(sysreg)

Definition at line 739 of file arm_acle.h.

__arm_rsrf

#define __arm_rsrf

(

sysreg

)

Value:

__builtin_bit_cast(float, __arm_rsr(sysreg))

Definition at line 742 of file arm_acle.h.

__arm_rsrf64

#define __arm_rsrf64

(

sysreg

)

Value:

__builtin_bit_cast(double, __arm_rsr64(sysreg))

Definition at line 743 of file arm_acle.h.

__arm_rsrp

#define __arm_rsrp

(

sysreg

)

Value:

__builtin_arm_rsrp(sysreg)

Definition at line 741 of file arm_acle.h.

__arm_wsr

#define __arm_wsr	(		sysreg,
			v )

Value:

__builtin_arm_wsr(sysreg, v)

Definition at line 744 of file arm_acle.h.

__arm_wsr128

#define __arm_wsr128	(		sysreg,
			v )

Value:

__builtin_arm_wsr128(sysreg, v)

Definition at line 746 of file arm_acle.h.

__arm_wsr64

#define __arm_wsr64	(		sysreg,
			v )

Value:

__builtin_arm_wsr64(sysreg, v)

Definition at line 745 of file arm_acle.h.

__arm_wsrf

#define __arm_wsrf	(		sysreg,
			v )

Value:

__arm_wsr(sysreg, __builtin_bit_cast(uint32_t, v))

Definition at line 748 of file arm_acle.h.

__arm_wsrf64

#define __arm_wsrf64	(		sysreg,
			v )

Value:

__arm_wsr64(sysreg, __builtin_bit_cast(uint64_t, v))

Definition at line 749 of file arm_acle.h.

__arm_wsrp

#define __arm_wsrp	(		sysreg,
			v )

Value:

__builtin_arm_wsrp(sysreg, v)

Definition at line 747 of file arm_acle.h.

__pld

#define __pld

(

addr

)

Value:

__pldx(0, 0, 0, addr)

Definition at line 93 of file arm_acle.h.

__pldx

#define __pldx	(		access_kind,
			cache_level,
			retention_policy,
			addr )

Value:

  __builtin_arm_prefetch(addr, access_kind, cache_level, retention_policy, 1)

Definition at line 99 of file arm_acle.h.

__pli

#define __pli

(

addr

)

Value:

__plix(0, 0, addr)

Definition at line 104 of file arm_acle.h.

__plix

#define __plix	(		cache_level,
			retention_policy,
			addr )

Value:

  __builtin_arm_prefetch(addr, 0, cache_level, retention_policy, 0)

Definition at line 110 of file arm_acle.h.

Function Documentation

__asm__()

__asm__	(	"swp %	0,
		%	1 )

References __p, and __v.

Referenced by __attribute__(), __attribute__(), __trap(), __vabs2(), __vabs4(), __vabsdiffs2(), __vabsdiffs4(), __vabsdiffu2(), __vabsdiffu4(), __vabsss2(), __vabsss4(), __vadd2(), __vadd4(), __vaddss2(), __vaddss4(), __vaddus2(), __vaddus4(), __vavgs2(), __vavgs4(), __vavgu2(), __vavgu4(), __vmaxs2(), __vmaxs4(), __vmaxu2(), __vmaxu4(), __vmins2(), __vmins4(), __vminu2(), __vminu4(), __vsads2(), __vsads4(), __vsadu2(), __vsadu4(), __vseteq2(), __vseteq4(), __vsetges2(), __vsetges4(), __vsetgeu2(), __vsetgeu4(), __vsetgts2(), __vsetgts4(), __vsetgtu2(), __vsetgtu4(), __vsetles2(), __vsetles4(), __vsetleu2(), __vsetleu4(), __vsetlts2(), __vsetlts4(), __vsetltu2(), __vsetltu4(), __vsetne2(), __vsetne4(), __vsub2(), __vsub4(), __vsubss2(), __vsubss4(), __vsubus2(), and __vsubus4().

__attribute__() [1/2]

__inline__ uint32_t __attribute__ ( (__always_inline__, __nodebug__) )

static

Definition at line 116 of file arm_acle.h.

__attribute__() [2/2]

__inline__ uint32_t __attribute__ ( (__always_inline__, __nodebug__, target("crc")) )

static

__dmb()

void __dmb

(

unsigned int

)

__dsb()

void __dsb

(

unsigned int

)

__isb()

void __isb

(

unsigned int

)

__sev()

void __sev

(

void

)

__sevl()

void __sevl

(

void

)

__wfe()

void __wfe

(

void

)

__wfi()

void __wfi

(

void

)

__yield()

void __yield

(

void

)

if()

if

(

__y

= =0

)

References __y.

return()

return	(	__x	,
		__y	)

References __y.

Variable Documentation

__b

__inline__ uint32_t uint64_t __b

Initial value:

{
  return __builtin_arm_crc32b(__a, __b)

Definition at line 620 of file arm_acle.h.

__p

__inline__ uint32_t volatile uint32_t* __p

Initial value:

{
  uint32_t __v

Definition at line 57 of file arm_acle.h.

Referenced by __asm__(), __attribute__(), __attribute__(), __dAtomicAdd(), __dAtomicAdd_block(), __dAtomicAdd_system(), __fAtomicAdd(), __fAtomicAdd_block(), __fAtomicAdd_system(), __fAtomicExch(), __fAtomicExch_block(), __fAtomicExch_system(), __iAtomicAdd(), __iAtomicAdd_block(), __iAtomicAdd_system(), __iAtomicAnd(), __iAtomicAnd_block(), __iAtomicAnd_system(), __iAtomicCAS(), __iAtomicCAS_block(), __iAtomicCAS_system(), __iAtomicExch(), __iAtomicExch_block(), __iAtomicExch_system(), __iAtomicMax(), __iAtomicMax_block(), __iAtomicMax_system(), __iAtomicMin(), __iAtomicMin_block(), __iAtomicMin_system(), __iAtomicOr(), __iAtomicOr_block(), __iAtomicOr_system(), __iAtomicXor(), __iAtomicXor_block(), __iAtomicXor_system(), __illAtomicMax(), __illAtomicMax_block(), __illAtomicMax_system(), __illAtomicMin(), __illAtomicMin_block(), __illAtomicMin_system(), __llAtomicAnd(), __llAtomicAnd_block(), __llAtomicAnd_system(), __llAtomicOr(), __llAtomicOr_block(), __llAtomicOr_system(), __llAtomicXor(), __llAtomicXor_block(), __llAtomicXor_system(), __uAtomicAdd(), __uAtomicAdd_block(), __uAtomicAdd_system(), __uAtomicAnd(), __uAtomicAnd_block(), __uAtomicAnd_system(), __uAtomicCAS(), __uAtomicCAS_block(), __uAtomicCAS_system(), __uAtomicDec(), __uAtomicDec_block(), __uAtomicDec_system(), __uAtomicExch(), __uAtomicExch_block(), __uAtomicExch_system(), __uAtomicInc(), __uAtomicInc_block(), __uAtomicInc_system(), __uAtomicMax(), __uAtomicMax_block(), __uAtomicMax_system(), __uAtomicMin(), __uAtomicMin_block(), __uAtomicMin_system(), __uAtomicOr(), __uAtomicOr_block(), __uAtomicOr_system(), __uAtomicXor(), __uAtomicXor_block(), __uAtomicXor_system(), __ullAtomicAdd(), __ullAtomicAdd_block(), __ullAtomicAdd_system(), __ullAtomicAnd(), __ullAtomicAnd_block(), __ullAtomicAnd_system(), __ullAtomicCAS(), __ullAtomicCAS_block(), __ullAtomicCAS_system(), __ullAtomicExch(), __ullAtomicExch_block(), __ullAtomicExch_system(), __ullAtomicMax(), __ullAtomicMax_block(), __ullAtomicMax_system(), __ullAtomicMin(), __ullAtomicMin_block(), __ullAtomicMin_system(), __ullAtomicOr(), __ullAtomicOr_block(), __ullAtomicOr_system(), __ullAtomicXor(), __ullAtomicXor_block(), __ullAtomicXor_system(), __usAtomicCAS(), __usAtomicCAS_block(), __usAtomicCAS_system(), _addcarry_u32(), _addcarryx_u32(), _clrssbsy(), _fxrstor(), _fxsave(), _mm256_lddqu_si256(), _mm256_load_pd(), _mm256_load_ps(), _mm256_load_si256(), _mm256_loadu_pd(), _mm256_loadu_ps(), _mm256_loadu_si256(), _mm256_maskload_pd(), _mm256_maskload_ps(), _mm256_maskstore_pd(), _mm256_maskstore_ps(), _mm256_store_pd(), _mm256_store_ps(), _mm256_store_si256(), _mm256_storeu_pd(), _mm256_storeu_ps(), _mm256_storeu_si256(), _mm256_stream_ps(), _mm512_load_pd(), _mm512_load_ps(), _mm512_loadu_pd(), _mm512_loadu_ps(), _mm_clflush(), _mm_clwb(), _mm_lddqu_si128(), _mm_load1_ps(), _mm_load_ps(), _mm_load_si128(), _mm_load_ss(), _mm_loadh_pi(), _mm_loadl_epi64(), _mm_loadl_pi(), _mm_loadr_ps(), _mm_loadu_ps(), _mm_loadu_si128(), _mm_maskload_pd(), _mm_maskload_ps(), _mm_maskmove_si64(), _mm_maskmoveu_si128(), _mm_maskstore_pd(), _mm_maskstore_ps(), _mm_monitor(), _mm_monitorx(), _mm_store1_ps(), _mm_store_ps(), _mm_store_ps1(), _mm_store_si128(), _mm_store_ss(), _mm_storeh_pi(), _mm_storel_epi64(), _mm_storel_pi(), _mm_storer_ps(), _mm_storeu_ps(), _mm_storeu_si128(), _mm_storeu_si16(), _mm_storeu_si32(), _mm_storeu_si64(), _mm_stream_pd(), _mm_stream_pi(), _mm_stream_ps(), _mm_stream_sd(), _mm_stream_si128(), _mm_stream_ss(), _rdseed16_step(), _rdseed32_step(), _rstorssp(), _subborrow_u32(), _wrssd(), _wrussd(), _xrstor(), _xrstors(), _xsave(), _xsavec(), _xsaveopt(), _xsaves(), and operator new().

__v

struct __storeu_i32 *__P __v = __builtin_bswap32((unsigned int)__D)

Definition at line 88 of file arm_acle.h.

Referenced by __asm__(), __attribute__(), __dAtomicAdd(), __dAtomicAdd_block(), __dAtomicAdd_system(), __fAtomicAdd(), __fAtomicAdd_block(), __fAtomicAdd_system(), __fAtomicExch(), __fAtomicExch_block(), __fAtomicExch_system(), __iAtomicAdd(), __iAtomicAdd_block(), __iAtomicAdd_system(), __iAtomicAnd(), __iAtomicAnd_block(), __iAtomicAnd_system(), __iAtomicCAS(), __iAtomicCAS_block(), __iAtomicCAS_system(), __iAtomicExch(), __iAtomicExch_block(), __iAtomicExch_system(), __iAtomicMax(), __iAtomicMax_block(), __iAtomicMax_system(), __iAtomicMin(), __iAtomicMin_block(), __iAtomicMin_system(), __iAtomicOr(), __iAtomicOr_block(), __iAtomicOr_system(), __iAtomicXor(), __iAtomicXor_block(), __iAtomicXor_system(), __illAtomicMax(), __illAtomicMax_block(), __illAtomicMax_system(), __illAtomicMin(), __illAtomicMin_block(), __illAtomicMin_system(), __llAtomicAnd(), __llAtomicAnd_block(), __llAtomicAnd_system(), __llAtomicOr(), __llAtomicOr_block(), __llAtomicOr_system(), __llAtomicXor(), __llAtomicXor_block(), __llAtomicXor_system(), __uAtomicAdd(), __uAtomicAdd_block(), __uAtomicAdd_system(), __uAtomicAnd(), __uAtomicAnd_block(), __uAtomicAnd_system(), __uAtomicCAS(), __uAtomicCAS_block(), __uAtomicCAS_system(), __uAtomicDec(), __uAtomicDec_block(), __uAtomicDec_system(), __uAtomicExch(), __uAtomicExch_block(), __uAtomicExch_system(), __uAtomicInc(), __uAtomicInc_block(), __uAtomicInc_system(), __uAtomicMax(), __uAtomicMax_block(), __uAtomicMax_system(), __uAtomicMin(), __uAtomicMin_block(), __uAtomicMin_system(), __uAtomicOr(), __uAtomicOr_block(), __uAtomicOr_system(), __uAtomicXor(), __uAtomicXor_block(), __uAtomicXor_system(), __ullAtomicAdd(), __ullAtomicAdd_block(), __ullAtomicAdd_system(), __ullAtomicAnd(), __ullAtomicAnd_block(), __ullAtomicAnd_system(), __ullAtomicCAS(), __ullAtomicCAS_block(), __ullAtomicCAS_system(), __ullAtomicExch(), __ullAtomicExch_block(), __ullAtomicExch_system(), __ullAtomicMax(), __ullAtomicMax_block(), __ullAtomicMax_system(), __ullAtomicMin(), __ullAtomicMin_block(), __ullAtomicMin_system(), __ullAtomicOr(), __ullAtomicOr_block(), __ullAtomicOr_system(), __ullAtomicXor(), __ullAtomicXor_block(), __ullAtomicXor_system(), __usAtomicCAS(), __usAtomicCAS_block(), __usAtomicCAS_system(), _mm256_loadu_epi16(), _mm256_loadu_epi32(), _mm256_loadu_epi64(), _mm256_loadu_epi8(), _mm256_loadu_pd(), _mm256_loadu_ps(), _mm256_loadu_si256(), _mm256_storeu_epi16(), _mm256_storeu_epi32(), _mm256_storeu_epi64(), _mm256_storeu_epi8(), _mm256_storeu_pd(), _mm256_storeu_ps(), _mm256_storeu_si256(), _mm512_loadu_epi16(), _mm512_loadu_epi32(), _mm512_loadu_epi64(), _mm512_loadu_epi8(), _mm512_loadu_pd(), _mm512_loadu_ps(), _mm512_loadu_si512(), _mm512_storeu_epi16(), _mm512_storeu_epi32(), _mm512_storeu_epi64(), _mm512_storeu_epi8(), _mm512_storeu_pd(), _mm512_storeu_ps(), _mm512_storeu_si512(), _mm_cvtph_ps(), _mm_loadu_epi16(), _mm_loadu_epi32(), _mm_loadu_epi64(), _mm_loadu_epi8(), _mm_loadu_pd(), _mm_loadu_ps(), _mm_loadu_si128(), _mm_loadu_si16(), _mm_loadu_si32(), _mm_loadu_si64(), _mm_storeu_epi16(), _mm_storeu_epi32(), _mm_storeu_epi64(), _mm_storeu_epi8(), _mm_storeu_pd(), _mm_storeu_ps(), _mm_storeu_si128(), _mm_storeu_si16(), _mm_storeu_si32(), _mm_storeu_si64(), wasm_f32x4_replace_lane(), wasm_f64x2_replace_lane(), wasm_i16x8_load8x8(), wasm_i16x8_replace_lane(), wasm_i32x4_load16x4(), wasm_i32x4_replace_lane(), wasm_i64x2_load32x2(), wasm_i64x2_replace_lane(), wasm_i8x16_replace_lane(), wasm_u16x8_load8x8(), wasm_u16x8_replace_lane(), wasm_u32x4_load16x4(), wasm_u32x4_replace_lane(), wasm_u64x2_load32x2(), wasm_u64x2_replace_lane(), wasm_u8x16_replace_lane(), wasm_v128_load(), wasm_v128_load16_lane(), wasm_v128_load16_splat(), wasm_v128_load32_lane(), wasm_v128_load32_splat(), wasm_v128_load32_zero(), wasm_v128_load64_lane(), wasm_v128_load64_splat(), wasm_v128_load64_zero(), wasm_v128_load8_lane(), wasm_v128_load8_splat(), wasm_v128_store(), wasm_v128_store16_lane(), wasm_v128_store32_lane(), wasm_v128_store64_lane(), and wasm_v128_store8_lane().

__y

__inline__ unsigned long uint32_t __y

Initial value:

{
  __y %= 32

Definition at line 125 of file arm_acle.h.

Referenced by __dadd_rn(), __ddiv_rn(), __dmul_rn(), __dsub_rn(), __fadd_rn(), __fdiv_rn(), __fdividef(), __fma_rn(), __fmaf_rn(), __fmul_rn(), __fsub_rn(), __powf(), __tg_atan2(), __tg_atan2(), __tg_atan2(), __tg_copysign(), __tg_copysign(), __tg_copysign(), __tg_fdim(), __tg_fdim(), __tg_fdim(), __tg_fma(), __tg_fma(), __tg_fma(), __tg_fmax(), __tg_fmax(), __tg_fmax(), __tg_fmin(), __tg_fmin(), __tg_fmin(), __tg_fmod(), __tg_fmod(), __tg_fmod(), __tg_frexp(), __tg_frexp(), __tg_frexp(), __tg_hypot(), __tg_hypot(), __tg_hypot(), __tg_ldexp(), __tg_ldexp(), __tg_ldexp(), __tg_nextafter(), __tg_nextafter(), __tg_nextafter(), __tg_nexttoward(), __tg_nexttoward(), __tg_nexttoward(), __tg_pow(), __tg_pow(), __tg_pow(), __tg_pow(), __tg_pow(), __tg_pow(), __tg_remainder(), __tg_remainder(), __tg_remainder(), __tg_remquo(), __tg_remquo(), __tg_remquo(), __tg_scalbln(), __tg_scalbln(), __tg_scalbln(), __tg_scalbn(), __tg_scalbn(), __tg_scalbn(), _addcarry_u32(), _addcarryx_u32(), _mm_extract_si64(), _mm_insert_si64(), _mm_set_ps(), _mm_setr_ps(), _subborrow_u32(), atan2(), atan2(), atan2f(), copysign(), copysignf(), fdim(), fdimf(), fdividef(), fma(), fma(), fmaf(), fmax(), fmaxf(), fmin(), fminf(), fmod(), fmod(), fmodf(), hypot(), hypotf(), if(), isgreater(), isgreater(), isgreaterequal(), isgreaterequal(), isless(), isless(), islessequal(), islessequal(), islessgreater(), islessgreater(), isunordered(), isunordered(), nextafter(), nextafterf(), norm3d(), norm3df(), norm4d(), norm4df(), std::polar(), pow(), std::pow(), powf(), powi(), powif(), remainder(), remainderf(), remquo(), remquo(), remquof(), return(), rhypot(), rhypotf(), rnorm3d(), rnorm3df(), rnorm4d(), and rnorm4df().