Home
last modified time | relevance | path

Searched refs:iv (Results 1 – 25 of 156) sorted by relevance

1234567

/f-stack/freebsd/crypto/rijndael/
H A Drijndael-api-fst.c163 iv[0][0] = (iv[0][0] << 1) | (iv[0][1] >> 7); in rijndael_blockEncrypt()
164 iv[0][1] = (iv[0][1] << 1) | (iv[0][2] >> 7); in rijndael_blockEncrypt()
165 iv[0][2] = (iv[0][2] << 1) | (iv[0][3] >> 7); in rijndael_blockEncrypt()
166 iv[0][3] = (iv[0][3] << 1) | (iv[1][0] >> 7); in rijndael_blockEncrypt()
167 iv[1][0] = (iv[1][0] << 1) | (iv[1][1] >> 7); in rijndael_blockEncrypt()
168 iv[1][1] = (iv[1][1] << 1) | (iv[1][2] >> 7); in rijndael_blockEncrypt()
169 iv[1][2] = (iv[1][2] << 1) | (iv[1][3] >> 7); in rijndael_blockEncrypt()
170 iv[1][3] = (iv[1][3] << 1) | (iv[2][0] >> 7); in rijndael_blockEncrypt()
171 iv[2][0] = (iv[2][0] << 1) | (iv[2][1] >> 7); in rijndael_blockEncrypt()
172 iv[2][1] = (iv[2][1] << 1) | (iv[2][2] >> 7); in rijndael_blockEncrypt()
[all …]
/f-stack/dpdk/app/test/
H A Dtest_cryptodev_aead_test_vectors.h41 } iv; member
73 } iv; member
96 .iv = {
133 .iv = {
171 .iv = {
223 .iv = {
278 .iv = {
333 .iv = {
388 .iv = {
443 .iv = {
[all …]
H A Dtest_cryptodev_security_docsis_test_vectors.h23 } iv; member
52 .iv = {
101 .iv = {
150 .iv = {
201 .iv = {
254 .iv = {
317 .iv = {
382 .iv = {
447 .iv = {
496 .iv = {
[all …]
H A Dtest_cryptodev_des_test_vectors.h114 .iv = {
140 .iv = {
175 .iv = {
286 .iv = {
313 .iv = {
349 .iv = {
528 .iv = {
554 .iv = {
589 .iv = {
700 .iv = {
[all …]
H A Dtest_cryptodev_aes_test_vectors.h730 .iv = {
755 .iv = {
781 .iv = {
805 .iv = {
830 .iv = {
856 .iv = {
880 .iv = {
1106 .iv = {
1152 .iv = {
1197 .iv = {
[all …]
/f-stack/dpdk/drivers/crypto/bcmfs/
H A Dbcmfs_sym.c51 fsattr_sz(&iv) = sess->cipher.iv.length; in process_crypto_cipher_op()
59 &dst, &key, &iv); in process_crypto_cipher_op()
101 fsattr_pa(&iv) = 0; in process_crypto_auth_op()
102 fsattr_sz(&iv) = sess->auth.iv.length; in process_crypto_auth_op()
104 fsattr_va(&iv) = NULL; in process_crypto_auth_op()
105 fsattr_sz(&iv) = 0; in process_crypto_auth_op()
113 &key, &iv); in process_crypto_auth_op()
156 fsattr_pa(&iv) = 0; in process_crypto_combined_op()
157 fsattr_sz(&iv) = sess->cipher.iv.length; in process_crypto_combined_op()
231 fsattr_pa(&iv) = 0; in process_crypto_aead_op()
[all …]
H A Dbcmfs_sym_session.c61 sess->cipher.iv.offset = cipher_xform->iv.offset; in crypto_set_session_cipher_parameters()
62 sess->cipher.iv.length = cipher_xform->iv.length; in crypto_set_session_cipher_parameters()
86 sess->auth.iv.length = auth_xform->iv.length; in crypto_set_session_auth_parameters()
87 sess->auth.iv.offset = auth_xform->iv.offset; in crypto_set_session_auth_parameters()
107 sess->aead.iv.offset = aead_xform->aead.iv.offset; in crypto_set_session_aead_parameters()
108 sess->aead.iv.length = aead_xform->aead.iv.length; in crypto_set_session_aead_parameters()
/f-stack/dpdk/lib/librte_ipsec/
H A Dcrypto.h20 uint64_t iv; member
31 uint64_t iv; member
51 uint64_t iv; member
55 aes_ctr_cnt_blk_fill(struct aesctr_cnt_blk *ctr, uint64_t iv, uint32_t nonce) in aes_ctr_cnt_blk_fill() argument
58 ctr->iv = iv; in aes_ctr_cnt_blk_fill()
63 aead_gcm_iv_fill(struct aead_gcm_iv *gcm, uint64_t iv, uint32_t salt) in aead_gcm_iv_fill() argument
66 gcm->iv = iv; in aead_gcm_iv_fill()
90 gen_iv(uint64_t iv[IPSEC_MAX_IV_QWORD], rte_be64_t sqn) in gen_iv()
92 iv[0] = sqn; in gen_iv()
93 iv[1] = 0; in gen_iv()
H A Desp_outb.c117 uint64_t *iv; in outb_tun_pkt_prepare() local
246 gen_iv(iv, sqc); in esp_outb_tun_prepare()
285 uint64_t *iv; in outb_trs_pkt_prepare() local
389 gen_iv(iv, sqc); in esp_outb_trs_prepare()
417 uint32_t plen, void *iv) in outb_cpu_crypto_prepare() argument
419 uint64_t *ivp = iv; in outb_cpu_crypto_prepare()
426 gcm = iv; in outb_cpu_crypto_prepare()
430 ctr = iv; in outb_cpu_crypto_prepare()
491 iv[k].va = ivbuf[k]; in cpu_outb_pkt_prepare()
618 gen_iv(iv, sqc); in inline_outb_tun_pkt_process()
[all …]
/f-stack/freebsd/contrib/openzfs/module/zfs/
H A Dvdev_indirect.c313 kmem_free(iv, sizeof (*iv)); in vdev_indirect_map_free()
1302 indirect_vsd_t *iv = kmem_zalloc(sizeof (*iv), KM_SLEEP); in vdev_indirect_io_start() local
1306 zio->io_vsd = iv; in vdev_indirect_io_start()
1534 iv->iv_attempts = 0; in vdev_indirect_splits_enumerate_all()
1541 iv->iv_attempts++; in vdev_indirect_splits_enumerate_all()
1560 ASSERT3S(iv->iv_attempts, <=, iv->iv_unique_combinations); in vdev_indirect_splits_enumerate_all()
1573 iv->iv_attempts = 0; in vdev_indirect_splits_enumerate_randomly()
1575 while (iv->iv_attempts < iv->iv_attempts_max) { in vdev_indirect_splits_enumerate_randomly()
1576 iv->iv_attempts++; in vdev_indirect_splits_enumerate_randomly()
1642 iv->iv_attempts_max = 1; in vdev_indirect_splits_damage()
[all …]
/f-stack/dpdk/drivers/common/dpaax/caamflib/desc/
H A Dalgo.h181 iv[8] = iv[0]; in conv_to_zuc_eia_iv()
182 iv[9] = iv[1]; in conv_to_zuc_eia_iv()
183 iv[10] = iv[2]; in conv_to_zuc_eia_iv()
184 iv[11] = iv[3]; in conv_to_zuc_eia_iv()
201 iv[12] = iv[4]; in conv_to_snow_f9_iv()
202 iv[13] = iv[5]; in conv_to_snow_f9_iv()
203 iv[14] = iv[6]; in conv_to_snow_f9_iv()
211 iv[4] = iv[0]; in conv_to_snow_f9_iv()
212 iv[5] = iv[1]; in conv_to_snow_f9_iv()
213 iv[6] = iv[2]; in conv_to_snow_f9_iv()
[all …]
/f-stack/freebsd/netpfil/ipfw/
H A Dip_fw_table_value.c644 v.tag = iv->tag; in ipfw_import_table_value_v1()
649 v.fib = iv->fib; in ipfw_import_table_value_v1()
650 v.nat = iv->nat; in ipfw_import_table_value_v1()
652 v.nh4 = iv->nh4; in ipfw_import_table_value_v1()
653 v.nh6 = iv->nh6; in ipfw_import_table_value_v1()
669 memset(&iv, 0, sizeof(iv)); in ipfw_export_table_value_v1()
670 iv.tag = v->tag; in ipfw_export_table_value_v1()
675 iv.fib = v->fib; in ipfw_export_table_value_v1()
676 iv.nat = v->nat; in ipfw_export_table_value_v1()
679 iv.nh4 = v->nh4; in ipfw_export_table_value_v1()
[all …]
/f-stack/dpdk/examples/fips_validation/
H A Dfips_validation_gcm.c88 if (!vec.iv.val) { in parse_gcm_pt_ct_str()
89 vec.iv.val = rte_malloc(0, vec.iv.len, 0); in parse_gcm_pt_ct_str()
90 if (!vec.iv.val) in parse_gcm_pt_ct_str()
94 for (i = 0; i < vec.iv.len; i++) { in parse_gcm_pt_ct_str()
96 vec.iv.val[i] = (uint8_t)random; in parse_gcm_pt_ct_str()
109 {IV_STR, parse_uint8_known_len_hex_str, &vec.iv},
119 {IVLEN_STR, parser_read_uint32_bit_val, &vec.iv},
150 tmp_val.val = vec.iv.val; in parse_test_gcm_writeback()
151 tmp_val.len = vec.iv.len; in parse_test_gcm_writeback()
154 rte_free(vec.iv.val); in parse_test_gcm_writeback()
[all …]
H A Dmain.c593 memcpy(iv, vec.iv.val, vec.iv.len); in prepare_cipher_op()
628 memset(iv, 0, vec.iv.len); in prepare_auth_op()
630 memcpy(iv, vec.iv.val, vec.iv.len); in prepare_auth_op()
676 memcpy(iv, vec.iv.val, vec.iv.len); in prepare_aead_op()
679 memset(iv, 0, vec.iv.len); in prepare_aead_op()
740 cipher_xform->iv.length = vec.iv.len; in prepare_aes_xform()
788 cipher_xform->iv.length = vec.iv.len; in prepare_tdes_xform()
866 aead_xform->iv.length = vec.iv.len; in prepare_gcm_xform()
913 auth_xform->iv.length = vec.iv.len; in prepare_gmac_xform()
995 aead_xform->iv.length = vec.iv.len; in prepare_ccm_xform()
[all …]
H A Dfips_dev_self_test.c32 } iv; member
369 .iv = {
428 .iv = {
470 .iv = {
514 .iv = {
558 .iv = {
1028 cipher_xform->iv.length = vec->iv.len; in prepare_cipher_xform()
1142 aead_xform->iv.length = vec->iv.len; in prepare_aead_xform()
1195 memcpy(iv, vec->iv.data, vec->iv.len); in prepare_cipher_op()
1273 memcpy(iv + 1, vec->iv.data, vec->iv.len); in prepare_aead_op()
[all …]
H A Dfips_validation_ccm.c111 {IV_STR, parse_uint8_known_len_hex_str, &vec.iv},
121 {IVLEN_PREFIX, parser_read_uint32_val, &vec.iv},
135 {IVLEN_PREFIX, parser_read_uint32_val, &vec.iv},
138 {IV_STR, parse_uint8_known_len_hex_str, &vec.iv},
150 {IVLEN_PREFIX, parser_read_uint32_val, &vec.iv},
154 {IV_STR, parse_uint8_known_len_hex_str, &vec.iv},
166 {IVLEN_PREFIX, parser_read_uint32_val, &vec.iv},
170 {IV_STR, parse_uint8_known_len_hex_str, &vec.iv},
175 {IV_STR, parse_uint8_known_len_hex_str, &vec.iv},
184 {IVLEN_PREFIX, parser_dvpt_interim, &vec.iv},
/f-stack/freebsd/contrib/libsodium/src/libsodium/crypto_stream/chacha20/dolbeau/
H A Dchacha20_dolbeau-ssse3.c49 chacha_ivsetup(chacha_ctx *ctx, const uint8_t *iv, const uint8_t *counter) in chacha_ivsetup() argument
53 ctx->input[14] = LOAD32_LE(iv + 0); in chacha_ivsetup()
54 ctx->input[15] = LOAD32_LE(iv + 4); in chacha_ivsetup()
58 chacha_ietf_ivsetup(chacha_ctx *ctx, const uint8_t *iv, const uint8_t *counter) in chacha_ietf_ivsetup() argument
61 ctx->input[13] = LOAD32_LE(iv + 0); in chacha_ietf_ivsetup()
62 ctx->input[14] = LOAD32_LE(iv + 4); in chacha_ietf_ivsetup()
63 ctx->input[15] = LOAD32_LE(iv + 8); in chacha_ietf_ivsetup()
H A Dchacha20_dolbeau-avx2.c54 chacha_ivsetup(chacha_ctx *ctx, const uint8_t *iv, const uint8_t *counter) in chacha_ivsetup() argument
58 ctx->input[14] = LOAD32_LE(iv + 0); in chacha_ivsetup()
59 ctx->input[15] = LOAD32_LE(iv + 4); in chacha_ivsetup()
63 chacha_ietf_ivsetup(chacha_ctx *ctx, const uint8_t *iv, const uint8_t *counter) in chacha_ietf_ivsetup() argument
66 ctx->input[13] = LOAD32_LE(iv + 0); in chacha_ietf_ivsetup()
67 ctx->input[14] = LOAD32_LE(iv + 4); in chacha_ietf_ivsetup()
68 ctx->input[15] = LOAD32_LE(iv + 8); in chacha_ietf_ivsetup()
/f-stack/dpdk/drivers/crypto/openssl/
H A Drte_openssl_pmd.c421 sess->iv.offset = xform->cipher.iv.offset; in openssl_set_session_cipher_parameters()
422 sess->iv.length = xform->cipher.iv.length; in openssl_set_session_cipher_parameters()
555 sess->iv.offset = xform->auth.iv.offset; in openssl_set_session_auth_parameters()
556 sess->iv.length = xform->auth.iv.length; in openssl_set_session_auth_parameters()
624 sess->iv.offset = xform->aead.iv.offset + 1; in openssl_set_session_aead_parameters()
626 sess->iv.offset = xform->aead.iv.offset; in openssl_set_session_aead_parameters()
628 sess->iv.length = xform->aead.iv.length; in openssl_set_session_aead_parameters()
1486 iv, srclen, in process_openssl_docsis_bpi_op()
1506 dst, iv, in process_openssl_docsis_bpi_op()
1514 iv, in process_openssl_docsis_bpi_op()
[all …]
/f-stack/freebsd/opencrypto/
H A Dxform_aes_icm.c117 aes_icm_reinit(void *key, const uint8_t *iv) in aes_icm_reinit() argument
122 bcopy(iv, ctx->ac_block, AESICM_BLOCKSIZE); in aes_icm_reinit()
126 aes_gcm_reinit(void *key, const uint8_t *iv) in aes_gcm_reinit() argument
130 aes_icm_reinit(key, iv); in aes_gcm_reinit()
139 aes_ccm_reinit(void *key, const uint8_t *iv) in aes_ccm_reinit() argument
149 bcopy(iv, ctx->ac_block+1, AES_CCM_IV_LEN); in aes_ccm_reinit()
/f-stack/freebsd/crypto/armv8/
H A Darmv8_crypto_wrap.c103 ivreg = vld1q_u8(iv); in armv8_aes_encrypt_cbc()
123 ivreg = vld1q_u8(iv); in armv8_aes_decrypt_cbc()
188 bcopy(iv, tweak, AES_XTS_IVSIZE); in armv8_aes_crypt_xts()
209 const uint8_t iv[static AES_BLOCK_LEN]) in armv8_aes_encrypt_xts()
214 to, iv, 1); in armv8_aes_encrypt_xts()
220 const uint8_t iv[static AES_BLOCK_LEN]) in armv8_aes_decrypt_xts()
225 to,iv, 0); in armv8_aes_decrypt_xts()
242 const uint8_t iv[static AES_GCM_IV_LEN], in armv8_aes_encrypt_gcm()
254 memcpy(aes_counter, iv, AES_GCM_IV_LEN); in armv8_aes_encrypt_gcm()
328 const uint8_t iv[static AES_GCM_IV_LEN], in armv8_aes_decrypt_gcm()
[all …]
/f-stack/freebsd/net80211/
H A Dieee80211_crypto_wep.c129 uint32_t iv; in wep_setiv() local
153 iv = ctx->wc_iv; in wep_setiv()
154 if ((iv & 0xff00) == 0xff00) { in wep_setiv()
157 iv += 0x0100; in wep_setiv()
159 ctx->wc_iv = iv + 1; in wep_setiv()
166 ivp[0] = iv >> 0; in wep_setiv()
167 ivp[1] = iv >> 8; in wep_setiv()
168 ivp[2] = iv >> 16; in wep_setiv()
170 ivp[2] = iv >> 0; in wep_setiv()
171 ivp[1] = iv >> 8; in wep_setiv()
[all …]
/f-stack/freebsd/contrib/openzfs/include/sys/
H A Dzio_crypt.h126 int zio_crypt_key_wrap(crypto_key_t *cwkey, zio_crypt_key_t *key, uint8_t *iv,
129 uint64_t guid, uint8_t *keydata, uint8_t *hmac_keydata, uint8_t *iv,
135 void zio_crypt_encode_params_bp(blkptr_t *bp, uint8_t *salt, uint8_t *iv);
136 void zio_crypt_decode_params_bp(const blkptr_t *bp, uint8_t *salt, uint8_t *iv);
152 dmu_object_type_t ot, boolean_t byteswap, uint8_t *salt, uint8_t *iv,
156 dmu_object_type_t ot, boolean_t byteswap, uint8_t *salt, uint8_t *iv,
/f-stack/dpdk/drivers/crypto/nitrox/
H A Dnitrox_sym_reqmgr.c145 struct iv { struct
159 struct iv iv; argument
243 uint16_t offset = sr->ctx->iv.offset + salt_size; in softreq_copy_iv()
247 sr->iv.len = sr->ctx->iv.length - salt_size; in softreq_copy_iv()
334 fill_sglist(&sr->in, sr->iv.len, sr->iv.iova, sr->iv.virt); in create_cipher_inbuf()
363 fill_sglist(&sr->out, sr->iv.len, sr->iv.iova, sr->iv.virt); in create_cipher_outbuf()
456 fill_sglist(sgtbl, sr->iv.len, sr->iv.iova, sr->iv.virt); in create_cipher_auth_sglist()
487 fill_sglist(sgtbl, sr->iv.len, sr->iv.iova, sr->iv.virt); in create_combined_sglist()
671 if (unlikely(ctx->iv.length < AES_GCM_SALT_SIZE)) { in softreq_copy_salt()
681 memcpy(ctx->fctx.crypto.iv, addr, AES_GCM_SALT_SIZE); in softreq_copy_salt()
[all …]
/f-stack/freebsd/crypto/aesni/
H A Daesni.h82 const uint8_t iv[__min_size(AES_BLOCK_LEN)]);
84 size_t len, uint8_t *buf, const uint8_t iv[__min_size(AES_BLOCK_LEN)]);
91 const uint8_t iv[__min_size(AES_BLOCK_LEN)]);
96 const uint8_t iv[__min_size(AES_BLOCK_LEN)]);
100 const uint8_t iv[__min_size(AES_BLOCK_LEN)]);

1234567