Home
last modified time | relevance | path

Searched refs:AEGIS_BLOCK_SIZE (Results 1 - 6 of 6) sorted by relevance

/kernel/linux/linux-5.10/crypto/
H A Daegis128-core.c106 crypto_xor(state->blocks[0].bytes, msg, AEGIS_BLOCK_SIZE); in crypto_aegis128_update_u()
117 crypto_xor(key_iv.bytes, iv, AEGIS_BLOCK_SIZE); in crypto_aegis128_init()
141 while (size >= AEGIS_BLOCK_SIZE) { in crypto_aegis128_ad()
144 size -= AEGIS_BLOCK_SIZE; in crypto_aegis128_ad()
148 while (size >= AEGIS_BLOCK_SIZE) { in crypto_aegis128_ad()
151 size -= AEGIS_BLOCK_SIZE; in crypto_aegis128_ad()
152 src += AEGIS_BLOCK_SIZE; in crypto_aegis128_ad()
163 while (size >= AEGIS_BLOCK_SIZE) { in crypto_aegis128_encrypt_chunk()
179 size -= AEGIS_BLOCK_SIZE; in crypto_aegis128_encrypt_chunk()
180 src += AEGIS_BLOCK_SIZE; in crypto_aegis128_encrypt_chunk()
[all...]
H A Daegis128-neon-inner.c16 #define AEGIS_BLOCK_SIZE 16 macro
184 while (size >= AEGIS_BLOCK_SIZE) { in crypto_aegis128_encrypt_chunk_neon()
191 size -= AEGIS_BLOCK_SIZE; in crypto_aegis128_encrypt_chunk_neon()
192 src += AEGIS_BLOCK_SIZE; in crypto_aegis128_encrypt_chunk_neon()
193 dst += AEGIS_BLOCK_SIZE; in crypto_aegis128_encrypt_chunk_neon()
198 uint8_t buf[AEGIS_BLOCK_SIZE] = {}; in crypto_aegis128_encrypt_chunk_neon()
218 while (size >= AEGIS_BLOCK_SIZE) { in crypto_aegis128_decrypt_chunk_neon()
223 size -= AEGIS_BLOCK_SIZE; in crypto_aegis128_decrypt_chunk_neon()
224 src += AEGIS_BLOCK_SIZE; in crypto_aegis128_decrypt_chunk_neon()
225 dst += AEGIS_BLOCK_SIZE; in crypto_aegis128_decrypt_chunk_neon()
[all...]
H A 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];
/kernel/linux/linux-6.6/crypto/
H A 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...]
H A 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...]
H A 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];

Completed in 3 milliseconds