| /crypto/asymmetric_keys/ |
| A D | pkcs7_parser.c | 91 sinfo = msg->signed_infos; in pkcs7_check_authattrs()
97 msg->have_authattrs = true; in pkcs7_check_authattrs()
125 if (!ctx->msg) in pkcs7_parse_message()
142 msg = ERR_PTR(ret); in pkcs7_parse_message()
148 msg = ERR_PTR(ret); in pkcs7_parse_message()
152 msg = ctx->msg; in pkcs7_parse_message()
153 ctx->msg = NULL; in pkcs7_parse_message()
164 pkcs7_free_message(ctx->msg); in pkcs7_parse_message()
168 return msg; in pkcs7_parse_message()
490 ctx->msg->data = value; in pkcs7_note_data()
[all …]
|
| /crypto/ |
| A D | algif_hash.c | 83 if (!msg_data_left(msg)) in hash_sendmsg()
86 } else if (!msg_data_left(msg)) { in hash_sendmsg()
91 if (!(msg->msg_flags & MSG_MORE)) { in hash_sendmsg()
105 while (msg_data_left(msg)) { in hash_sendmsg()
126 if (!msg_data_left(msg)) { in hash_sendmsg()
135 if (!msg_data_left(msg) && !continuing && in hash_sendmsg()
136 !(msg->msg_flags & MSG_MORE)) { in hash_sendmsg()
148 if (msg_data_left(msg) || (msg->msg_flags & MSG_MORE)) in hash_sendmsg()
164 ctx->more = msg->msg_flags & MSG_MORE; in hash_sendmsg()
192 msg->msg_flags |= MSG_TRUNC; in hash_recvmsg()
[all …]
|
| A D | aegis128-neon-inner.c | 171 st = aegis128_update_neon(st, vld1q_u8(msg)); in crypto_aegis128_update_neon()
227 uint8x16_t msg; in crypto_aegis128_encrypt_chunk_neon() local
234 msg = vld1q_u8(src); in crypto_aegis128_encrypt_chunk_neon()
235 st = aegis128_update_neon(st, msg); in crypto_aegis128_encrypt_chunk_neon()
236 msg ^= s; in crypto_aegis128_encrypt_chunk_neon()
237 vst1q_u8(dst, msg); in crypto_aegis128_encrypt_chunk_neon()
265 vst1q_u8(out - AEGIS_BLOCK_SIZE, msg); in crypto_aegis128_encrypt_chunk_neon()
276 uint8x16_t msg; in crypto_aegis128_decrypt_chunk_neon() local
282 st = aegis128_update_neon(st, msg); in crypto_aegis128_decrypt_chunk_neon()
283 vst1q_u8(dst, msg); in crypto_aegis128_decrypt_chunk_neon()
[all …]
|
| A D | algif_skcipher.c | 37 static int skcipher_sendmsg(struct socket *sock, struct msghdr *msg, in skcipher_sendmsg() argument
47 return af_alg_sendmsg(sock, msg, size, ivsize); in skcipher_sendmsg()
96 static int _skcipher_recvmsg(struct socket *sock, struct msghdr *msg, in _skcipher_recvmsg() argument
124 err = af_alg_get_rsgl(sk, msg, flags, areq, ctx->used, &len); in _skcipher_recvmsg()
169 if (msg->msg_iocb && !is_sync_kiocb(msg->msg_iocb)) { in _skcipher_recvmsg()
172 areq->iocb = msg->msg_iocb; in _skcipher_recvmsg()
213 static int skcipher_recvmsg(struct socket *sock, struct msghdr *msg, in skcipher_recvmsg() argument
220 while (msg_data_left(msg)) { in skcipher_recvmsg()
221 int err = _skcipher_recvmsg(sock, msg, ignored, flags); in skcipher_recvmsg()
309 return skcipher_sendmsg(sock, msg, size); in skcipher_sendmsg_nokey()
[all …]
|
| A D | algif_aead.c | 63 return af_alg_sendmsg(sock, msg, size, ivsize); in aead_sendmsg()
66 static int _aead_recvmsg(struct socket *sock, struct msghdr *msg, in _aead_recvmsg() argument
135 err = af_alg_get_rsgl(sk, msg, flags, areq, outlen, &usedpages); in _aead_recvmsg()
256 if (msg->msg_iocb && !is_sync_kiocb(msg->msg_iocb)) { in _aead_recvmsg()
259 areq->iocb = msg->msg_iocb; in _aead_recvmsg()
294 static int aead_recvmsg(struct socket *sock, struct msghdr *msg, in aead_recvmsg() argument
301 while (msg_data_left(msg)) { in aead_recvmsg()
302 int err = _aead_recvmsg(sock, msg, ignored, flags); in aead_recvmsg()
381 static int aead_sendmsg_nokey(struct socket *sock, struct msghdr *msg, in aead_sendmsg_nokey() argument
390 return aead_sendmsg(sock, msg, size); in aead_sendmsg_nokey()
[all …]
|
| A D | aegis128-core.c | 74 const union aegis_block *msg, in crypto_aegis128_update_a() argument
78 crypto_aegis128_update_simd(state, msg); in crypto_aegis128_update_a()
90 crypto_aegis128_update_simd(state, msg); in crypto_aegis128_update_u()
198 union aegis_block msg = {}; in crypto_aegis128_encrypt_chunk() local
199 memcpy(msg.bytes, src, size); in crypto_aegis128_encrypt_chunk()
208 crypto_aegis_block_xor(&msg, &tmp); in crypto_aegis128_encrypt_chunk()
210 memcpy(dst, msg.bytes, size); in crypto_aegis128_encrypt_chunk()
259 union aegis_block msg = {}; in crypto_aegis128_decrypt_chunk() local
260 memcpy(msg.bytes, src, size); in crypto_aegis128_decrypt_chunk()
266 crypto_aegis_block_xor(&msg, &tmp); in crypto_aegis128_decrypt_chunk()
[all …]
|
| A D | algif_rng.c | 73 static int _rng_recvmsg(struct crypto_rng *drng, struct msghdr *msg, size_t len, in _rng_recvmsg() argument
101 err = memcpy_to_msg(msg, result, len); in _rng_recvmsg()
107 static int rng_recvmsg(struct socket *sock, struct msghdr *msg, size_t len, in rng_recvmsg() argument
114 return _rng_recvmsg(ctx->drng, msg, len, NULL, 0); in rng_recvmsg()
117 static int rng_test_recvmsg(struct socket *sock, struct msghdr *msg, size_t len, in rng_test_recvmsg() argument
126 ret = _rng_recvmsg(ctx->drng, msg, len, ctx->addtl, ctx->addtl_len); in rng_test_recvmsg()
133 static int rng_test_sendmsg(struct socket *sock, struct msghdr *msg, size_t len) in rng_test_sendmsg() argument
152 err = memcpy_from_msg(ctx->addtl, msg, len); in rng_test_sendmsg()
|
| A D | af_alg.c | 563 for_each_cmsghdr(cmsg, msg) { in af_alg_cmsg_send()
564 if (!CMSG_OK(msg, cmsg)) in af_alg_cmsg_send()
951 if (msg->msg_controllen) { in af_alg_sendmsg()
952 err = af_alg_cmsg_send(msg, &con); in af_alg_sendmsg()
1008 msg, len); in af_alg_sendmsg()
1041 if (msg->msg_flags & MSG_SPLICE_PAGES) { in af_alg_sendmsg()
1079 msg, plen); in af_alg_sendmsg()
1103 ctx->more = msg->msg_flags & MSG_MORE; in af_alg_sendmsg()
1241 while (maxsize > len && msg_data_left(msg)) { in af_alg_get_rsgl()
1251 msg_data_left(msg)); in af_alg_get_rsgl()
[all …]
|
| A D | aegis128-neon.c | 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()
|
| A D | aegis-neon.h | 7 void crypto_aegis128_update_neon(void *state, const void *msg);
|
| A D | algboss.c | 220 static int cryptomgr_notify(struct notifier_block *this, unsigned long msg, in cryptomgr_notify() argument
223 switch (msg) { in cryptomgr_notify()
|
| A D | aegis.h | 32 void crypto_aegis128_update_simd(struct aegis_state *state, const void *msg);
|