Lines Matching +full:11 +full:w

40 	uint64x2_t W[8];  in SHA512_Transform_arm64_impl()  local
47 W[x] = vld1q_u64((const uint64_t *)(&block[(x) * 16])); \ in SHA512_Transform_arm64_impl()
48 W[x] = vreinterpretq_u64_u8(vrev64q_u8(vreinterpretq_u8_u64(W[x]))) in SHA512_Transform_arm64_impl()
50 /* 1. Prepare the first part of the message schedule W. */ in SHA512_Transform_arm64_impl()
78 * gh = S[(11 - i) % 4] in SHA512_Transform_arm64_impl()
93 #define A64_RNDr(S, W, i, ii) \ in SHA512_Transform_arm64_impl() argument
95 K_tmp = vaddq_u64(W[i], K_tmp); \ in SHA512_Transform_arm64_impl()
97 K_tmp = vaddq_u64(K_tmp, S[(11 - i) % 4]); \ in SHA512_Transform_arm64_impl()
99 vextq_u64(S[(10 - i) % 4], S[(11 - i) % 4], 1), \ in SHA512_Transform_arm64_impl()
101 S[(11 - i) % 4] = vsha512h2q_u64(S_tmp, S[(9 - i) % 4], S[(8 - i) % 4]); \ in SHA512_Transform_arm64_impl()
104 A64_RNDr(S, W, 0, i); in SHA512_Transform_arm64_impl()
105 A64_RNDr(S, W, 1, i); in SHA512_Transform_arm64_impl()
106 A64_RNDr(S, W, 2, i); in SHA512_Transform_arm64_impl()
107 A64_RNDr(S, W, 3, i); in SHA512_Transform_arm64_impl()
108 A64_RNDr(S, W, 4, i); in SHA512_Transform_arm64_impl()
109 A64_RNDr(S, W, 5, i); in SHA512_Transform_arm64_impl()
110 A64_RNDr(S, W, 6, i); in SHA512_Transform_arm64_impl()
111 A64_RNDr(S, W, 7, i); in SHA512_Transform_arm64_impl()
125 W[x] = vsha512su1q_u64( \ in SHA512_Transform_arm64_impl()
126 vsha512su0q_u64(W[x], W[(x + 1) % 8]), \ in SHA512_Transform_arm64_impl()
127 W[(x + 7) % 8], \ in SHA512_Transform_arm64_impl()
128 vextq_u64(W[(x + 4) % 8], W[(x + 5) % 8], 1)) in SHA512_Transform_arm64_impl()