166 static inline block gen_offset(uint64_t KtopStr[3], unsigned bot) {  in gen_offset()
167     block hi = _mm_load_si128((__m128i*)(KtopStr + 0));  /* hi = B A */  in gen_offset()
168     block lo = _mm_loadu_si128((__m128i*)(KtopStr + 1)); /* lo = C B */  in gen_offset()
194 block gen_offset(uint64_t KtopStr[3], unsigned bot) {  in gen_offset()
199     rval.u64[0] = (KtopStr[0] << bot) | (KtopStr[1] >> (64 - bot));  in gen_offset()
200     rval.u64[1] = (KtopStr[1] << bot) | (KtopStr[2] >> (64 - bot));  in gen_offset()
205 block gen_offset(uint64_t KtopStr[3], unsigned bot) {  in gen_offset()
207     vector unsigned hi = *(vector unsigned*)(KtopStr + 0);  in gen_offset()
208     vector unsigned lo = *(vector unsigned*)(KtopStr + 2);  in gen_offset()
251 block gen_offset(uint64_t KtopStr[3], unsigned bot) {  in gen_offset()
258     uint64x2_t hi = vld1q_u64(KtopStr + 0); /* hi = A B */  in gen_offset()
259     uint64x2_t lo = vld1q_u64(KtopStr + 1); /* lo = B C */  in gen_offset()
302 block gen_offset(uint64_t KtopStr[3], unsigned bot) {  in gen_offset()
305         rval.l = (KtopStr[0] << bot) | (KtopStr[1] >> (64 - bot));  in gen_offset()
306         rval.r = (KtopStr[1] << bot) | (KtopStr[2] >> (64 - bot));  in gen_offset()
308         rval.l = KtopStr[0];  in gen_offset()
309         rval.r = KtopStr[1];  in gen_offset()
628     uint64_t KtopStr[3]; /* Register correct, each item  */  member
781         AES_encrypt(tmp.u8, (unsigned char*)&ctx->KtopStr, &ctx->encrypt_key);  in gen_offset_from_nonce()
783             ctx->KtopStr[0] = bswap64(ctx->KtopStr[0]);  in gen_offset_from_nonce()
784             ctx->KtopStr[1] = bswap64(ctx->KtopStr[1]);  in gen_offset_from_nonce()
786         ctx->KtopStr[2] = ctx->KtopStr[0] ^ (ctx->KtopStr[0] << 8) ^ (ctx->KtopStr[1] >> 56);  in gen_offset_from_nonce()
788     return gen_offset(ctx->KtopStr, idx);  in gen_offset_from_nonce()