| /src/sys/crypto/chacha/arch/arm/ |
| chacha_neon.c | 159 uint32x4_t in0, in1, in2, in3;
165 r3 = in3 = vreinterpretq_u32_u8(vld1q_u8(in));
172 vst1q_u8(out + 48, vreinterpretq_u8_u32(vaddq_u32(r3, in3)));
210 uint32x4_t in0, in1, in2, in3;
216 in3 = (uint32x4_t) VQ_N_U32(
227 r3 = in3;
232 r3 = vaddq_u32(r3, in3);
250 in3 = vaddq_u32(in3, blkno_inc);
271 uint32x4_t in0, in1, in2, in3;
156 uint32x4_t in0, in1, in2, in3; local in function:chacha_core_neon
206 uint32x4_t in0, in1, in2, in3; local in function:chacha_stream_neon
266 uint32x4_t in0, in1, in2, in3; local in function:chacha_stream_xor_neon
[all...] |
| /src/sys/crypto/chacha/arch/x86/ |
| chacha_sse2.c | 92 __m128i in0, in1, in2, in3;
98 r3 = in3 = _mm_loadu_si128((const __m128i *)in);
105 _mm_storeu_si128((__m128i *)out + 3, _mm_add_epi32(r3, in3));
314 __m128i in0, in1, in2, in3;
320 in3 = _mm_set_epi32(le32dec(nonce + 8), le32dec(nonce + 4),
327 r3 = in3;
332 r3 = _mm_add_epi32(r3, in3);
350 in3 = _mm_add_epi32(in3, blkno_inc);
473 __m128i in0, in1, in2, in3;
90 __m128i in0, in1, in2, in3; local in function:chacha_core_sse2
307 __m128i in0, in1, in2, in3; local in function:chacha_stream_sse2
463 __m128i in0, in1, in2, in3; local in function:chacha_stream_xor_sse2
[all...] |
