| /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 | 165 void crypto_aegis128_update_neon(void *state, const void *msg) in crypto_aegis128_update_neon() argument
171 st = aegis128_update_neon(st, vld1q_u8(msg)); in crypto_aegis128_update_neon()
180 uint8x16_t msg; in crypto_aegis128_encrypt_chunk_neon() local
187 msg = vld1q_u8(src); in crypto_aegis128_encrypt_chunk_neon()
188 st = aegis128_update_neon(st, msg); in crypto_aegis128_encrypt_chunk_neon()
189 vst1q_u8(dst, msg ^ s); in crypto_aegis128_encrypt_chunk_neon()
201 msg = vld1q_u8(buf); in crypto_aegis128_encrypt_chunk_neon()
202 st = aegis128_update_neon(st, msg); in crypto_aegis128_encrypt_chunk_neon()
203 vst1q_u8(buf, msg ^ s); in crypto_aegis128_encrypt_chunk_neon()
214 uint8x16_t msg; in crypto_aegis128_decrypt_chunk_neon() local
[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, ctx->used, &len); in _skcipher_recvmsg()
110 if (msg->msg_iocb && !is_sync_kiocb(msg->msg_iocb)) { in _skcipher_recvmsg()
113 areq->iocb = msg->msg_iocb; in _skcipher_recvmsg()
149 static int skcipher_recvmsg(struct socket *sock, struct msghdr *msg, in skcipher_recvmsg() argument
156 while (msg_data_left(msg)) { in skcipher_recvmsg()
157 int err = _skcipher_recvmsg(sock, msg, ignored, flags); in skcipher_recvmsg()
237 static int skcipher_sendmsg_nokey(struct socket *sock, struct msghdr *msg, in skcipher_sendmsg_nokey() argument
[all …]
|
| D | aegis128-core.c | 62 void crypto_aegis128_update_simd(struct aegis_state *state, const void *msg);
87 const union aegis_block *msg) in crypto_aegis128_update_a() argument
90 crypto_aegis128_update_simd(state, msg); in crypto_aegis128_update_a()
95 crypto_aegis_block_xor(&state->blocks[0], msg); in crypto_aegis128_update_a()
98 static void crypto_aegis128_update_u(struct aegis_state *state, const void *msg) in crypto_aegis128_update_u() argument
101 crypto_aegis128_update_simd(state, msg); in crypto_aegis128_update_u()
106 crypto_xor(state->blocks[0].bytes, msg, AEGIS_BLOCK_SIZE); in crypto_aegis128_update_u()
202 union aegis_block msg = {}; in crypto_aegis128_encrypt_chunk() local
203 memcpy(msg.bytes, src, size); in crypto_aegis128_encrypt_chunk()
210 crypto_aegis128_update_a(state, &msg); in crypto_aegis128_encrypt_chunk()
[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()
323 static int aead_recvmsg(struct socket *sock, struct msghdr *msg, in aead_recvmsg() argument
330 while (msg_data_left(msg)) { in aead_recvmsg()
331 int err = _aead_recvmsg(sock, msg, ignored, flags); in aead_recvmsg()
411 static int aead_sendmsg_nokey(struct socket *sock, struct msghdr *msg, in aead_sendmsg_nokey() argument
[all …]
|
| 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()
|
| D | aegis128-neon.c | 12 void crypto_aegis128_update_neon(void *state, const void *msg);
40 void crypto_aegis128_update_simd(union aegis_block *state, const void *msg) in crypto_aegis128_update_simd() argument
43 crypto_aegis128_update_neon(state, msg); in crypto_aegis128_update_simd()
|
| D | af_alg.c | 451 static int af_alg_cmsg_send(struct msghdr *msg, struct af_alg_control *con) in af_alg_cmsg_send() argument
455 for_each_cmsghdr(cmsg, msg) { in af_alg_cmsg_send()
456 if (!CMSG_OK(msg, cmsg)) in af_alg_cmsg_send()
830 int af_alg_sendmsg(struct socket *sock, struct msghdr *msg, size_t size, in af_alg_sendmsg() argument
843 if (msg->msg_controllen) { in af_alg_sendmsg()
844 err = af_alg_cmsg_send(msg, &con); in af_alg_sendmsg()
900 msg, len); in af_alg_sendmsg()
915 err = af_alg_wait_for_wmem(sk, msg->msg_flags); in af_alg_sendmsg()
945 msg, plen); in af_alg_sendmsg()
968 ctx->more = msg->msg_flags & MSG_MORE; in af_alg_sendmsg()
[all …]
|
| D | algboss.c | 252 static int cryptomgr_notify(struct notifier_block *this, unsigned long msg, in cryptomgr_notify() argument
255 switch (msg) { in cryptomgr_notify()
|