Home
last modified time | relevance | path

Searched refs:authsize (Results 1 – 25 of 37) sorted by relevance

12

/linux/crypto/
H A Dauthencesn.c48 unsigned int authsize) in crypto_authenc_esn_setauthsize() argument
50 if (authsize > 0 && authsize < 4) in crypto_authenc_esn_setauthsize()
90 unsigned int authsize = crypto_aead_authsize(authenc_esn); in crypto_authenc_esn_genicv_tail() local
101 scatterwalk_map_and_copy(hash, dst, assoclen + cryptlen, authsize, 1); in crypto_authenc_esn_genicv_tail()
122 unsigned int authsize = crypto_aead_authsize(authenc_esn); in crypto_authenc_esn_genicv() local
128 if (!authsize) in crypto_authenc_esn_genicv()
201 unsigned int authsize = crypto_aead_authsize(authenc_esn); in crypto_authenc_esn_decrypt_tail() local
208 unsigned int cryptlen = req->cryptlen - authsize; in crypto_authenc_esn_decrypt_tail()
215 if (!authsize) in crypto_authenc_esn_decrypt_tail()
226 if (crypto_memneq(ihash, ohash, authsize)) in crypto_authenc_esn_decrypt_tail()
[all …]
H A Dauthenc.c239 unsigned int authsize = crypto_aead_authsize(authenc); in crypto_authenc_decrypt_tail() local
241 u8 *ihash = ahreq->result + authsize; in crypto_authenc_decrypt_tail()
244 scatterwalk_map_and_copy(ihash, req->src, ahreq->nbytes, authsize, 0); in crypto_authenc_decrypt_tail()
246 if (crypto_memneq(ihash, ahreq->result, authsize)) in crypto_authenc_decrypt_tail()
261 req->cryptlen - authsize, req->iv); in crypto_authenc_decrypt_tail()
281 unsigned int authsize = crypto_aead_authsize(authenc); in crypto_authenc_decrypt() local
293 req->assoclen + req->cryptlen - authsize); in crypto_authenc_decrypt()
H A Daegis128-neon.c55 unsigned int authsize) in crypto_aegis128_final_simd() argument
59 cryptlen, authsize); in crypto_aegis128_final_simd()
H A Daegis128-neon-inner.c320 unsigned int authsize) in crypto_aegis128_final_neon() argument
336 if (authsize > 0) { in crypto_aegis128_final_neon()
338 vld1q_u8(permute + authsize)); in crypto_aegis128_final_neon()
H A Daegis-neon.h15 unsigned int authsize);
H A Dalgif_aead.c378 static int aead_setauthsize(void *private, unsigned int authsize) in aead_setauthsize() argument
380 return crypto_aead_setauthsize(private, authsize); in aead_setauthsize()
/linux/drivers/crypto/cavium/nitrox/
H A Dnitrox_aead.c59 unsigned int authsize) in nitrox_aead_setauthsize() argument
66 flags.w0.mac_len = authsize; in nitrox_aead_setauthsize()
69 aead->authsize = authsize; in nitrox_aead_setauthsize()
75 unsigned int authsize) in nitrox_aes_gcm_setauthsize() argument
77 switch (authsize) { in nitrox_aes_gcm_setauthsize()
90 return nitrox_aead_setauthsize(aead, authsize); in nitrox_aes_gcm_setauthsize()
230 rctx->dstlen = rctx->srclen + aead->authsize; in nitrox_aes_gcm_enc()
261 rctx->cryptlen = areq->cryptlen - aead->authsize; in nitrox_aes_gcm_dec()
264 rctx->dstlen = rctx->srclen - aead->authsize; in nitrox_aes_gcm_dec()
379 unsigned int authsize) in nitrox_rfc4106_setauthsize() argument
[all …]
/linux/arch/arm64/crypto/
H A Dsm4-ce-ccm-glue.c45 static int ccm_setauthsize(struct crypto_aead *tfm, unsigned int authsize) in ccm_setauthsize() argument
47 if ((authsize & 1) || authsize < 4) in ccm_setauthsize()
221 unsigned int authsize = crypto_aead_authsize(aead); in ccm_decrypt() local
228 err = ccm_format_input(mac, req, req->cryptlen - authsize); in ccm_decrypt()
242 req->assoclen + req->cryptlen - authsize, in ccm_decrypt()
243 authsize, 0); in ccm_decrypt()
245 if (crypto_memneq(authtag, mac, authsize)) in ccm_decrypt()
H A Dsm4-ce-gcm-glue.c59 static int gcm_setauthsize(struct crypto_aead *tfm, unsigned int authsize) in gcm_setauthsize() argument
61 switch (authsize) { in gcm_setauthsize()
197 unsigned int authsize = crypto_aead_authsize(aead); in gcm_decrypt() local
210 req->assoclen + req->cryptlen - authsize, in gcm_decrypt()
211 authsize, 0); in gcm_decrypt()
213 if (crypto_memneq(authtag, ghash, authsize)) in gcm_decrypt()
/linux/include/crypto/
H A Daead.h142 int (*setauthsize)(struct crypto_aead *tfm, unsigned int authsize);
156 unsigned int authsize; member
287 return tfm->authsize; in crypto_aead_authsize()
400 int crypto_aead_setauthsize(struct crypto_aead *tfm, unsigned int authsize);
403 unsigned int authsize) in crypto_sync_aead_setauthsize() argument
405 return crypto_aead_setauthsize(&tfm->base, authsize); in crypto_sync_aead_setauthsize()
/linux/drivers/crypto/caam/
H A Dcaamalg_qi.c73 unsigned int authsize; member
100 if (!ctx->cdata.keylen || !ctx->authsize) in aead_set_sh_desc()
150 ivsize, ctx->authsize, is_rfc3686, nonce, in aead_set_sh_desc()
165 ivsize, ctx->authsize, alg->caam.geniv, in aead_set_sh_desc()
183 ivsize, ctx->authsize, is_rfc3686, nonce, in aead_set_sh_desc()
190 static int aead_setauthsize(struct crypto_aead *authenc, unsigned int authsize) in aead_setauthsize() argument
194 ctx->authsize = authsize; in aead_setauthsize()
312 if (!ctx->cdata.keylen || !ctx->authsize) in gcm_set_sh_desc()
328 ctx->authsize, true); in gcm_set_sh_desc()
343 ctx->authsize, true); in gcm_set_sh_desc()
[all …]
H A Dcaamalg.c131 unsigned int authsize; member
169 cnstr_shdsc_aead_null_encap(desc, &ctx->adata, ctx->authsize, in aead_null_set_sh_desc()
188 cnstr_shdsc_aead_null_decap(desc, &ctx->adata, ctx->authsize, in aead_null_set_sh_desc()
213 if (!ctx->authsize) in aead_set_sh_desc()
272 ctx->authsize, is_rfc3686, nonce, ctx1_iv_off, in aead_set_sh_desc()
294 ctx->authsize, alg->caam.geniv, is_rfc3686, in aead_set_sh_desc()
318 ctx->authsize, is_rfc3686, nonce, in aead_set_sh_desc()
328 unsigned int authsize) in aead_setauthsize() argument
332 ctx->authsize = authsize; in aead_setauthsize()
347 if (!ctx->cdata.keylen || !ctx->authsize) in gcm_set_sh_desc()
[all …]
H A Dcaamalg_qi2.c91 unsigned int authsize; member
192 if (!ctx->cdata.keylen || !ctx->authsize) in aead_set_sh_desc()
244 ivsize, ctx->authsize, is_rfc3686, in aead_set_sh_desc()
249 ivsize, ctx->authsize, is_rfc3686, nonce, in aead_set_sh_desc()
270 ivsize, ctx->authsize, alg->caam.geniv, in aead_set_sh_desc()
281 static int aead_setauthsize(struct crypto_aead *authenc, unsigned int authsize) in aead_setauthsize() argument
285 ctx->authsize = authsize; in aead_setauthsize()
371 unsigned int authsize = ctx->authsize; in aead_edesc_alloc() local
385 dst_len = src_len + (encrypt ? authsize : (-authsize)); in aead_edesc_alloc()
430 (encrypt ? authsize : 0); in aead_edesc_alloc()
[all …]
/linux/drivers/crypto/ccree/
H A Dcc_buffer_mgr.c538 static bool cc_is_icv_frag(unsigned int sgl_nents, unsigned int authsize, in cc_is_icv_frag() argument
541 return ((sgl_nents > 1) && (last_entry_data_size < authsize)); in cc_is_icv_frag()
657 unsigned int authsize = areq_ctx->req_authsize; in cc_prepare_aead_data_dlli() local
665 offset = *src_last_bytes - authsize; in cc_prepare_aead_data_dlli()
668 offset = *dst_last_bytes - authsize; in cc_prepare_aead_data_dlli()
683 unsigned int authsize = areq_ctx->req_authsize; in cc_prepare_aead_data_mlli() local
695 cc_is_icv_frag(areq_ctx->src.nents, authsize, in cc_prepare_aead_data_mlli()
722 (*src_last_bytes - authsize); in cc_prepare_aead_data_mlli()
724 (*src_last_bytes - authsize); in cc_prepare_aead_data_mlli()
739 cc_is_icv_frag(areq_ctx->src.nents, authsize, in cc_prepare_aead_data_mlli()
[all …]
/linux/tools/testing/selftests/bpf/progs/
H A Dcrypto_bench.c15 u32 key_len, authsize; variable
28 .authsize = authsize, in crypto_setup()
H A Dcrypto_sanity.c15 u32 authsize, key_len; variable
59 .authsize = authsize, in skb_crypto_setup()
/linux/drivers/crypto/tegra/
H A Dtegra-se-aes.c48 unsigned int authsize; member
62 unsigned int authsize; member
823 offset, rctx->authsize, 1); in tegra_gcm_do_final()
835 scatterwalk_map_and_copy(mac, rctx->src_sg, offset, rctx->authsize, 0); in tegra_gcm_do_verify()
837 if (crypto_memneq(rctx->outbuf.buf, mac, rctx->authsize)) in tegra_gcm_do_verify()
978 t = rctx->authsize; in tegra_ccm_format_nonce()
1066 memcpy(rctx->authdata, result, rctx->authsize); in tegra_ccm_mac_result()
1068 ret = crypto_memneq(rctx->authdata, result, rctx->authsize); in tegra_ccm_mac_result()
1085 rctx->authsize, 1); in tegra_ccm_ctr_result()
1087 memcpy(rctx->authdata, rctx->outbuf.buf, rctx->authsize); in tegra_ccm_ctr_result()
[all …]
/linux/drivers/crypto/marvell/octeontx/
H A Dotx_cptvf_algs.c632 unsigned int authsize) in otx_cpt_aead_set_authsize() argument
638 if (authsize != SHA1_DIGEST_SIZE && in otx_cpt_aead_set_authsize()
639 authsize != SHA1_TRUNC_DIGEST_SIZE) in otx_cpt_aead_set_authsize()
642 if (authsize == SHA1_TRUNC_DIGEST_SIZE) in otx_cpt_aead_set_authsize()
647 if (authsize != SHA256_DIGEST_SIZE && in otx_cpt_aead_set_authsize()
648 authsize != SHA256_TRUNC_DIGEST_SIZE) in otx_cpt_aead_set_authsize()
651 if (authsize == SHA256_TRUNC_DIGEST_SIZE) in otx_cpt_aead_set_authsize()
656 if (authsize != SHA384_DIGEST_SIZE && in otx_cpt_aead_set_authsize()
657 authsize != SHA384_TRUNC_DIGEST_SIZE) in otx_cpt_aead_set_authsize()
660 if (authsize == SHA384_TRUNC_DIGEST_SIZE) in otx_cpt_aead_set_authsize()
[all …]
/linux/kernel/bpf/
H A Dcrypto.c36 u32 authsize; member
169 if (!!params->authsize ^ !!type->setauthsize) { in bpf_crypto_ctx_create()
192 if (params->authsize) { in bpf_crypto_ctx_create()
193 *err = type->setauthsize(ctx->tfm, params->authsize); in bpf_crypto_ctx_create()
/linux/drivers/net/ethernet/chelsio/inline_crypto/ch_ipsec/
H A Dchcr_ipsec.c146 int authsize = x->aead->alg_icv_len / 8; in ch_ipsec_setauthsize() local
148 sa_entry->authsize = authsize; in ch_ipsec_setauthsize()
150 switch (authsize) { in ch_ipsec_setauthsize()
647 sa_entry->authsize, in ch_ipsec_crypto_wreq()
648 sa_entry->authsize); in ch_ipsec_crypto_wreq()
H A Dchcr_ipsec.h50 unsigned int authsize; member
/linux/include/linux/
H A Dbpf_crypto.h11 int (*setauthsize)(void *tfm, unsigned int authsize);
/linux/drivers/crypto/qce/
H A Daead.h21 unsigned int authsize; member
/linux/drivers/virt/coco/sev-guest/
H A Dsev-guest.c90 resp_len = sizeof(report_resp->data) + mdesc->ctx->authsize; in get_report()
133 resp_len = sizeof(derived_key_resp->data) + mdesc->ctx->authsize; in get_derived_key()
233 resp_len = sizeof(report_resp->data) + mdesc->ctx->authsize; in get_ext_report()
/linux/drivers/crypto/ccp/
H A Dccp-ops.c647 unsigned int authsize; in ccp_run_aes_gcm_cmd() local
674 authsize = aes->authsize ? aes->authsize : AES_BLOCK_SIZE; in ccp_run_aes_gcm_cmd()
675 switch (authsize) { in ccp_run_aes_gcm_cmd()
702 ilen = aes->src_len - authsize; in ccp_run_aes_gcm_cmd()
883 ccp_get_dm_area(&wa->final, 0, p_tag, 0, authsize); in ccp_run_aes_gcm_cmd()
886 ret = ccp_init_dm_workarea(&wa->tag, cmd_q, authsize, in ccp_run_aes_gcm_cmd()
890 ret = ccp_set_dm_area(&wa->tag, 0, p_tag, 0, authsize); in ccp_run_aes_gcm_cmd()
897 authsize) ? -EBADMSG : 0; in ccp_run_aes_gcm_cmd()

12