Lines Matching refs:w
51 uint8x16_t aegis_aes_round(uint8x16_t w) in aegis_aes_round() argument
68 w = vqtbl1q_u8(w, vld1q_u8(shift_rows)); in aegis_aes_round()
72 v = vqtbl4q_u8(vld1q_u8_x4(crypto_aes_sbox), w); in aegis_aes_round()
73 v = vqtbx4q_u8(v, vld1q_u8_x4(crypto_aes_sbox + 0x40), w - 0x40); in aegis_aes_round()
74 v = vqtbx4q_u8(v, vld1q_u8_x4(crypto_aes_sbox + 0x80), w - 0x80); in aegis_aes_round()
75 v = vqtbx4q_u8(v, vld1q_u8_x4(crypto_aes_sbox + 0xc0), w - 0xc0); in aegis_aes_round()
77 asm("tbl %0.16b, {v16.16b-v19.16b}, %1.16b" : "=w"(v) : "w"(w)); in aegis_aes_round()
78 w -= 0x40; in aegis_aes_round()
79 asm("tbx %0.16b, {v20.16b-v23.16b}, %1.16b" : "+w"(v) : "w"(w)); in aegis_aes_round()
80 w -= 0x40; in aegis_aes_round()
81 asm("tbx %0.16b, {v24.16b-v27.16b}, %1.16b" : "+w"(v) : "w"(w)); in aegis_aes_round()
82 w -= 0x40; in aegis_aes_round()
83 asm("tbx %0.16b, {v28.16b-v31.16b}, %1.16b" : "+w"(v) : "w"(w)); in aegis_aes_round()
87 w = (v << 1) ^ (uint8x16_t)(((int8x16_t)v >> 7) & 0x1b); in aegis_aes_round()
88 w ^= (uint8x16_t)vrev32q_u16((uint16x8_t)v); in aegis_aes_round()
89 w ^= vqtbl1q_u8(v ^ w, vld1q_u8(ror32by8)); in aegis_aes_round()
91 return w; in aegis_aes_round()
101 asm(AES_ROUND : "+w"(w) : "w"(z)); in aegis_aes_round()
102 return w; in aegis_aes_round()