Lines Matching refs:C0
64 #define G1(A0, B0, C0, D0, A1, B1, C1, D1) \ argument
75 C0 = fBlaMka(C0, D0); \
78 B0 = _mm_xor_si128(B0, C0); \
85 #define G2(A0, B0, C0, D0, A1, B1, C1, D1) \ argument
96 C0 = fBlaMka(C0, D0); \
99 B0 = _mm_xor_si128(B0, C0); \
107 #define DIAGONALIZE(A0, B0, C0, D0, A1, B1, C1, D1) \ argument
114 t0 = C0; \
115 C0 = C1; \
124 #define UNDIAGONALIZE(A0, B0, C0, D0, A1, B1, C1, D1) \ argument
131 t0 = C0; \
132 C0 = C1; \
141 #define DIAGONALIZE(A0, B0, C0, D0, A1, B1, C1, D1) \ argument
145 D0 = C0; \
146 C0 = C1; \
154 #define UNDIAGONALIZE(A0, B0, C0, D0, A1, B1, C1, D1) \ argument
157 t0 = C0; \
158 C0 = C1; \
169 #define BLAKE2_ROUND(A0, A1, B0, B1, C0, C1, D0, D1) \ argument
171 G1(A0, B0, C0, D0, A1, B1, C1, D1); \
172 G2(A0, B0, C0, D0, A1, B1, C1, D1); \
174 DIAGONALIZE(A0, B0, C0, D0, A1, B1, C1, D1); \
176 G1(A0, B0, C0, D0, A1, B1, C1, D1); \
177 G2(A0, B0, C0, D0, A1, B1, C1, D1); \
179 UNDIAGONALIZE(A0, B0, C0, D0, A1, B1, C1, D1); \
190 #define G1_AVX2(A0, A1, B0, B1, C0, C1, D0, D1) \ argument
198 ml = _mm256_mul_epu32(C0, D0); \
200 C0 = _mm256_add_epi64(C0, _mm256_add_epi64(D0, ml)); \
202 B0 = _mm256_xor_si256(B0, C0); \
219 #define G2_AVX2(A0, A1, B0, B1, C0, C1, D0, D1) \ argument
227 ml = _mm256_mul_epu32(C0, D0); \
229 C0 = _mm256_add_epi64(C0, _mm256_add_epi64(D0, ml)); \
230 B0 = _mm256_xor_si256(B0, C0); \
246 #define DIAGONALIZE_1(A0, B0, C0, D0, A1, B1, C1, D1) \ argument
249 C0 = _mm256_permute4x64_epi64(C0, _MM_SHUFFLE(1, 0, 3, 2)); \
257 #define DIAGONALIZE_2(A0, A1, B0, B1, C0, C1, D0, D1) \ argument
264 tmp1 = C0; \
265 C0 = C1; \
274 #define UNDIAGONALIZE_1(A0, B0, C0, D0, A1, B1, C1, D1) \ argument
277 C0 = _mm256_permute4x64_epi64(C0, _MM_SHUFFLE(1, 0, 3, 2)); \
285 #define UNDIAGONALIZE_2(A0, A1, B0, B1, C0, C1, D0, D1) \ argument
292 tmp1 = C0; \
293 C0 = C1; \
302 #define BLAKE2_ROUND_1(A0, A1, B0, B1, C0, C1, D0, D1) \ argument
304 G1_AVX2(A0, A1, B0, B1, C0, C1, D0, D1) \
305 G2_AVX2(A0, A1, B0, B1, C0, C1, D0, D1) \
307 DIAGONALIZE_1(A0, B0, C0, D0, A1, B1, C1, D1) \
309 G1_AVX2(A0, A1, B0, B1, C0, C1, D0, D1) \
310 G2_AVX2(A0, A1, B0, B1, C0, C1, D0, D1) \
312 UNDIAGONALIZE_1(A0, B0, C0, D0, A1, B1, C1, D1) \
315 #define BLAKE2_ROUND_2(A0, A1, B0, B1, C0, C1, D0, D1) \ argument
317 G1_AVX2(A0, A1, B0, B1, C0, C1, D0, D1) \
318 G2_AVX2(A0, A1, B0, B1, C0, C1, D0, D1) \
320 DIAGONALIZE_2(A0, A1, B0, B1, C0, C1, D0, D1) \
322 G1_AVX2(A0, A1, B0, B1, C0, C1, D0, D1) \
323 G2_AVX2(A0, A1, B0, B1, C0, C1, D0, D1) \
325 UNDIAGONALIZE_2(A0, A1, B0, B1, C0, C1, D0, D1) \
342 #define G1(A0, B0, C0, D0, A1, B1, C1, D1) \ argument
353 C0 = muladd(C0, D0); \
356 B0 = _mm512_xor_si512(B0, C0); \
363 #define G2(A0, B0, C0, D0, A1, B1, C1, D1) \ argument
374 C0 = muladd(C0, D0); \
377 B0 = _mm512_xor_si512(B0, C0); \
384 #define DIAGONALIZE(A0, B0, C0, D0, A1, B1, C1, D1) \ argument
389 C0 = _mm512_permutex_epi64(C0, _MM_SHUFFLE(1, 0, 3, 2)); \
396 #define UNDIAGONALIZE(A0, B0, C0, D0, A1, B1, C1, D1) \ argument
401 C0 = _mm512_permutex_epi64(C0, _MM_SHUFFLE(1, 0, 3, 2)); \
408 #define BLAKE2_ROUND(A0, B0, C0, D0, A1, B1, C1, D1) \ argument
410 G1(A0, B0, C0, D0, A1, B1, C1, D1); \
411 G2(A0, B0, C0, D0, A1, B1, C1, D1); \
413 DIAGONALIZE(A0, B0, C0, D0, A1, B1, C1, D1); \
415 G1(A0, B0, C0, D0, A1, B1, C1, D1); \
416 G2(A0, B0, C0, D0, A1, B1, C1, D1); \
418 UNDIAGONALIZE(A0, B0, C0, D0, A1, B1, C1, D1); \
444 #define BLAKE2_ROUND_1(A0, C0, B0, D0, A1, C1, B1, D1) \ argument
447 SWAP_HALVES(C0, D0); \
450 BLAKE2_ROUND(A0, B0, C0, D0, A1, B1, C1, D1); \
452 SWAP_HALVES(C0, D0); \
457 #define BLAKE2_ROUND_2(A0, A1, B0, B1, C0, C1, D0, D1) \ argument
461 SWAP_QUARTERS(C0, C1); \
463 BLAKE2_ROUND(A0, B0, C0, D0, A1, B1, C1, D1); \
466 UNSWAP_QUARTERS(C0, C1); \