| /crypto/asymmetric_keys/ |
| D | pkcs7_parser.c | 24 struct pkcs7_message *msg; /* Message being constructed */ member
86 static int pkcs7_check_authattrs(struct pkcs7_message *msg) in pkcs7_check_authattrs() argument
91 sinfo = msg->signed_infos; in pkcs7_check_authattrs()
97 msg->have_authattrs = true; in pkcs7_check_authattrs()
118 struct pkcs7_message *msg = ERR_PTR(-ENOMEM); in pkcs7_parse_message() local
124 ctx->msg = kzalloc(sizeof(struct pkcs7_message), GFP_KERNEL); in pkcs7_parse_message()
125 if (!ctx->msg) in pkcs7_parse_message()
137 ctx->ppsinfo = &ctx->msg->signed_infos; in pkcs7_parse_message()
142 msg = ERR_PTR(ret); in pkcs7_parse_message()
146 ret = pkcs7_check_authattrs(ctx->msg); in pkcs7_parse_message()
[all …]
|
| /crypto/ |
| D | aegis128-neon-inner.c | 135 void crypto_aegis128_update_neon(void *state, const void *msg) in crypto_aegis128_update_neon() argument
141 st = aegis128_update_neon(st, vld1q_u8(msg)); in crypto_aegis128_update_neon()
150 uint8x16_t msg; in crypto_aegis128_encrypt_chunk_neon() local
157 msg = vld1q_u8(src); in crypto_aegis128_encrypt_chunk_neon()
158 st = aegis128_update_neon(st, msg); in crypto_aegis128_encrypt_chunk_neon()
159 vst1q_u8(dst, msg ^ s); in crypto_aegis128_encrypt_chunk_neon()
171 msg = vld1q_u8(buf); in crypto_aegis128_encrypt_chunk_neon()
172 st = aegis128_update_neon(st, msg); in crypto_aegis128_encrypt_chunk_neon()
173 vst1q_u8(buf, msg ^ s); in crypto_aegis128_encrypt_chunk_neon()
184 uint8x16_t msg; in crypto_aegis128_decrypt_chunk_neon() local
[all …]
|
| D | aegis128-core.c | 69 void crypto_aegis128_update_simd(struct aegis_state *state, const void *msg);
88 const union aegis_block *msg) in crypto_aegis128_update_a() argument
91 crypto_aegis128_update_simd(state, msg); in crypto_aegis128_update_a()
96 crypto_aegis_block_xor(&state->blocks[0], msg); in crypto_aegis128_update_a()
99 static void crypto_aegis128_update_u(struct aegis_state *state, const void *msg) in crypto_aegis128_update_u() argument
102 crypto_aegis128_update_simd(state, msg); in crypto_aegis128_update_u()
107 crypto_xor(state->blocks[0].bytes, msg, AEGIS_BLOCK_SIZE); in crypto_aegis128_update_u()
203 union aegis_block msg = {}; in crypto_aegis128_encrypt_chunk() local
204 memcpy(msg.bytes, src, size); in crypto_aegis128_encrypt_chunk()
211 crypto_aegis128_update_a(state, &msg); in crypto_aegis128_encrypt_chunk()
[all …]
|
| 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()
50 static int _skcipher_recvmsg(struct socket *sock, struct msghdr *msg, in _skcipher_recvmsg() argument
77 err = af_alg_get_rsgl(sk, msg, flags, areq, -1, &len); in _skcipher_recvmsg()
114 if (msg->msg_iocb && !is_sync_kiocb(msg->msg_iocb)) { in _skcipher_recvmsg()
117 areq->iocb = msg->msg_iocb; in _skcipher_recvmsg()
153 static int skcipher_recvmsg(struct socket *sock, struct msghdr *msg, in skcipher_recvmsg() argument
160 while (msg_data_left(msg)) { in skcipher_recvmsg()
161 int err = _skcipher_recvmsg(sock, msg, ignored, flags); in skcipher_recvmsg()
246 static int skcipher_sendmsg_nokey(struct socket *sock, struct msghdr *msg, in skcipher_sendmsg_nokey() argument
[all …]
|
| D | algif_hash.c | 63 static int hash_sendmsg(struct socket *sock, struct msghdr *msg, in hash_sendmsg() argument
78 if ((msg->msg_flags & MSG_MORE)) in hash_sendmsg()
88 while (msg_data_left(msg)) { in hash_sendmsg()
89 int len = msg_data_left(msg); in hash_sendmsg()
94 len = af_alg_make_sg(&ctx->sgl, &msg->msg_iter, len); in hash_sendmsg()
109 iov_iter_advance(&msg->msg_iter, len); in hash_sendmsg()
114 ctx->more = msg->msg_flags & MSG_MORE; in hash_sendmsg()
183 static int hash_recvmsg(struct socket *sock, struct msghdr *msg, size_t len, in hash_recvmsg() argument
196 msg->msg_flags |= MSG_TRUNC; in hash_recvmsg()
221 err = memcpy_to_msg(msg, ctx->result, len); in hash_recvmsg()
[all …]
|
| D | algif_aead.c | 61 static int aead_sendmsg(struct socket *sock, struct msghdr *msg, size_t size) in aead_sendmsg() argument
71 return af_alg_sendmsg(sock, msg, size, ivsize); in aead_sendmsg()
88 static int _aead_recvmsg(struct socket *sock, struct msghdr *msg, in _aead_recvmsg() argument
159 err = af_alg_get_rsgl(sk, msg, flags, areq, outlen, &usedpages); in _aead_recvmsg()
285 if (msg->msg_iocb && !is_sync_kiocb(msg->msg_iocb)) { in _aead_recvmsg()
288 areq->iocb = msg->msg_iocb; in _aead_recvmsg()
322 static int aead_recvmsg(struct socket *sock, struct msghdr *msg, in aead_recvmsg() argument
329 while (msg_data_left(msg)) { in aead_recvmsg()
330 int err = _aead_recvmsg(sock, msg, ignored, flags); in aead_recvmsg()
415 static int aead_sendmsg_nokey(struct socket *sock, struct msghdr *msg, in aead_sendmsg_nokey() argument
[all …]
|
| D | aegis128-neon.c | 11 void crypto_aegis128_update_neon(void *state, const void *msg);
28 void crypto_aegis128_update_simd(union aegis_block *state, const void *msg) in crypto_aegis128_update_simd() argument
31 crypto_aegis128_update_neon(state, msg); in crypto_aegis128_update_simd()
|
| D | af_alg.c | 440 static int af_alg_cmsg_send(struct msghdr *msg, struct af_alg_control *con) in af_alg_cmsg_send() argument
444 for_each_cmsghdr(cmsg, msg) { in af_alg_cmsg_send()
445 if (!CMSG_OK(msg, cmsg)) in af_alg_cmsg_send()
815 int af_alg_sendmsg(struct socket *sock, struct msghdr *msg, size_t size, in af_alg_sendmsg() argument
828 if (msg->msg_controllen) { in af_alg_sendmsg()
829 err = af_alg_cmsg_send(msg, &con); in af_alg_sendmsg()
878 msg, len); in af_alg_sendmsg()
893 err = af_alg_wait_for_wmem(sk, msg->msg_flags); in af_alg_sendmsg()
923 msg, plen); in af_alg_sendmsg()
946 ctx->more = msg->msg_flags & MSG_MORE; in af_alg_sendmsg()
[all …]
|
| D | algif_rng.c | 58 static int rng_recvmsg(struct socket *sock, struct msghdr *msg, size_t len, in rng_recvmsg() argument
89 err = memcpy_to_msg(msg, result, len); in rng_recvmsg()
|
| D | algboss.c | 264 static int cryptomgr_notify(struct notifier_block *this, unsigned long msg, in cryptomgr_notify() argument
267 switch (msg) { in cryptomgr_notify()
|