Home
last modified time | relevance | path

Searched refs:AEGIS_BLOCK_SIZE (Results 1 – 3 of 3) sorted by relevance

/linux-6.12.1/crypto/
Daegis128-core.c95 crypto_xor(state->blocks[0].bytes, msg, AEGIS_BLOCK_SIZE); in crypto_aegis128_update_u()
106 crypto_xor(key_iv.bytes, iv, AEGIS_BLOCK_SIZE); in crypto_aegis128_init()
131 while (size >= AEGIS_BLOCK_SIZE) { in crypto_aegis128_ad()
134 size -= AEGIS_BLOCK_SIZE; in crypto_aegis128_ad()
138 while (size >= AEGIS_BLOCK_SIZE) { in crypto_aegis128_ad()
141 size -= AEGIS_BLOCK_SIZE; in crypto_aegis128_ad()
142 src += AEGIS_BLOCK_SIZE; in crypto_aegis128_ad()
159 while (size >= AEGIS_BLOCK_SIZE) { in crypto_aegis128_encrypt_chunk()
175 size -= AEGIS_BLOCK_SIZE; in crypto_aegis128_encrypt_chunk()
176 src += AEGIS_BLOCK_SIZE; in crypto_aegis128_encrypt_chunk()
[all …]
Daegis128-neon-inner.c16 #define AEGIS_BLOCK_SIZE 16 macro
226 const int short_input = size < AEGIS_BLOCK_SIZE; in crypto_aegis128_encrypt_chunk_neon()
231 while (size >= AEGIS_BLOCK_SIZE) { in crypto_aegis128_encrypt_chunk_neon()
239 size -= AEGIS_BLOCK_SIZE; in crypto_aegis128_encrypt_chunk_neon()
240 src += AEGIS_BLOCK_SIZE; in crypto_aegis128_encrypt_chunk_neon()
241 dst += AEGIS_BLOCK_SIZE; in crypto_aegis128_encrypt_chunk_neon()
246 uint8_t buf[AEGIS_BLOCK_SIZE]; in crypto_aegis128_encrypt_chunk_neon()
252 in = out = memcpy(buf + AEGIS_BLOCK_SIZE - size, src, size); in crypto_aegis128_encrypt_chunk_neon()
254 m = vqtbl1q_u8(vld1q_u8(in + size - AEGIS_BLOCK_SIZE), in crypto_aegis128_encrypt_chunk_neon()
259 vst1q_u8(out + size - AEGIS_BLOCK_SIZE, in crypto_aegis128_encrypt_chunk_neon()
[all …]
Daegis.h16 #define AEGIS_BLOCK_SIZE 16 macro
19 __le64 words64[AEGIS_BLOCK_SIZE / sizeof(__le64)];
20 __le32 words32[AEGIS_BLOCK_SIZE / sizeof(__le32)];
21 u8 bytes[AEGIS_BLOCK_SIZE];