Home
last modified time | relevance | path

Searched refs:state (Results 1 – 21 of 21) sorted by relevance

/crypto/
A Dwp512.c963 state[0] = L[0]; in wp512_process_buffer()
964 state[1] = L[1]; in wp512_process_buffer()
965 state[2] = L[2]; in wp512_process_buffer()
966 state[3] = L[3]; in wp512_process_buffer()
967 state[4] = L[4]; in wp512_process_buffer()
968 state[5] = L[5]; in wp512_process_buffer()
969 state[6] = L[6]; in wp512_process_buffer()
970 state[7] = L[7]; in wp512_process_buffer()
975 wctx->hash[0] ^= state[0] ^ block[0]; in wp512_process_buffer()
976 wctx->hash[1] ^= state[1] ^ block[1]; in wp512_process_buffer()
[all …]
A Daegis128-core.c68 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()
108 state->blocks[0] = key_iv; in crypto_aegis128_init()
111 state->blocks[3] = *key; in crypto_aegis128_init()
112 state->blocks[4] = *key; in crypto_aegis128_init()
165 tmp = state->blocks[2]; in crypto_aegis128_encrypt_chunk()
181 tmp = state->blocks[2]; in crypto_aegis128_encrypt_chunk()
201 tmp = state->blocks[2]; in crypto_aegis128_encrypt_chunk()
226 tmp = state->blocks[2]; in crypto_aegis128_decrypt_chunk()
[all …]
A Dnhpoly1305.c81 poly1305_core_blocks(&state->poly_state, &key->poly_key, state->nh_hash, in process_nh_hash_value()
149 state->buflen = 0; in crypto_nhpoly1305_init()
150 state->nh_remaining = 0; in crypto_nhpoly1305_init()
163 if (state->buflen) { in crypto_nhpoly1305_update_helper()
165 memcpy(&state->buffer[state->buflen], src, bytes); in crypto_nhpoly1305_update_helper()
166 state->buflen += bytes; in crypto_nhpoly1305_update_helper()
169 nhpoly1305_units(state, key, state->buffer, NH_MESSAGE_UNIT, in crypto_nhpoly1305_update_helper()
171 state->buflen = 0; in crypto_nhpoly1305_update_helper()
203 if (state->buflen) { in crypto_nhpoly1305_final_helper()
204 memset(&state->buffer[state->buflen], 0, in crypto_nhpoly1305_final_helper()
[all …]
A Danubis.c575 u32 state[4]; in anubis_crypt() local
591 T0[(state[0] >> 24) ] ^ in anubis_crypt()
592 T1[(state[1] >> 24) ] ^ in anubis_crypt()
593 T2[(state[2] >> 24) ] ^ in anubis_crypt()
594 T3[(state[3] >> 24) ] ^ in anubis_crypt()
597 T0[(state[0] >> 16) & 0xff] ^ in anubis_crypt()
598 T1[(state[1] >> 16) & 0xff] ^ in anubis_crypt()
614 state[0] = inter[0]; in anubis_crypt()
615 state[1] = inter[1]; in anubis_crypt()
616 state[2] = inter[2]; in anubis_crypt()
[all …]
A Dkhazad.c804 u64 state; in khazad_crypt() local
809 state = T0[(int)(state >> 56) ] ^ in khazad_crypt()
810 T1[(int)(state >> 48) & 0xff] ^ in khazad_crypt()
811 T2[(int)(state >> 40) & 0xff] ^ in khazad_crypt()
812 T3[(int)(state >> 32) & 0xff] ^ in khazad_crypt()
813 T4[(int)(state >> 24) & 0xff] ^ in khazad_crypt()
814 T5[(int)(state >> 16) & 0xff] ^ in khazad_crypt()
815 T6[(int)(state >> 8) & 0xff] ^ in khazad_crypt()
816 T7[(int)(state ) & 0xff] ^ in khazad_crypt()
820 state = (T0[(int)(state >> 56) ] & 0xff00000000000000ULL) ^ in khazad_crypt()
[all …]
A Daegis128-neon.c23 void crypto_aegis128_init_simd(struct aegis_state *state, in crypto_aegis128_init_simd() argument
28 crypto_aegis128_init_neon(state, key, iv); in crypto_aegis128_init_simd()
32 void crypto_aegis128_update_simd(struct aegis_state *state, const void *msg) in crypto_aegis128_update_simd() argument
35 crypto_aegis128_update_neon(state, msg); in crypto_aegis128_update_simd()
39 void crypto_aegis128_encrypt_chunk_simd(struct aegis_state *state, u8 *dst, in crypto_aegis128_encrypt_chunk_simd() argument
43 crypto_aegis128_encrypt_chunk_neon(state, dst, src, size); in crypto_aegis128_encrypt_chunk_simd()
47 void crypto_aegis128_decrypt_chunk_simd(struct aegis_state *state, u8 *dst, in crypto_aegis128_decrypt_chunk_simd() argument
51 crypto_aegis128_decrypt_chunk_neon(state, dst, src, size); in crypto_aegis128_decrypt_chunk_simd()
55 int crypto_aegis128_final_simd(struct aegis_state *state, in crypto_aegis128_final_simd() argument
64 ret = crypto_aegis128_final_neon(state, tag_xor, assoclen, cryptlen, in crypto_aegis128_final_simd()
A Daegis128-neon-inner.c34 vld1q_u8(state), in aegis128_load_state_neon()
35 vld1q_u8(state + 16), in aegis128_load_state_neon()
36 vld1q_u8(state + 32), in aegis128_load_state_neon()
37 vld1q_u8(state + 48), in aegis128_load_state_neon()
38 vld1q_u8(state + 64) in aegis128_load_state_neon()
44 vst1q_u8(state, st.v[0]); in aegis128_save_state_neon()
45 vst1q_u8(state + 16, st.v[1]); in aegis128_save_state_neon()
46 vst1q_u8(state + 32, st.v[2]); in aegis128_save_state_neon()
47 vst1q_u8(state + 48, st.v[3]); in aegis128_save_state_neon()
48 vst1q_u8(state + 64, st.v[4]); in aegis128_save_state_neon()
[all …]
A Daegis-neon.h6 void crypto_aegis128_init_neon(void *state, const void *key, const void *iv);
7 void crypto_aegis128_update_neon(void *state, const void *msg);
8 void crypto_aegis128_encrypt_chunk_neon(void *state, void *dst, const void *src,
10 void crypto_aegis128_decrypt_chunk_neon(void *state, void *dst, const void *src,
12 int crypto_aegis128_final_neon(void *state, void *tag_xor,
A Dacompress.c169 struct acomp_req_chain *state = &req->chain; in acomp_save_req() local
171 state->compl = req->base.complete; in acomp_save_req()
172 state->data = req->base.data; in acomp_save_req()
174 req->base.data = state; in acomp_save_req()
181 req->base.complete = state->compl; in acomp_restore_req()
182 req->base.data = state->data; in acomp_restore_req()
187 struct acomp_req_chain *state = &req->chain; in acomp_reqchain_virt() local
208 state->src = svirt; in acomp_virt_to_sg()
209 sg_init_one(&state->ssg, svirt, slen); in acomp_virt_to_sg()
217 state->dst = dvirt; in acomp_virt_to_sg()
[all …]
A Drmd160.c19 u32 state[5]; member
50 aa = state[0]; in rmd160_transform()
51 bb = state[1]; in rmd160_transform()
52 cc = state[2]; in rmd160_transform()
53 dd = state[3]; in rmd160_transform()
54 ee = state[4]; in rmd160_transform()
57 aaa = state[0]; in rmd160_transform()
245 state[1] = state[2] + dd + eee; in rmd160_transform()
246 state[2] = state[3] + ee + aaa; in rmd160_transform()
247 state[3] = state[4] + aa + bbb; in rmd160_transform()
[all …]
A Daegis.h32 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,
A Dchacha.c53 struct chacha_state state; in chacha_stream_xor() local
58 chacha_init(&state, ctx->key, iv); in chacha_stream_xor()
67 chacha_crypt(&state, walk.dst.virt.addr, in chacha_stream_xor()
70 chacha_crypt_generic(&state, walk.dst.virt.addr, in chacha_stream_xor()
100 struct chacha_state state; in crypto_xchacha_crypt() local
104 chacha_init(&state, ctx->key, req->iv); in crypto_xchacha_crypt()
106 hchacha_block(&state, subctx.key, ctx->nrounds); in crypto_xchacha_crypt()
108 hchacha_block_generic(&state, subctx.key, ctx->nrounds); in crypto_xchacha_crypt()
A Dalgif_skcipher.c69 ctx->state = sock_kmalloc(sk, statesize, GFP_ATOMIC); in algif_skcipher_export()
70 if (!ctx->state) in algif_skcipher_export()
73 err = crypto_skcipher_export(req, ctx->state); in algif_skcipher_export()
75 sock_kzfree_s(sk, ctx->state, statesize); in algif_skcipher_export()
76 ctx->state = NULL; in algif_skcipher_export()
159 if (ctx->state) { in _skcipher_recvmsg()
161 ctx->state); in _skcipher_recvmsg()
162 sock_kzfree_s(sk, ctx->state, crypto_skcipher_statesize(tfm)); in _skcipher_recvmsg()
163 ctx->state = NULL; in _skcipher_recvmsg()
368 if (ctx->state) in skcipher_sock_destruct()
[all …]
A Dalgif_hash.c237 char *state; in hash_accept() local
242 state = kmalloc(crypto_ahash_statesize(tfm), GFP_KERNEL); in hash_accept()
244 if (!state) in hash_accept()
249 err = more ? crypto_ahash_export(req, state) : 0; in hash_accept()
267 err = crypto_ahash_import(&ctx2->req, state); in hash_accept()
270 kfree_sensitive(state); in hash_accept()
A Dblake2b_generic.c114 static 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()
A Dadiantum.c231 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()
A Dsha1.c24 static_assert(offsetof(struct sha1_ctx, state) == offsetof(struct sha1_state, state));
A Dahash.c341 u8 state[HASH_MAX_STATESIZE]; in ahash_do_req_chain() local
349 err = crypto_ahash_export(req, state); in ahash_do_req_chain()
351 err = err ?: crypto_ahash_import(req, state); in ahash_do_req_chain()
360 crypto_ahash_export(req, state); in ahash_do_req_chain()
363 return err ?: crypto_ahash_import(req, state); in ahash_do_req_chain()
A Daf_alg.c158 if (sock->state == SS_CONNECTED) in alg_bind()
378 if (sock->state == SS_CONNECTED) in alg_setsockopt()
389 if (sock->state == SS_CONNECTED) in alg_setsockopt()
396 if (sock->state == SS_CONNECTED) in alg_setsockopt()
458 newsock->state = SS_CONNECTED; in af_alg_accept()
A Dsha512.c23 static_assert(offsetof(struct __sha512_ctx, state) == 0);
A Dsha256.c24 static_assert(offsetof(struct __sha256_ctx, state) == 0);

Completed in 34 milliseconds