| /crypto/ |
| D | authencesn.c | 50 unsigned int authsize) in crypto_authenc_esn_setauthsize() argument
52 if (authsize > 0 && authsize < 4) in crypto_authenc_esn_setauthsize()
95 unsigned int authsize = crypto_aead_authsize(authenc_esn); in crypto_authenc_esn_genicv_tail() local
106 scatterwalk_map_and_copy(hash, dst, assoclen + cryptlen, authsize, 1); in crypto_authenc_esn_genicv_tail()
129 unsigned int authsize = crypto_aead_authsize(authenc_esn); in crypto_authenc_esn_genicv() local
135 if (!authsize) in crypto_authenc_esn_genicv()
223 unsigned int authsize = crypto_aead_authsize(authenc_esn); in crypto_authenc_esn_decrypt_tail() local
231 unsigned int cryptlen = req->cryptlen - authsize; in crypto_authenc_esn_decrypt_tail()
237 if (!authsize) in crypto_authenc_esn_decrypt_tail()
245 if (crypto_memneq(ihash, ohash, authsize)) in crypto_authenc_esn_decrypt_tail()
[all …]
|
| D | aegis128-core.c | 379 unsigned int authsize) in crypto_aegis128_setauthsize() argument
381 if (authsize > AEGIS128_MAX_AUTH_SIZE) in crypto_aegis128_setauthsize()
383 if (authsize < AEGIS128_MIN_AUTH_SIZE) in crypto_aegis128_setauthsize()
392 unsigned int authsize = crypto_aead_authsize(tfm); in crypto_aegis128_encrypt_generic() local
406 authsize, 1); in crypto_aegis128_encrypt_generic()
415 unsigned int authsize = crypto_aead_authsize(tfm); in crypto_aegis128_decrypt_generic() local
416 unsigned int cryptlen = req->cryptlen - authsize; in crypto_aegis128_decrypt_generic()
422 authsize, 0); in crypto_aegis128_decrypt_generic()
431 if (unlikely(crypto_memneq(tag.bytes, zeros, authsize))) { in crypto_aegis128_decrypt_generic()
453 unsigned int authsize = crypto_aead_authsize(tfm); in crypto_aegis128_encrypt_simd() local
[all …]
|
| D | aead.c | 64 int crypto_aead_setauthsize(struct crypto_aead *tfm, unsigned int authsize) in crypto_aead_setauthsize() argument
68 if ((!authsize && crypto_aead_maxauthsize(tfm)) || in crypto_aead_setauthsize()
69 authsize > crypto_aead_maxauthsize(tfm)) in crypto_aead_setauthsize()
73 err = crypto_aead_alg(tfm)->setauthsize(tfm, authsize); in crypto_aead_setauthsize()
78 tfm->authsize = authsize; in crypto_aead_setauthsize()
134 aead->authsize = alg->maxauthsize; in crypto_aead_init_tfm()
|
| D | aegis128-neon.c | 20 unsigned int authsize);
69 unsigned int authsize) in crypto_aegis128_final_simd() argument
75 authsize); in crypto_aegis128_final_simd()
|
| D | gcm.c | 147 unsigned int authsize) in crypto_gcm_setauthsize() argument
149 return crypto_gcm_check_authsize(authsize); in crypto_gcm_setauthsize()
471 unsigned int authsize = crypto_aead_authsize(aead); in crypto_gcm_verify() local
472 unsigned int cryptlen = req->cryptlen - authsize; in crypto_gcm_verify()
476 req->assoclen + cryptlen, authsize, 0); in crypto_gcm_verify()
477 return crypto_memneq(iauth_tag, auth_tag, authsize) ? -EBADMSG : 0; in crypto_gcm_verify()
506 unsigned int authsize = crypto_aead_authsize(aead); in crypto_gcm_decrypt() local
510 cryptlen -= authsize; in crypto_gcm_decrypt()
710 unsigned int authsize) in crypto_rfc4106_setauthsize() argument
715 err = crypto_rfc4106_check_authsize(authsize); in crypto_rfc4106_setauthsize()
[all …]
|
| D | ccm.c | 109 unsigned int authsize) in crypto_ccm_setauthsize() argument
111 switch (authsize) { in crypto_ccm_setauthsize()
329 unsigned int authsize = crypto_aead_authsize(aead); in crypto_ccm_decrypt_done() local
330 unsigned int cryptlen = req->cryptlen - authsize; in crypto_ccm_decrypt_done()
339 if (!err && crypto_memneq(pctx->auth_tag, pctx->odata, authsize)) in crypto_ccm_decrypt_done()
352 unsigned int authsize = crypto_aead_authsize(aead); in crypto_ccm_decrypt() local
359 cryptlen -= authsize; in crypto_ccm_decrypt()
366 authsize, 0); in crypto_ccm_decrypt()
387 if (crypto_memneq(authtag, odata, authsize)) in crypto_ccm_decrypt()
588 unsigned int authsize) in crypto_rfc4309_setauthsize() argument
[all …]
|
| D | authenc.c | 240 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()
259 req->cryptlen - authsize, req->iv); in crypto_authenc_decrypt_tail()
281 unsigned int authsize = crypto_aead_authsize(authenc); in crypto_authenc_decrypt() local
296 req->assoclen + req->cryptlen - authsize); in crypto_authenc_decrypt()
|
| D | geniv.c | 28 unsigned int authsize) in aead_geniv_setauthsize() argument
32 return crypto_aead_setauthsize(ctx->child, authsize); in aead_geniv_setauthsize()
|
| D | aegis128-neon-inner.c | 319 unsigned int authsize) in crypto_aegis128_final_neon() argument
335 if (authsize > 0) { in crypto_aegis128_final_neon()
337 vld1q_u8(permute + authsize)); in crypto_aegis128_final_neon()
|
| D | aegis.h | 44 unsigned int authsize);
|
| D | tcrypt.c | 242 unsigned int tcount, u8 authsize, in test_mb_aead_speed() argument
281 ret = crypto_aead_setauthsize(tfm, authsize); in test_mb_aead_speed()
336 if (bs + authsize > XBUFSIZE * PAGE_SIZE) { in test_mb_aead_speed()
338 authsize + bs, in test_mb_aead_speed()
379 bs + (enc ? 0 : authsize), in test_mb_aead_speed()
383 bs + (enc ? authsize : 0), in test_mb_aead_speed()
406 (enc ? 0 : authsize), in test_mb_aead_speed()
517 unsigned int tcount, u8 authsize, in test_aead_speed() argument
570 ret = crypto_aead_setauthsize(tfm, authsize); in test_aead_speed()
632 sg_init_aead(sg, xbuf, bs + (enc ? 0 : authsize), in test_aead_speed()
[all …]
|
| D | pcrypt.c | 51 unsigned int authsize) in pcrypt_aead_setauthsize() argument
55 return crypto_aead_setauthsize(ctx->child, authsize); in pcrypt_aead_setauthsize()
|
| D | testmgr.c | 2030 const unsigned int authsize = vec->clen - vec->plen; in test_aead_vec_cfg() local
2063 err = crypto_aead_setauthsize(tfm, authsize); in test_aead_vec_cfg()
2275 const unsigned int authsize = vec->clen - vec->plen; in mutate_aead_message() local
2286 flip_random_bit(rng, (u8 *)vec->ctext + vec->plen, authsize); in mutate_aead_message()
2308 const unsigned int authsize = vec->clen - vec->plen; in generate_aead_message() local
2309 const bool inauthentic = (authsize >= MIN_COLLISION_FREE_AUTHSIZE) && in generate_aead_message()
2379 unsigned int authsize; in generate_random_aead_testvec() local
2393 authsize = maxauthsize; in generate_random_aead_testvec()
2395 authsize = prandom_u32_below(rng, maxauthsize + 1); in generate_random_aead_testvec()
2396 if (prefer_inauthentic && authsize < MIN_COLLISION_FREE_AUTHSIZE) in generate_random_aead_testvec()
[all …]
|
| D | simd.c | 302 static int simd_aead_setauthsize(struct crypto_aead *tfm, unsigned int authsize) in simd_aead_setauthsize() argument
307 return crypto_aead_setauthsize(child, authsize); in simd_aead_setauthsize()
|
| D | algif_aead.c | 505 static int aead_setauthsize(void *private, unsigned int authsize) in aead_setauthsize() argument
509 return crypto_aead_setauthsize(tfm->aead, authsize); in aead_setauthsize()
|
| D | essiv.c | 127 unsigned int authsize) in essiv_aead_setauthsize() argument
131 return crypto_aead_setauthsize(tctx->u.aead, authsize); in essiv_aead_setauthsize()
|
| D | chacha20poly1305.c | 492 unsigned int authsize) in chachapoly_setauthsize() argument
494 if (authsize != POLY1305_DIGEST_SIZE) in chachapoly_setauthsize()
|
| D | cryptd.c | 706 unsigned int authsize) in cryptd_aead_setauthsize() argument
711 return crypto_aead_setauthsize(child, authsize); in cryptd_aead_setauthsize()
|