167 static inline block gen_offset(uint64_t KtopStr[3], unsigned bot) {  in gen_offset()
168     block hi = _mm_load_si128((__m128i*)(KtopStr + 0));  /* hi = B A */  in gen_offset()
169     block lo = _mm_loadu_si128((__m128i*)(KtopStr + 1)); /* lo = C B */  in gen_offset()
195 block gen_offset(uint64_t KtopStr[3], unsigned bot) {  in gen_offset()
200     rval.u64[0] = (KtopStr[0] << bot) | (KtopStr[1] >> (64 - bot));  in gen_offset()
201     rval.u64[1] = (KtopStr[1] << bot) | (KtopStr[2] >> (64 - bot));  in gen_offset()
206 block gen_offset(uint64_t KtopStr[3], unsigned bot) {  in gen_offset()
208     vector unsigned hi = *(vector unsigned*)(KtopStr + 0);  in gen_offset()
209     vector unsigned lo = *(vector unsigned*)(KtopStr + 2);  in gen_offset()
252 block gen_offset(uint64_t KtopStr[3], unsigned bot) {  in gen_offset()
259     uint64x2_t hi = vld1q_u64(KtopStr + 0); /* hi = A B */  in gen_offset()
260     uint64x2_t lo = vld1q_u64(KtopStr + 1); /* lo = B C */  in gen_offset()
303 block gen_offset(uint64_t KtopStr[3], unsigned bot) {  in gen_offset()
306         rval.l = (KtopStr[0] << bot) | (KtopStr[1] >> (64 - bot));  in gen_offset()
307         rval.r = (KtopStr[1] << bot) | (KtopStr[2] >> (64 - bot));  in gen_offset()
309         rval.l = KtopStr[0];  in gen_offset()
310         rval.r = KtopStr[1];  in gen_offset()
639     uint64_t KtopStr[3]; /* Register correct, each item  */  member
792         AES_encrypt(tmp.u8, (unsigned char*)&ctx->KtopStr, &ctx->encrypt_key);  in gen_offset_from_nonce()
794             ctx->KtopStr[0] = bswap64(ctx->KtopStr[0]);  in gen_offset_from_nonce()
795             ctx->KtopStr[1] = bswap64(ctx->KtopStr[1]);  in gen_offset_from_nonce()
797         ctx->KtopStr[2] = ctx->KtopStr[0] ^ (ctx->KtopStr[0] << 8) ^ (ctx->KtopStr[1] >> 56);  in gen_offset_from_nonce()
799     return gen_offset(ctx->KtopStr, idx);  in gen_offset_from_nonce()