| /src/sys/crypto/aes/arch/arm/ |
| aes_neon_impl.h | 40 uint8x16_t aes_neon_enc1(const struct aesenc *, uint8x16_t, unsigned);
41 uint8x16_t aes_neon_dec1(const struct aesdec *, uint8x16_t, unsigned);
|
| aes_neon.c | 61 static const uint8x16_t
200 static inline uint8x16_t
208 storeroundkey(void *rkp, uint8x16_t rk)
215 bytes2nybbles(uint8x16_t *restrict lo, uint8x16_t *restrict hi, uint8x16_t x)
226 static uint8x16_t
227 aes_schedule_transform(uint8x16_t x, const uint8x16_t t[static 2])
229 uint8x16_t lo, hi
[all...] |
| aes_neon_subr.c | 47 static inline uint8x16_t
54 storeblock(void *out, uint8x16_t block)
63 uint8x16_t block;
74 uint8x16_t block;
86 uint8x16_t cv;
104 uint8x16_t iv0, cv, b;
142 static inline uint8x16_t
143 aes_neon_xts_update(uint8x16_t t8)
206 uint8x16_t t, b;
223 uint8x16_t t1
[all...] |
| /src/sys/crypto/arch/arm/ |
| arm_neon.h | 45 typedef __Uint8x16_t uint8x16_t; typedef in typeref:typename:__Uint8x16_t
46 typedef struct { uint8x16_t val[2]; } uint8x16x2_t;
54 typedef __simd128_uint8_t uint8x16_t; typedef in typeref:typename:__simd128_uint8_t
60 typedef struct { uint8x16_t val[2]; } uint8x16x2_t;
83 typedef __attribute__((neon_vector_type(16))) uint8_t uint8x16_t; typedef in typeref:typename:uint8_t
93 typedef struct { uint8x16_t val[2]; } uint8x16x2_t;
138 static __inline uint8x16_t
141 return (uint8x16_t) {
181 static __inline uint8x16_t
182 vextq_u8(uint8x16_t __lo, uint8x16_t __hi, uint8_t __i
[all...] |
| /src/sys/crypto/chacha/arch/arm/ |
| chacha_neon.c | 68 static const uint8x16_t rol8_tab = VQ_N_U8(
72 uint8x16_t y8, x8 = vreinterpretq_u8_u32(x);
|
