222 					unsigned int size)  in crypto_aegis128_encrypt_chunk_neon()  argument
225 	const int short_input = size < AEGIS_BLOCK_SIZE;  in crypto_aegis128_encrypt_chunk_neon()
230 	while (size >= AEGIS_BLOCK_SIZE) {  in crypto_aegis128_encrypt_chunk_neon()
238 		size -= AEGIS_BLOCK_SIZE;  in crypto_aegis128_encrypt_chunk_neon()
243 	if (size > 0) {  in crypto_aegis128_encrypt_chunk_neon()
251 			in = out = memcpy(buf + AEGIS_BLOCK_SIZE - size, src, size);  in crypto_aegis128_encrypt_chunk_neon()
253 		m = vqtbl1q_u8(vld1q_u8(in + size - AEGIS_BLOCK_SIZE),  in crypto_aegis128_encrypt_chunk_neon()
254 			       vld1q_u8(permute + 32 - size));  in crypto_aegis128_encrypt_chunk_neon()
258 		vst1q_u8(out + size - AEGIS_BLOCK_SIZE,  in crypto_aegis128_encrypt_chunk_neon()
259 			 vqtbl1q_u8(m ^ s, vld1q_u8(permute + size)));  in crypto_aegis128_encrypt_chunk_neon()
262 			memcpy(dst, out, size);  in crypto_aegis128_encrypt_chunk_neon()
271 					unsigned int size)  in crypto_aegis128_decrypt_chunk_neon()  argument
274 	const int short_input = size < AEGIS_BLOCK_SIZE;  in crypto_aegis128_decrypt_chunk_neon()
279 	while (size >= AEGIS_BLOCK_SIZE) {  in crypto_aegis128_decrypt_chunk_neon()
284 		size -= AEGIS_BLOCK_SIZE;  in crypto_aegis128_decrypt_chunk_neon()
289 	if (size > 0) {  in crypto_aegis128_decrypt_chunk_neon()
297 			in = out = memcpy(buf + AEGIS_BLOCK_SIZE - size, src, size);  in crypto_aegis128_decrypt_chunk_neon()
299 		m = s ^ vqtbx1q_u8(s, vld1q_u8(in + size - AEGIS_BLOCK_SIZE),  in crypto_aegis128_decrypt_chunk_neon()
300 				   vld1q_u8(permute + 32 - size));  in crypto_aegis128_decrypt_chunk_neon()
304 		vst1q_u8(out + size - AEGIS_BLOCK_SIZE,  in crypto_aegis128_decrypt_chunk_neon()
305 			 vqtbl1q_u8(m, vld1q_u8(permute + size)));  in crypto_aegis128_decrypt_chunk_neon()
308 			memcpy(dst, out, size);  in crypto_aegis128_decrypt_chunk_neon()