Home
last modified time | relevance | path

Searched refs:loadu (Results 1 – 5 of 5) sorted by relevance

/freebsd/contrib/llvm-project/llvm/lib/Support/BLAKE3/
H A Dblake3_avx2.c7 INLINE __m256i loadu(const uint8_t src[32]) { in loadu() function
194 out[0] = loadu(&inputs[0][block_offset + 0 * sizeof(__m256i)]); in transpose_msg_vecs()
195 out[1] = loadu(&inputs[1][block_offset + 0 * sizeof(__m256i)]); in transpose_msg_vecs()
196 out[2] = loadu(&inputs[2][block_offset + 0 * sizeof(__m256i)]); in transpose_msg_vecs()
197 out[3] = loadu(&inputs[3][block_offset + 0 * sizeof(__m256i)]); in transpose_msg_vecs()
198 out[4] = loadu(&inputs[4][block_offset + 0 * sizeof(__m256i)]); in transpose_msg_vecs()
199 out[5] = loadu(&inputs[5][block_offset + 0 * sizeof(__m256i)]); in transpose_msg_vecs()
200 out[6] = loadu(&inputs[6][block_offset + 0 * sizeof(__m256i)]); in transpose_msg_vecs()
201 out[7] = loadu(&inputs[7][block_offset + 0 * sizeof(__m256i)]); in transpose_msg_vecs()
202 out[8] = loadu(&inputs[0][block_offset + 1 * sizeof(__m256i)]); in transpose_msg_vecs()
[all …]
H A Dblake3_sse41.c11 INLINE __m128i loadu(const uint8_t src[16]) { in loadu() function
86 rows[0] = loadu((uint8_t *)&cv[0]); in compress_pre()
87 rows[1] = loadu((uint8_t *)&cv[4]); in compress_pre()
92 __m128i m0 = loadu(&block[sizeof(__m128i) * 0]); in compress_pre()
93 __m128i m1 = loadu(&block[sizeof(__m128i) * 1]); in compress_pre()
94 __m128i m2 = loadu(&block[sizeof(__m128i) * 2]); in compress_pre()
95 __m128i m3 = loadu(&block[sizeof(__m128i) * 3]); in compress_pre()
272 storeu(xorv(rows[2], loadu((uint8_t *)&cv[0])), &out[32]); in blake3_compress_xof_sse41()
273 storeu(xorv(rows[3], loadu((uint8_t *)&cv[4])), &out[48]); in blake3_compress_xof_sse41()
415 out[0] = loadu(&inputs[0][block_offset + 0 * sizeof(__m128i)]); in transpose_msg_vecs()
[all …]
H A Dblake3_sse2.c11 INLINE __m128i loadu(const uint8_t src[16]) { in loadu() function
92 rows[0] = loadu((uint8_t *)&cv[0]); in compress_pre()
93 rows[1] = loadu((uint8_t *)&cv[4]); in compress_pre()
98 __m128i m0 = loadu(&block[sizeof(__m128i) * 0]); in compress_pre()
99 __m128i m1 = loadu(&block[sizeof(__m128i) * 1]); in compress_pre()
100 __m128i m2 = loadu(&block[sizeof(__m128i) * 2]); in compress_pre()
101 __m128i m3 = loadu(&block[sizeof(__m128i) * 3]); in compress_pre()
278 storeu(xorv(rows[2], loadu((uint8_t *)&cv[0])), &out[32]); in blake3_compress_xof_sse2()
279 storeu(xorv(rows[3], loadu((uint8_t *)&cv[4])), &out[48]); in blake3_compress_xof_sse2()
421 out[0] = loadu(&inputs[0][block_offset + 0 * sizeof(__m128i)]); in transpose_msg_vecs()
[all …]
/freebsd/contrib/llvm-project/llvm/lib/Target/SystemZ/
H A DSystemZInstrFP.td365 def SQEB : UnaryRXE<"sqeb", 0xED14, loadu<any_fsqrt>, FP32, 4>;
366 def SQDB : UnaryRXE<"sqdb", 0xED15, loadu<any_fsqrt>, FP64, 8>;
574 def LFPC : SideEffectUnaryS<"lfpc", 0xB29D, loadu<int_s390_sfpc>, 4>;
H A DSystemZOperators.td866 class loadu<SDPatternOperator operator, SDPatternOperator load = z_load>