| /netbsd-src/sys/crypto/aes/arch/arm/ |
| H A D | aes_neon.c | 61 static const uint8x16_t
200 static inline uint8x16_t
208 storeroundkey(void *rkp, uint8x16_t rk) in storeroundkey()
215 bytes2nybbles(uint8x16_t *restrict lo, uint8x16_t *restrict hi, uint8x16_t x) in bytes2nybbles()
226 static uint8x16_t
227 aes_schedule_transform(uint8x16_t x, const uint8x16_t t[static 2]) in aes_schedule_transform()
229 uint8x16_t lo, hi; in aes_schedule_transform()
236 subbytes(uint8x16_t *io, uint8x16_t *jo, uint8x16_t x, uint8x16_t inv_, in subbytes()
237 uint8x16_t inva_) in subbytes()
239 uint8x16_t k, i, ak, j; in subbytes()
[all …]
|
| H A D | aes_neon_subr.c | 47 static inline uint8x16_t
54 storeblock(void *out, uint8x16_t block) in storeblock()
63 uint8x16_t block; in aes_neon_enc()
74 uint8x16_t block; in aes_neon_dec()
86 uint8x16_t cv; in aes_neon_cbc_enc()
104 uint8x16_t iv0, cv, b; in aes_neon_cbc_dec()
142 static inline uint8x16_t
143 aes_neon_xts_update(uint8x16_t t8) in aes_neon_xts_update()
206 uint8x16_t t, b; in aes_neon_xts_enc()
223 uint8x16_t t1; in aes_neon_xts_enc()
[all …]
|
| H A D | 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);
|
| /netbsd-src/sys/crypto/arch/arm/ |
| H A D | arm_neon.h | 45 typedef __Uint8x16_t uint8x16_t; typedef
46 typedef struct { uint8x16_t val[2]; } uint8x16x2_t;
54 typedef __simd128_uint8_t uint8x16_t; typedef
60 typedef struct { uint8x16_t val[2]; } uint8x16x2_t;
83 typedef __attribute__((neon_vector_type(16))) uint8_t uint8x16_t; typedef
93 typedef struct { uint8x16_t val[2]; } uint8x16x2_t;
138 static __inline uint8x16_t
141 return (uint8x16_t) { in vdupq_n_u8()
181 static __inline uint8x16_t
182 vextq_u8(uint8x16_t __lo, uint8x16_t __hi, uint8_t __i) in vextq_u8()
[all …]
|
| /netbsd-src/external/gpl3/gcc.old/dist/gcc/config/arm/ |
| H A D | arm_mve_types.h | 38 typedef __simd128_uint8_t uint8x16_t; typedef
57 typedef struct { uint8x16_t val[2]; } uint8x16x2_t;
58 typedef struct { uint8x16_t val[4]; } uint8x16x4_t;
104 __arm_vreinterpretq_s16_u8 (uint8x16_t __a) in __arm_vreinterpretq_s16_u8()
153 __arm_vreinterpretq_s32_u8 (uint8x16_t __a) in __arm_vreinterpretq_s32_u8()
202 __arm_vreinterpretq_s64_u8 (uint8x16_t __a) in __arm_vreinterpretq_s64_u8()
251 __arm_vreinterpretq_s8_u8 (uint8x16_t __a) in __arm_vreinterpretq_s8_u8()
300 __arm_vreinterpretq_u16_u8 (uint8x16_t __a) in __arm_vreinterpretq_u16_u8()
350 __arm_vreinterpretq_u32_u8 (uint8x16_t __a) in __arm_vreinterpretq_u32_u8()
399 __arm_vreinterpretq_u64_u8 (uint8x16_t __a) in __arm_vreinterpretq_u64_u8()
[all …]
|
| H A D | arm_mve.h | 3352 __extension__ extern __inline uint8x16_t
3354 __arm_vrev64q_u8 (uint8x16_t __a) in __arm_vrev64q_u8()
3373 __extension__ extern __inline uint8x16_t
3375 __arm_vmvnq_u8 (uint8x16_t __a) in __arm_vmvnq_u8()
3394 __extension__ extern __inline uint8x16_t
3415 __extension__ extern __inline uint8x16_t
3417 __arm_vclzq_u8 (uint8x16_t __a) in __arm_vclzq_u8()
3438 __arm_vaddvq_u8 (uint8x16_t __a) in __arm_vaddvq_u8()
3457 __extension__ extern __inline uint8x16_t
3459 __arm_vrev32q_u8 (uint8x16_t __a) in __arm_vrev32q_u8()
[all …]
|
| H A D | arm_neon.h | 92 typedef __simd128_uint8_t uint8x16_t; typedef
159 uint8x16_t val[2];
298 uint8x16_t val[3];
437 uint8x16_t val[4];
635 __extension__ extern __inline uint8x16_t
637 vaddq_u8 (uint8x16_t __a, uint8x16_t __b) in vaddq_u8()
810 __extension__ extern __inline uint8x16_t
812 vhaddq_u8 (uint8x16_t __a, uint8x16_t __b) in vhaddq_u8()
814 return (uint8x16_t)__builtin_neon_vhadduv16qi ((int8x16_t) __a, (int8x16_t) __b); in vhaddq_u8()
894 __extension__ extern __inline uint8x16_t
[all …]
|
| H A D | arm_cde.h | 143 (uint8x16_t)__builtin_arm_vcx1qv16qi(coproc, imm)
149 (uint8x16_t)__builtin_arm_vcx2qv16qi(coproc, n, imm)
155 (uint8x16_t)__builtin_arm_vcx3qv16qi(coproc, n, m, imm)
|
| /netbsd-src/external/gpl3/gcc/dist/gcc/config/arm/ |
| H A D | arm_mve_types.h | 76 __arm_vreinterpretq_s16_u8 (uint8x16_t __a) in __arm_vreinterpretq_s16_u8()
125 __arm_vreinterpretq_s32_u8 (uint8x16_t __a) in __arm_vreinterpretq_s32_u8()
174 __arm_vreinterpretq_s64_u8 (uint8x16_t __a) in __arm_vreinterpretq_s64_u8()
223 __arm_vreinterpretq_s8_u8 (uint8x16_t __a) in __arm_vreinterpretq_s8_u8()
272 __arm_vreinterpretq_u16_u8 (uint8x16_t __a) in __arm_vreinterpretq_u16_u8()
322 __arm_vreinterpretq_u32_u8 (uint8x16_t __a) in __arm_vreinterpretq_u32_u8()
371 __arm_vreinterpretq_u64_u8 (uint8x16_t __a) in __arm_vreinterpretq_u64_u8()
376 __extension__ extern __inline uint8x16_t
380 return (uint8x16_t) __a; in __arm_vreinterpretq_u8_s16()
383 __extension__ extern __inline uint8x16_t
[all …]
|
| H A D | arm_mve.h | 3352 __extension__ extern __inline uint8x16_t
3354 __arm_vrev64q_u8 (uint8x16_t __a) in __arm_vrev64q_u8()
3373 __extension__ extern __inline uint8x16_t
3375 __arm_vmvnq_u8 (uint8x16_t __a) in __arm_vmvnq_u8()
3394 __extension__ extern __inline uint8x16_t
3415 __extension__ extern __inline uint8x16_t
3417 __arm_vclzq_u8 (uint8x16_t __a) in __arm_vclzq_u8()
3438 __arm_vaddvq_u8 (uint8x16_t __a) in __arm_vaddvq_u8()
3457 __extension__ extern __inline uint8x16_t
3459 __arm_vrev32q_u8 (uint8x16_t __a) in __arm_vrev32q_u8()
[all …]
|
| H A D | arm_cde.h | 143 (uint8x16_t)__builtin_arm_vcx1qv16qi(coproc, imm)
149 (uint8x16_t)__builtin_arm_vcx2qv16qi(coproc, n, imm)
155 (uint8x16_t)__builtin_arm_vcx3qv16qi(coproc, n, m, imm)
|
| H A D | arm-mve-builtins.def | 26 DEF_MVE_TYPE (uint8x16_t, unsigned_intQI_type_node)
|
| /netbsd-src/external/gpl3/gcc.old/dist/gcc/config/aarch64/ |
| H A D | arm_neon.h | 62 typedef __Uint8x16_t uint8x16_t; typedef
156 uint8x16_t val[2];
316 uint8x16_t val[3];
446 uint8x16_t val[4];
796 __extension__ extern __inline uint8x16_t
798 vaddq_u8 (uint8x16_t __a, uint8x16_t __b) in vaddq_u8()
892 vaddl_high_u8 (uint8x16_t __a, uint8x16_t __b) in vaddl_high_u8()
982 vaddw_high_u8 (uint16x8_t __a, uint8x16_t __b) in vaddw_high_u8()
1070 __extension__ extern __inline uint8x16_t
1072 vhaddq_u8 (uint8x16_t __a, uint8x16_t __b) in vhaddq_u8()
[all …]
|
| /netbsd-src/external/gpl3/gcc.old/dist/libcpp/ |
| H A D | lex.c | 769 const uint8x16_t repl_nl = vdupq_n_u8 ('\n'); in search_line_fast()
770 const uint8x16_t repl_cr = vdupq_n_u8 ('\r'); in search_line_fast()
771 const uint8x16_t repl_bs = vdupq_n_u8 ('\\'); in search_line_fast()
772 const uint8x16_t repl_qm = vdupq_n_u8 ('?'); in search_line_fast()
773 const uint8x16_t xmask = (uint8x16_t) vdupq_n_u64 (0x8040201008040201ULL); in search_line_fast()
783 uint8x16_t data; in search_line_fast()
784 uint8x16_t t; in search_line_fast()
786 uint8x16_t u, v, w; in search_line_fast()
856 const uint8x16_t repl_nl = vdupq_n_u8 ('\n'); in search_line_fast()
857 const uint8x16_t repl_cr = vdupq_n_u8 ('\r'); in search_line_fast()
[all …]
|
| /netbsd-src/external/gpl3/gcc/dist/libcpp/ |
| H A D | lex.cc | 769 const uint8x16_t repl_nl = vdupq_n_u8 ('\n'); in search_line_fast()
770 const uint8x16_t repl_cr = vdupq_n_u8 ('\r'); in search_line_fast()
771 const uint8x16_t repl_bs = vdupq_n_u8 ('\\'); in search_line_fast()
772 const uint8x16_t repl_qm = vdupq_n_u8 ('?'); in search_line_fast()
773 const uint8x16_t xmask = (uint8x16_t) vdupq_n_u64 (0x8040201008040201ULL); in search_line_fast()
783 uint8x16_t data; in search_line_fast()
784 uint8x16_t t; in search_line_fast()
786 uint8x16_t u, v, w; in search_line_fast()
856 const uint8x16_t repl_nl = vdupq_n_u8 ('\n'); in search_line_fast()
857 const uint8x16_t repl_cr = vdupq_n_u8 ('\r'); in search_line_fast()
[all …]
|
| /netbsd-src/sys/crypto/chacha/arch/arm/ |
| H A D | chacha_neon.c | 67 static const uint8x16_t rol8_tab = VQ_N_U8( in rol8()
71 uint8x16_t y8, x8 = vreinterpretq_u8_u32(x); in rol8()
|
| /netbsd-src/external/gpl3/gcc/dist/gcc/ |
| H A D | ChangeLog-2014 | 5656 (uint8x16_t): Likewise.
|