| /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 | 164 void crypto_aegis128_update_neon(void *state, const void *msg) in crypto_aegis128_update_neon() argument
170 st = aegis128_update_neon(st, vld1q_u8(msg)); in crypto_aegis128_update_neon()
226 uint8x16_t msg; in crypto_aegis128_encrypt_chunk_neon() local
233 msg = vld1q_u8(src); in crypto_aegis128_encrypt_chunk_neon()
234 st = aegis128_update_neon(st, msg); in crypto_aegis128_encrypt_chunk_neon()
235 msg ^= s; in crypto_aegis128_encrypt_chunk_neon()
236 vst1q_u8(dst, msg); in crypto_aegis128_encrypt_chunk_neon()
264 vst1q_u8(out - AEGIS_BLOCK_SIZE, msg); in crypto_aegis128_encrypt_chunk_neon()
275 uint8x16_t msg; in crypto_aegis128_decrypt_chunk_neon() local
280 msg = vld1q_u8(src) ^ st.v[1] ^ (st.v[2] & st.v[3]) ^ st.v[4]; in crypto_aegis128_decrypt_chunk_neon()
[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 | 74 const union aegis_block *msg, in crypto_aegis128_update_a() argument
78 crypto_aegis128_update_simd(state, msg); in crypto_aegis128_update_a()
83 crypto_aegis_block_xor(&state->blocks[0], msg); in crypto_aegis128_update_a()
86 static void crypto_aegis128_update_u(struct aegis_state *state, const void *msg, in crypto_aegis128_update_u() argument
90 crypto_aegis128_update_simd(state, msg); in crypto_aegis128_update_u()
95 crypto_xor(state->blocks[0].bytes, msg, AEGIS_BLOCK_SIZE); 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()
206 crypto_aegis128_update_a(state, &msg, false); in crypto_aegis128_encrypt_chunk()
208 crypto_aegis_block_xor(&msg, &tmp); 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()
106 iov_iter_revert(&msg->msg_iter, len); in hash_sendmsg()
115 ctx->more = msg->msg_flags & MSG_MORE; in hash_sendmsg()
184 static int hash_recvmsg(struct socket *sock, struct msghdr *msg, size_t len, in hash_recvmsg() argument
197 msg->msg_flags |= MSG_TRUNC; in hash_recvmsg()
222 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);
42 void crypto_aegis128_update_simd(struct aegis_state *state, const void *msg) in crypto_aegis128_update_simd() argument
45 crypto_aegis128_update_neon(state, msg); in crypto_aegis128_update_simd()
|
| D | af_alg.c | 448 static int af_alg_cmsg_send(struct msghdr *msg, struct af_alg_control *con) in af_alg_cmsg_send() argument
452 for_each_cmsghdr(cmsg, msg) { in af_alg_cmsg_send()
453 if (!CMSG_OK(msg, cmsg)) in af_alg_cmsg_send()
827 int af_alg_sendmsg(struct socket *sock, struct msghdr *msg, size_t size, in af_alg_sendmsg() argument
840 if (msg->msg_controllen) { in af_alg_sendmsg()
841 err = af_alg_cmsg_send(msg, &con); in af_alg_sendmsg()
897 msg, len); in af_alg_sendmsg()
912 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 | 221 static int cryptomgr_notify(struct notifier_block *this, unsigned long msg, in cryptomgr_notify() argument
224 switch (msg) { in cryptomgr_notify()
|
| D | aegis.h | 32 void crypto_aegis128_update_simd(struct aegis_state *state, const void *msg);
|