| /crypto/ |
| A D | authencesn.c | 48 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
122 unsigned int authsize = crypto_aead_authsize(authenc_esn); in crypto_authenc_esn_genicv() local
128 if (!authsize) in crypto_authenc_esn_genicv()
205 unsigned int cryptlen = req->cryptlen - authsize; in crypto_authenc_esn_decrypt_tail()
211 if (!authsize) in crypto_authenc_esn_decrypt_tail()
219 if (crypto_memneq(ihash, ohash, authsize)) in crypto_authenc_esn_decrypt_tail()
259 cryptlen -= authsize; in crypto_authenc_esn_decrypt()
265 authsize, 0); in crypto_authenc_esn_decrypt()
[all …]
|
| A D | aegis128-core.c | 377 unsigned int authsize) in crypto_aegis128_setauthsize() argument
379 if (authsize > AEGIS128_MAX_AUTH_SIZE) in crypto_aegis128_setauthsize()
381 if (authsize < AEGIS128_MIN_AUTH_SIZE) in crypto_aegis128_setauthsize()
390 unsigned int authsize = crypto_aead_authsize(tfm); in crypto_aegis128_encrypt_generic() local
404 authsize, 1); in crypto_aegis128_encrypt_generic()
414 unsigned int cryptlen = req->cryptlen - authsize; in crypto_aegis128_decrypt_generic()
420 authsize, 0); in crypto_aegis128_decrypt_generic()
468 authsize, 1); in crypto_aegis128_encrypt_simd()
477 unsigned int cryptlen = req->cryptlen - authsize; in crypto_aegis128_decrypt_simd()
486 authsize, 0); in crypto_aegis128_decrypt_simd()
[all …]
|
| A D | aead.c | 65 int crypto_aead_setauthsize(struct crypto_aead *tfm, unsigned int authsize) in crypto_aead_setauthsize() argument
69 if ((!authsize && crypto_aead_maxauthsize(tfm)) || in crypto_aead_setauthsize()
70 authsize > crypto_aead_maxauthsize(tfm)) in crypto_aead_setauthsize()
74 err = crypto_aead_alg(tfm)->setauthsize(tfm, authsize); in crypto_aead_setauthsize()
79 tfm->authsize = authsize; in crypto_aead_setauthsize()
124 aead->authsize = alg->maxauthsize; in crypto_aead_init_tfm()
|
| A D | krb5enc.c | 252 unsigned int authsize = crypto_aead_authsize(krb5enc); in krb5enc_verify_hash() local
254 u8 *msg_hash = areq_ctx->tail + authsize; in krb5enc_verify_hash()
256 scatterwalk_map_and_copy(msg_hash, req->src, ahreq->nbytes, authsize, 0); in krb5enc_verify_hash()
258 if (crypto_memneq(msg_hash, calc_hash, authsize)) in krb5enc_verify_hash()
286 unsigned int authsize = crypto_aead_authsize(krb5enc); in krb5enc_dispatch_decrypt_hash() local
292 req->assoclen + req->cryptlen - authsize); in krb5enc_dispatch_decrypt_hash()
315 unsigned int authsize = crypto_aead_authsize(krb5enc); in krb5enc_dispatch_decrypt() local
328 req->cryptlen - authsize, req->iv); in krb5enc_dispatch_decrypt()
|
| A D | gcm.c | 143 unsigned int authsize) in crypto_gcm_setauthsize() argument
145 return crypto_gcm_check_authsize(authsize); in crypto_gcm_setauthsize()
466 unsigned int cryptlen = req->cryptlen - authsize; in crypto_gcm_verify()
470 req->assoclen + cryptlen, authsize, 0); in crypto_gcm_verify()
504 cryptlen -= authsize; in crypto_gcm_decrypt()
702 unsigned int authsize) in crypto_rfc4106_setauthsize() argument
707 err = crypto_rfc4106_check_authsize(authsize); in crypto_rfc4106_setauthsize()
910 unsigned int authsize) in crypto_rfc4543_setauthsize() argument
914 if (authsize != 16) in crypto_rfc4543_setauthsize()
932 (enc ? 0 : authsize); in crypto_rfc4543_crypt()
[all …]
|
| A D | authenc.c | 216 unsigned int authsize = crypto_aead_authsize(authenc); in crypto_authenc_decrypt_tail() local
217 u8 *ihash = ahreq->result + authsize; in crypto_authenc_decrypt_tail()
220 scatterwalk_map_and_copy(ihash, req->src, ahreq->nbytes, authsize, 0); in crypto_authenc_decrypt_tail()
222 if (crypto_memneq(ihash, ahreq->result, authsize)) in crypto_authenc_decrypt_tail()
235 req->cryptlen - authsize, req->iv); in crypto_authenc_decrypt_tail()
256 unsigned int authsize = crypto_aead_authsize(authenc); in crypto_authenc_decrypt() local
268 req->assoclen + req->cryptlen - authsize); in crypto_authenc_decrypt()
|
| A D | aegis128-neon.c | 59 unsigned int authsize) in crypto_aegis128_final_simd() argument
65 authsize); in crypto_aegis128_final_simd()
|
| A D | ccm.c | 106 unsigned int authsize) in crypto_ccm_setauthsize() argument
108 switch (authsize) { in crypto_ccm_setauthsize()
325 unsigned int authsize = crypto_aead_authsize(aead); in crypto_ccm_decrypt_done() local
326 unsigned int cryptlen = req->cryptlen - authsize; in crypto_ccm_decrypt_done()
348 unsigned int authsize = crypto_aead_authsize(aead); in crypto_ccm_decrypt() local
355 cryptlen -= authsize; in crypto_ccm_decrypt()
362 authsize, 0); in crypto_ccm_decrypt()
383 if (crypto_memneq(authtag, odata, authsize)) in crypto_ccm_decrypt()
582 unsigned int authsize) in crypto_rfc4309_setauthsize() argument
586 switch (authsize) { in crypto_rfc4309_setauthsize()
[all …]
|
| A D | geniv.c | 27 unsigned int authsize) in aead_geniv_setauthsize() argument
31 return crypto_aead_setauthsize(ctx->child, authsize); in aead_geniv_setauthsize()
|
| A D | aegis-neon.h | 15 unsigned int authsize);
|
| A D | aegis128-neon-inner.c | 320 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()
|
| A D | aegis.h | 44 unsigned int authsize);
|
| A D | tcrypt.c | 245 unsigned int tcount, u8 authsize, in test_mb_aead_speed() argument
284 ret = crypto_aead_setauthsize(tfm, authsize); in test_mb_aead_speed()
339 if (bs + authsize > XBUFSIZE * PAGE_SIZE) { in test_mb_aead_speed()
341 authsize + bs, in test_mb_aead_speed()
382 bs + (enc ? 0 : authsize), in test_mb_aead_speed()
386 bs + (enc ? authsize : 0), in test_mb_aead_speed()
409 (enc ? 0 : authsize), in test_mb_aead_speed()
520 unsigned int tcount, u8 authsize, in test_aead_speed() argument
573 ret = crypto_aead_setauthsize(tfm, authsize); in test_aead_speed()
639 bs + (enc ? authsize : 0), assoc, in test_aead_speed()
[all …]
|
| A D | pcrypt.c | 51 unsigned int authsize) in pcrypt_aead_setauthsize() argument
55 return crypto_aead_setauthsize(ctx->child, authsize); in pcrypt_aead_setauthsize()
|
| A D | algif_aead.c | 434 static int aead_setauthsize(void *private, unsigned int authsize) in aead_setauthsize() argument
436 return crypto_aead_setauthsize(private, authsize); in aead_setauthsize()
|
| A D | testmgr.c | 2047 const unsigned int authsize = vec->clen - vec->plen; in test_aead_vec_cfg() local
2080 err = crypto_aead_setauthsize(tfm, authsize); in test_aead_vec_cfg()
2288 const unsigned int authsize = vec->clen - vec->plen; in mutate_aead_message() local
2321 const unsigned int authsize = vec->clen - vec->plen; in generate_aead_message() local
2392 unsigned int authsize; in generate_random_aead_testvec() local
2406 authsize = maxauthsize; in generate_random_aead_testvec()
2410 authsize = MIN_COLLISION_FREE_AUTHSIZE; in generate_random_aead_testvec()
2411 if (WARN_ON(authsize > maxdatasize)) in generate_random_aead_testvec()
2412 authsize = maxdatasize; in generate_random_aead_testvec()
2413 maxdatasize -= authsize; in generate_random_aead_testvec()
[all …]
|
| A D | simd.c | 280 static int simd_aead_setauthsize(struct crypto_aead *tfm, unsigned int authsize) in simd_aead_setauthsize() argument
285 return crypto_aead_setauthsize(child, authsize); in simd_aead_setauthsize()
|
| A D | chacha20poly1305.c | 321 unsigned int authsize) in chachapoly_setauthsize() argument
323 if (authsize != POLY1305_DIGEST_SIZE) in chachapoly_setauthsize()
|
| A 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()
|
| A D | cryptd.c | 735 unsigned int authsize) in cryptd_aead_setauthsize() argument
740 return crypto_aead_setauthsize(child, authsize); in cryptd_aead_setauthsize()
|