| /crypto/ |
| D | wp512.c | 786 u64 state[8]; /* the cipher state */ in wp512_process_buffer() local
793 state[0] = block[0] ^ (K[0] = wctx->hash[0]); in wp512_process_buffer()
794 state[1] = block[1] ^ (K[1] = wctx->hash[1]); in wp512_process_buffer()
795 state[2] = block[2] ^ (K[2] = wctx->hash[2]); in wp512_process_buffer()
796 state[3] = block[3] ^ (K[3] = wctx->hash[3]); in wp512_process_buffer()
797 state[4] = block[4] ^ (K[4] = wctx->hash[4]); in wp512_process_buffer()
798 state[5] = block[5] ^ (K[5] = wctx->hash[5]); in wp512_process_buffer()
799 state[6] = block[6] ^ (K[6] = wctx->hash[6]); in wp512_process_buffer()
800 state[7] = block[7] ^ (K[7] = wctx->hash[7]); in wp512_process_buffer()
886 L[0] = C0[(int)(state[0] >> 56) ] ^ in wp512_process_buffer()
[all …]
|
| D | aegis128-core.c | 61 static void crypto_aegis128_update(struct aegis_state *state) in crypto_aegis128_update() argument
66 tmp = state->blocks[AEGIS128_STATE_BLOCKS - 1]; in crypto_aegis128_update()
68 crypto_aegis_aesenc(&state->blocks[i], &state->blocks[i - 1], in crypto_aegis128_update()
69 &state->blocks[i]); in crypto_aegis128_update()
70 crypto_aegis_aesenc(&state->blocks[0], &tmp, &state->blocks[0]); in crypto_aegis128_update()
73 static void crypto_aegis128_update_a(struct aegis_state *state, in crypto_aegis128_update_a() argument
78 crypto_aegis128_update_simd(state, msg); in crypto_aegis128_update_a()
82 crypto_aegis128_update(state); in crypto_aegis128_update_a()
83 crypto_aegis_block_xor(&state->blocks[0], msg); in crypto_aegis128_update_a()
86 static void crypto_aegis128_update_u(struct aegis_state *state, const void *msg, in crypto_aegis128_update_u() argument
[all …]
|
| D | nhpoly1305.c | 76 static void process_nh_hash_value(struct nhpoly1305_state *state, in process_nh_hash_value() argument
81 poly1305_core_blocks(&state->poly_state, &key->poly_key, state->nh_hash, in process_nh_hash_value()
92 static void nhpoly1305_units(struct nhpoly1305_state *state, in nhpoly1305_units() argument
99 if (state->nh_remaining == 0) { in nhpoly1305_units()
102 nh_fn(key->nh_key, src, bytes, state->nh_hash); in nhpoly1305_units()
103 state->nh_remaining = NH_MESSAGE_BYTES - bytes; in nhpoly1305_units()
110 pos = NH_MESSAGE_BYTES - state->nh_remaining; in nhpoly1305_units()
111 bytes = min(srclen, state->nh_remaining); in nhpoly1305_units()
114 le64_add_cpu(&state->nh_hash[i], in nhpoly1305_units()
116 state->nh_remaining -= bytes; in nhpoly1305_units()
[all …]
|
| D | anubis.c | 578 u32 state[4]; in anubis_crypt() local
586 state[i] = be32_to_cpu(src[i]) ^ roundKey[0][i]; in anubis_crypt()
594 T0[(state[0] >> 24) ] ^ in anubis_crypt()
595 T1[(state[1] >> 24) ] ^ in anubis_crypt()
596 T2[(state[2] >> 24) ] ^ in anubis_crypt()
597 T3[(state[3] >> 24) ] ^ in anubis_crypt()
600 T0[(state[0] >> 16) & 0xff] ^ in anubis_crypt()
601 T1[(state[1] >> 16) & 0xff] ^ in anubis_crypt()
602 T2[(state[2] >> 16) & 0xff] ^ in anubis_crypt()
603 T3[(state[3] >> 16) & 0xff] ^ in anubis_crypt()
[all …]
|
| D | aegis128-neon.c | 11 void crypto_aegis128_init_neon(void *state, const void *key, const void *iv);
12 void crypto_aegis128_update_neon(void *state, const void *msg);
13 void crypto_aegis128_encrypt_chunk_neon(void *state, void *dst, const void *src,
15 void crypto_aegis128_decrypt_chunk_neon(void *state, void *dst, const void *src,
17 int crypto_aegis128_final_neon(void *state, void *tag_xor,
33 void crypto_aegis128_init_simd(struct aegis_state *state, in crypto_aegis128_init_simd() argument
38 crypto_aegis128_init_neon(state, key, iv); in crypto_aegis128_init_simd()
42 void crypto_aegis128_update_simd(struct aegis_state *state, const void *msg) in crypto_aegis128_update_simd() argument
45 crypto_aegis128_update_neon(state, msg); in crypto_aegis128_update_simd()
49 void crypto_aegis128_encrypt_chunk_simd(struct aegis_state *state, u8 *dst, in crypto_aegis128_encrypt_chunk_simd() argument
[all …]
|
| D | khazad.c | 808 u64 state; in khazad_crypt() local
810 state = be64_to_cpu(*src) ^ roundKey[0]; in khazad_crypt()
813 state = T0[(int)(state >> 56) ] ^ in khazad_crypt()
814 T1[(int)(state >> 48) & 0xff] ^ in khazad_crypt()
815 T2[(int)(state >> 40) & 0xff] ^ in khazad_crypt()
816 T3[(int)(state >> 32) & 0xff] ^ in khazad_crypt()
817 T4[(int)(state >> 24) & 0xff] ^ in khazad_crypt()
818 T5[(int)(state >> 16) & 0xff] ^ in khazad_crypt()
819 T6[(int)(state >> 8) & 0xff] ^ in khazad_crypt()
820 T7[(int)(state ) & 0xff] ^ in khazad_crypt()
[all …]
|
| D | aegis128-neon-inner.c | 30 static struct aegis128_state aegis128_load_state_neon(const void *state) in aegis128_load_state_neon() argument
33 vld1q_u8(state), in aegis128_load_state_neon()
34 vld1q_u8(state + 16), in aegis128_load_state_neon()
35 vld1q_u8(state + 32), in aegis128_load_state_neon()
36 vld1q_u8(state + 48), in aegis128_load_state_neon()
37 vld1q_u8(state + 64) in aegis128_load_state_neon()
41 static void aegis128_save_state_neon(struct aegis128_state st, void *state) in aegis128_save_state_neon() argument
43 vst1q_u8(state, st.v[0]); in aegis128_save_state_neon()
44 vst1q_u8(state + 16, st.v[1]); in aegis128_save_state_neon()
45 vst1q_u8(state + 32, st.v[2]); in aegis128_save_state_neon()
[all …]
|
| D | sha512_generic.c | 99 sha512_transform(u64 *state, const u8 *input) in sha512_transform() argument
107 a=state[0]; b=state[1]; c=state[2]; d=state[3]; in sha512_transform()
108 e=state[4]; f=state[5]; g=state[6]; h=state[7]; in sha512_transform()
144 state[0] += a; state[1] += b; state[2] += c; state[3] += d; in sha512_transform()
145 state[4] += e; state[5] += f; state[6] += g; state[7] += h; in sha512_transform()
152 sha512_transform(sst->state, src); in sha512_generic_block_fn()
|
| D | rmd160.c | 22 u32 state[5]; member
49 static void rmd160_transform(u32 *state, const __le32 *in) in rmd160_transform() argument
54 aa = state[0]; in rmd160_transform()
55 bb = state[1]; in rmd160_transform()
56 cc = state[2]; in rmd160_transform()
57 dd = state[3]; in rmd160_transform()
58 ee = state[4]; in rmd160_transform()
61 aaa = state[0]; in rmd160_transform()
62 bbb = state[1]; in rmd160_transform()
63 ccc = state[2]; in rmd160_transform()
[all …]
|
| D | chacha_generic.c | 19 u32 state[16]; in chacha_stream_xor() local
24 chacha_init_generic(state, ctx->key, iv); in chacha_stream_xor()
32 chacha_crypt_generic(state, walk.dst.virt.addr, in chacha_stream_xor()
53 u32 state[16]; in crypto_xchacha_crypt() local
57 chacha_init_generic(state, ctx->key, req->iv); in crypto_xchacha_crypt()
58 hchacha_block_generic(state, subctx.key, ctx->nrounds); in crypto_xchacha_crypt()
|
| D | aegis.h | 32 void crypto_aegis128_update_simd(struct aegis_state *state, const void *msg);
33 void crypto_aegis128_init_simd(struct aegis_state *state,
36 void crypto_aegis128_encrypt_chunk_simd(struct aegis_state *state, u8 *dst,
38 void crypto_aegis128_decrypt_chunk_simd(struct aegis_state *state, u8 *dst,
40 int crypto_aegis128_final_simd(struct aegis_state *state,
|
| D | blake2b_generic.c | 114 void blake2b_compress_generic(struct blake2b_state *state, in blake2b_compress_generic() argument
118 blake2b_increment_counter(state, inc); in blake2b_compress_generic()
119 blake2b_compress_one_generic(state, block); in blake2b_compress_generic()
|
| D | adiantum.c | 231 struct poly1305_state state; in adiantum_hash_header() local
233 poly1305_core_init(&state); in adiantum_hash_header()
236 poly1305_core_blocks(&state, &tctx->header_hash_key, in adiantum_hash_header()
240 poly1305_core_blocks(&state, &tctx->header_hash_key, req->iv, in adiantum_hash_header()
243 poly1305_core_emit(&state, NULL, &rctx->header_hash); in adiantum_hash_header()
|
| D | sha1_generic.c | 36 sha1_transform(sst->state, src, temp); in sha1_generic_block_fn()
|
| D | algif_hash.c | 237 char state[HASH_MAX_STATESIZE]; in hash_accept() local
246 err = more ? crypto_ahash_export(req, state) : 0; in hash_accept()
264 err = crypto_ahash_import(&ctx2->req, state); in hash_accept()
|
| D | af_alg.c | 155 if (sock->state == SS_CONNECTED) in alg_bind()
248 if (sock->state == SS_CONNECTED) in alg_setsockopt()
256 if (sock->state == SS_CONNECTED) in alg_setsockopt()
263 if (sock->state == SS_CONNECTED) in alg_setsockopt()
324 newsock->state = SS_CONNECTED; in af_alg_accept()
|
| D | sm3_generic.c | 130 sm3_compress(w, wt, sst->state); in sm3_transform()
|