Home
last modified time | relevance | path

Searched refs:dat (Results 1 – 25 of 265) sorted by relevance

1234567891011

/src/crypto/openssl/crypto/sm4/asm/
H A Dsm4-armv8.pl269 my @dat=map("v$_",(16..23));
281 ld1 {@dat[0].4s,@dat[1].4s,@dat[2].4s,@dat[3].4s},[$inp],#64
284 ld1 {@dat[4].4s,@dat[5].4s,@dat[6].4s,@dat[7].4s},[$inp],#64
287 &rev32(@dat[0],@dat[0]);
288 &rev32(@dat[1],@dat[1]);
289 &rev32(@dat[2],@dat[2]);
290 &rev32(@dat[3],@dat[3]);
291 &rev32(@dat[4],@dat[4]);
292 &rev32(@dat[5],@dat[5]);
293 &rev32(@dat[6],@dat[6]);
[all …]
/src/crypto/openssl/providers/implementations/ciphers/
H A Dciphercommon_hw.c16 int ossl_cipher_hw_generic_cbc(PROV_CIPHER_CTX *dat, unsigned char *out, in ossl_cipher_hw_generic_cbc() argument
19 if (dat->stream.cbc) in ossl_cipher_hw_generic_cbc()
20 (*dat->stream.cbc)(in, out, len, dat->ks, dat->iv, dat->enc); in ossl_cipher_hw_generic_cbc()
21 else if (dat->enc) in ossl_cipher_hw_generic_cbc()
22 CRYPTO_cbc128_encrypt(in, out, len, dat->ks, dat->iv, dat->block); in ossl_cipher_hw_generic_cbc()
24 CRYPTO_cbc128_decrypt(in, out, len, dat->ks, dat->iv, dat->block); in ossl_cipher_hw_generic_cbc()
29 int ossl_cipher_hw_generic_ecb(PROV_CIPHER_CTX *dat, unsigned char *out, in ossl_cipher_hw_generic_ecb() argument
32 size_t i, bl = dat->blocksize; in ossl_cipher_hw_generic_ecb()
37 if (dat->stream.ecb) { in ossl_cipher_hw_generic_ecb()
38 (*dat->stream.ecb)(in, out, len, dat->ks, dat->enc); in ossl_cipher_hw_generic_ecb()
[all …]
H A Dcipher_aes_hw.c19 static int cipher_hw_aes_initkey(PROV_CIPHER_CTX *dat, in cipher_hw_aes_initkey() argument
23 PROV_AES_CTX *adat = (PROV_AES_CTX *)dat; in cipher_hw_aes_initkey()
26 dat->ks = ks; in cipher_hw_aes_initkey()
28 if ((dat->mode == EVP_CIPH_ECB_MODE || dat->mode == EVP_CIPH_CBC_MODE) in cipher_hw_aes_initkey()
29 && !dat->enc) { in cipher_hw_aes_initkey()
33 dat->block = (block128_f)HWAES_decrypt; in cipher_hw_aes_initkey()
34 dat->stream.cbc = NULL; in cipher_hw_aes_initkey()
36 if (dat->mode == EVP_CIPH_CBC_MODE) in cipher_hw_aes_initkey()
37 dat->stream.cbc = (cbc128_f)HWAES_cbc_encrypt; in cipher_hw_aes_initkey()
40 if (dat->mode == EVP_CIPH_ECB_MODE) in cipher_hw_aes_initkey()
[all …]
H A Dcipher_aes_hw_t4.inc15 static int cipher_hw_aes_t4_initkey(PROV_CIPHER_CTX *dat,
19 PROV_AES_CTX *adat = (PROV_AES_CTX *)dat;
22 dat->ks = (const void *)ks; /* used by cipher_hw_generic_XXX */
25 if ((dat->mode == EVP_CIPH_ECB_MODE || dat->mode == EVP_CIPH_CBC_MODE)
26 && !dat->enc) {
29 dat->block = (block128_f)aes_t4_decrypt;
32 dat->stream.cbc = dat->mode == EVP_CIPH_CBC_MODE ?
36 dat->stream.cbc = dat->mode == EVP_CIPH_CBC_MODE ?
40 dat->stream.cbc = dat->mode == EVP_CIPH_CBC_MODE ?
49 dat->block = (block128_f)aes_t4_encrypt;
[all …]
H A Dcipher_aes_hw_rv64i.inc23 static int cipher_hw_rv64i_zknd_zkne_initkey(PROV_CIPHER_CTX *dat,
27 PROV_AES_CTX *adat = (PROV_AES_CTX *)dat;
30 dat->ks = ks;
32 if ((dat->mode == EVP_CIPH_ECB_MODE || dat->mode == EVP_CIPH_CBC_MODE)
33 && !dat->enc) {
35 dat->block = (block128_f) rv64i_zknd_decrypt;
36 dat->stream.cbc = NULL;
39 dat->block = (block128_f) rv64i_zkne_encrypt;
40 dat->stream.cbc = NULL;
64 static int cipher_hw_rv64i_zvkned_initkey(PROV_CIPHER_CTX *dat,
[all …]
H A Dcipher_aes_hw_s390x.inc33 static int s390x_aes_ecb_initkey(PROV_CIPHER_CTX *dat,
36 PROV_AES_CTX *adat = (PROV_AES_CTX *)dat;
43 static int s390x_aes_ecb_cipher_hw(PROV_CIPHER_CTX *dat, unsigned char *out,
46 PROV_AES_CTX *adat = (PROV_AES_CTX *)dat;
54 static int s390x_aes_ofb128_initkey(PROV_CIPHER_CTX *dat,
57 PROV_AES_CTX *adat = (PROV_AES_CTX *)dat;
64 static int s390x_aes_ofb128_cipher_hw(PROV_CIPHER_CTX *dat, unsigned char *out,
67 PROV_AES_CTX *adat = (PROV_AES_CTX *)dat;
68 int n = dat->num;
71 memcpy(adat->plat.s390x.param.kmo_kmf.cv, dat->iv, dat->ivlen);
[all …]
H A Dcipher_aes_hw_rv32i.inc31 static int cipher_hw_rv32i_zknd_zkne_initkey(PROV_CIPHER_CTX *dat,
35 PROV_AES_CTX *adat = (PROV_AES_CTX *)dat;
38 dat->ks = ks;
40 if ((dat->mode == EVP_CIPH_ECB_MODE || dat->mode == EVP_CIPH_CBC_MODE)
41 && !dat->enc) {
43 dat->block = (block128_f) rv32i_zknd_decrypt;
44 dat->stream.cbc = NULL;
47 dat->block = (block128_f) rv32i_zkne_encrypt;
48 dat->stream.cbc = NULL;
59 static int cipher_hw_rv32i_zbkb_zknd_zkne_initkey(PROV_CIPHER_CTX *dat,
[all …]
H A Dcipher_camellia_hw_t4.inc15 static int cipher_hw_camellia_t4_initkey(PROV_CIPHER_CTX *dat,
19 int ret = 0, bits, mode = dat->mode;
20 PROV_CAMELLIA_CTX *adat = (PROV_CAMELLIA_CTX *)dat;
23 dat->ks = ks;
28 if (dat->enc || (mode != EVP_CIPH_ECB_MODE && mode != EVP_CIPH_CBC_MODE)) {
29 dat->block = (block128_f) cmll_t4_encrypt;
33 dat->stream.cbc = (cbc128_f) cmll128_t4_cbc_encrypt;
35 dat->stream.ctr = (ctr128_f) cmll128_t4_ctr32_encrypt;
37 dat->stream.cbc = NULL;
42 dat->stream.cbc = (cbc128_f) cmll256_t4_cbc_encrypt;
[all …]
/src/contrib/tcpdump/
H A Dprint-l2tp.c266 print_string(netdissect_options *ndo, const u_char *dat, u_int length) in print_string() argument
270 fn_print_char(ndo, GET_U_1(dat)); in print_string()
271 dat++; in print_string()
276 print_octets(netdissect_options *ndo, const u_char *dat, u_int length) in print_octets() argument
280 ND_PRINT("%02x", GET_U_1(dat)); in print_octets()
281 dat++; in print_octets()
286 print_16bits_val(netdissect_options *ndo, const uint8_t *dat) in print_16bits_val() argument
288 ND_PRINT("%u", GET_BE_U_2(dat)); in print_16bits_val()
292 print_32bits_val(netdissect_options *ndo, const uint8_t *dat) in print_32bits_val() argument
294 ND_PRINT("%u", GET_BE_U_4(dat)); in print_32bits_val()
[all …]
H A Dprint-pptp.c533 const u_char *dat) in pptp_sccrq_print() argument
535 const struct pptp_msg_sccrq *ptr = (const struct pptp_msg_sccrq *)dat; in pptp_sccrq_print()
549 const u_char *dat) in pptp_sccrp_print() argument
551 const struct pptp_msg_sccrp *ptr = (const struct pptp_msg_sccrp *)dat; in pptp_sccrp_print()
566 const u_char *dat) in pptp_stopccrq_print() argument
568 const struct pptp_msg_stopccrq *ptr = (const struct pptp_msg_stopccrq *)dat; in pptp_stopccrq_print()
594 const u_char *dat) in pptp_stopccrp_print() argument
596 const struct pptp_msg_stopccrp *ptr = (const struct pptp_msg_stopccrp *)dat; in pptp_stopccrp_print()
605 const u_char *dat) in pptp_echorq_print() argument
607 const struct pptp_msg_echorq *ptr = (const struct pptp_msg_echorq *)dat; in pptp_echorq_print()
[all …]
H A Dprint-aodv.c209 aodv_rreq(netdissect_options *ndo, const u_char *dat, u_int length) in aodv_rreq() argument
212 const struct aodv_rreq *ap = (const struct aodv_rreq *)dat; in aodv_rreq()
232 aodv_extension(ndo, (const struct aodv_ext *)(dat + sizeof(*ap)), i); in aodv_rreq()
240 aodv_rrep(netdissect_options *ndo, const u_char *dat, u_int length) in aodv_rrep() argument
243 const struct aodv_rrep *ap = (const struct aodv_rrep *)dat; in aodv_rrep()
260 aodv_extension(ndo, (const struct aodv_ext *)(dat + sizeof(*ap)), i); in aodv_rrep()
268 aodv_rerr(netdissect_options *ndo, const u_char *dat, u_int length) in aodv_rerr() argument
271 const struct aodv_rerr *ap = (const struct aodv_rerr *)dat; in aodv_rerr()
280 dp = (const struct rerr_unreach *)(dat + sizeof(*ap)); in aodv_rerr()
298 aodv_v6_rreq(netdissect_options *ndo, const u_char *dat, u_int length) in aodv_v6_rreq() argument
[all …]
/src/tests/sys/cddl/zfs/tests/cli_root/zpool_upgrade/blockfiles/
H A DMakefile8 ${PACKAGE}FILES+= zfs-broken-mirror1.dat.Z
9 ${PACKAGE}FILES+= zfs-broken-mirror2.dat.Z
10 ${PACKAGE}FILES+= zfs-pool-v1.dat.Z
11 ${PACKAGE}FILES+= zfs-pool-v10.dat.Z
12 ${PACKAGE}FILES+= zfs-pool-v11.dat.Z
13 ${PACKAGE}FILES+= zfs-pool-v12.dat.Z
14 ${PACKAGE}FILES+= zfs-pool-v13.dat.Z
15 ${PACKAGE}FILES+= zfs-pool-v14.dat.Z
16 ${PACKAGE}FILES+= zfs-pool-v15.dat.Z
17 ${PACKAGE}FILES+= zfs-pool-v1mirror1.dat.Z
[all …]
/src/crypto/openssl/crypto/evp/
H A De_sm4.c63 EVP_SM4_KEY *dat = EVP_C_DATA(EVP_SM4_KEY, ctx); in sm4_init_key() local
70 HWSM4_set_decrypt_key(key, &dat->ks.ks); in sm4_init_key()
71 dat->block = (block128_f)HWSM4_decrypt; in sm4_init_key()
72 dat->stream.cbc = NULL; in sm4_init_key()
75 dat->stream.cbc = (cbc128_f)HWSM4_cbc_encrypt; in sm4_init_key()
79 dat->stream.ecb = (ecb128_f)HWSM4_ecb_encrypt; in sm4_init_key()
85 vpsm4_set_decrypt_key(key, &dat->ks.ks); in sm4_init_key()
86 dat->block = (block128_f)vpsm4_decrypt; in sm4_init_key()
87 dat->stream.cbc = NULL; in sm4_init_key()
89 dat->stream.cbc = (cbc128_f)vpsm4_cbc_encrypt; in sm4_init_key()
[all …]
H A De_camellia.c55 EVP_CAMELLIA_KEY *dat = (EVP_CAMELLIA_KEY *)EVP_CIPHER_CTX_get_cipher_data(ctx); in cmll_t4_init_key() local
60 cmll_t4_set_key(key, bits, &dat->ks); in cmll_t4_init_key()
65 dat->block = (block128_f)cmll_t4_decrypt; in cmll_t4_init_key()
68 dat->stream.cbc = mode == EVP_CIPH_CBC_MODE ? (cbc128_f)cmll128_t4_cbc_decrypt : NULL; in cmll_t4_init_key()
72 dat->stream.cbc = mode == EVP_CIPH_CBC_MODE ? (cbc128_f)cmll256_t4_cbc_decrypt : NULL; in cmll_t4_init_key()
79 dat->block = (block128_f)cmll_t4_encrypt; in cmll_t4_init_key()
83 dat->stream.cbc = (cbc128_f)cmll128_t4_cbc_encrypt; in cmll_t4_init_key()
85 dat->stream.ctr = (ctr128_f)cmll128_t4_ctr32_encrypt; in cmll_t4_init_key()
87 dat->stream.cbc = NULL; in cmll_t4_init_key()
92 dat->stream.cbc = (cbc128_f)cmll256_t4_cbc_encrypt; in cmll_t4_init_key()
[all …]
H A De_des3.c110 DES_EDE_KEY *dat = data(ctx); in des_ede_cbc_cipher() local
112 if (dat->stream.cbc != NULL) { in des_ede_cbc_cipher()
113 (*dat->stream.cbc)(in, out, inl, dat->ks.ks, in des_ede_cbc_cipher()
120 &dat->ks1, &dat->ks2, &dat->ks3, in des_ede_cbc_cipher()
129 &dat->ks1, &dat->ks2, &dat->ks3, in des_ede_cbc_cipher()
229 DES_EDE_KEY *dat = data(ctx); in des_ede_init_key() local
231 dat->stream.cbc = NULL; in des_ede_init_key()
237 des_t4_key_expand(&deskey[0], &dat->ks1); in des_ede_init_key()
238 des_t4_key_expand(&deskey[1], &dat->ks2); in des_ede_init_key()
239 memcpy(&dat->ks3, &dat->ks1, sizeof(dat->ks1)); in des_ede_init_key()
[all …]
/src/crypto/openssl/crypto/rc4/asm/
H A Drc4-x86_64.pl130 $dat="%rdi"; # arg1
174 lea 8($dat),$dat
175 mov -8($dat),$XX[0]#b
176 mov -4($dat),$YY#b
177 cmpl \$-1,256($dat)
184 movl ($dat,$XX[0],4),$TX[0]#d
195 movl ($dat,$YY,4),$TY#d
196 movl $TX[0]#d,($dat,$YY,4)
197 movl $TY#d,($dat,$XX[0],4)
200 movl ($dat,$TX[0],4),$TY#d
[all …]
H A Drc4-md5-x86_64.pl72 my ($dat,$in0,$out,$ctx,$inp,$len, $func,$nargs);
75 ($dat,$len,$in0,$out) = ("%rdi","%rsi","%rdx","%rcx");
81 ($dat,$in0,$out,$ctx,$inp,$len) = ("%rdi","%rsi","%rdx","%rcx","%r8","%r9");
166 lea 8($dat),$dat
167 mov -8($dat),$XX[0]#b
168 mov -4($dat),$YY#b
172 movl ($dat,$XX[0],4),$TX[0]#d
184 movl ($dat,$YY,4),$TY#d
185 movl $TX[0]#d,($dat,$YY,4)
186 movl $TY#d,($dat,$XX[0],4)
[all …]
H A Drc4-586.pl81 $dat="edi";
88 &mov ($ty,&DWP(0,$dat,$yy,4));
89 &mov (&DWP(0,$dat,$yy,4),$tx);
90 &mov (&DWP(0,$dat,$xx,4),$ty);
96 &mov ($tx,&DWP(0,$dat,$xx,4));
100 &$func ($out,&DWP(0,$dat,$ty,4));
121 &mov ($ty,&DWP(0,$dat,$yy,4));
122 &mov (&DWP(0,$dat,$yy,4),$tx);
124 &mov (&DWP(0,$dat,$XX[0],4),$ty);
127 &mov ($tx,&DWP(0,$dat,@XX[1],4));
[all …]
/src/contrib/mandoc/
H A Dtbl_data.c46 struct tbl_dat *dat, *pdat; in getdata() local
95 dat = mandoc_malloc(sizeof(*dat)); in getdata()
96 dat->layout = cp; in getdata()
97 dat->next = NULL; in getdata()
98 dat->string = NULL; in getdata()
99 dat->hspans = 0; in getdata()
100 dat->vspans = 0; in getdata()
101 dat->block = 0; in getdata()
102 dat->pos = TBL_DATA_NONE; in getdata()
119 pdat->layout->col < dat->layout->col) in getdata()
[all …]
/src/sys/contrib/openzfs/tests/zfs-tests/tests/functional/cli_root/zpool_upgrade/
H A Dzpool_upgrade.cfg40 ZPOOL_VERSION_1_FILES="zfs-pool-v1.dat"
43 ZPOOL_VERSION_1stripe_FILES="zfs-pool-v1stripe1.dat \
44 zfs-pool-v1stripe2.dat zfs-pool-v1stripe3.dat"
47 ZPOOL_VERSION_1raidz_FILES="zfs-pool-v1raidz1.dat zfs-pool-v1raidz2.dat \
48 zfs-pool-v1raidz3.dat"
51 ZPOOL_VERSION_1mirror_FILES="zfs-pool-v1mirror1.dat zfs-pool-v1mirror2.dat \
52 zfs-pool-v1mirror3.dat"
56 ZPOOL_VERSION_2_FILES="zfs-pool-v2.dat"
59 ZPOOL_VERSION_2stripe_FILES="zfs-pool-v2stripe1.dat zfs-pool-v2stripe2.dat \
60 zfs-pool-v2stripe3.dat"
[all …]
/src/sys/contrib/openzfs/tests/zfs-tests/tests/functional/cli_user/misc/
H A Dsetup.ksh73 zfs send $TESTPOOL/$TESTFS@snap > $TEST_BASE_DIR/zfstest_datastream.dat
74 if [ ! -s $TEST_BASE_DIR/zfstest_datastream.dat ]
78 log_must chmod 644 $TEST_BASE_DIR/zfstest_datastream.dat
120 mkfile $MINVDEVSIZE $TEST_BASE_DIR/disk1.dat
121 mkfile $MINVDEVSIZE $TEST_BASE_DIR/disk2.dat
122 mkfile $MINVDEVSIZE $TEST_BASE_DIR/disk3.dat
123 mkfile $MINVDEVSIZE $TEST_BASE_DIR/disk-additional.dat
124 mkfile $MINVDEVSIZE $TEST_BASE_DIR/disk-export.dat
125 mkfile $MINVDEVSIZE $TEST_BASE_DIR/disk-offline.dat
126 mkfile $MINVDEVSIZE $TEST_BASE_DIR/disk-spare1.dat
[all …]
H A Dcleanup.ksh44 log_must rm -f $TEST_BASE_DIR/zfstest_datastream.dat
45 log_must rm -f $TEST_BASE_DIR/disk1.dat $TEST_BASE_DIR/disk2.dat \
46 $TEST_BASE_DIR/disk3.dat $TEST_BASE_DIR/disk-additional.dat \
47 $TEST_BASE_DIR/disk-export.dat $TEST_BASE_DIR/disk-offline.dat \
48 $TEST_BASE_DIR/disk-spare1.dat $TEST_BASE_DIR/disk-spare2.dat
49 log_must rm -f $TEST_BASE_DIR/zfs-pool-v1.dat \
50 $TEST_BASE_DIR/zfs-pool-v1.dat.bz2
/src/tests/sys/cddl/zfs/tests/cli_user/misc/
H A Dsetup.ksh66 $ZFS send $TESTPOOL/$TESTFS@snap > $TMPDIR/zfstest_datastream.dat
67 if [ ! -s $TMPDIR/zfstest_datastream.dat ]
71 log_must $CHMOD 644 $TMPDIR/zfstest_datastream.dat
123 /$TESTDIR/disk1.dat \
124 /$TESTDIR/disk2.dat \
125 /$TESTDIR/disk3.dat \
126 /$TESTDIR/disk-additional.dat \
127 /$TESTDIR/disk-export.dat \
128 /$TESTDIR/disk-offline.dat \
129 /$TESTDIR/disk-spare1.dat \
[all …]
/src/tests/sys/cddl/zfs/tests/cli_root/zpool_upgrade/
H A Dzpool_upgrade.cfg45 export ZPOOL_VERSION_1_FILES="zfs-pool-v1.dat"
48 export ZPOOL_VERSION_1stripe_FILES="zfs-pool-v1stripe1.dat \
49 zfs-pool-v1stripe2.dat zfs-pool-v1stripe3.dat"
52 export ZPOOL_VERSION_1raidz_FILES="zfs-pool-v1raidz1.dat zfs-pool-v1raidz2.dat \
53 zfs-pool-v1raidz3.dat"
56 export ZPOOL_VERSION_1mirror_FILES="zfs-pool-v1mirror1.dat \
57 zfs-pool-v1mirror2.dat zfs-pool-v1mirror3.dat"
62 export ZPOOL_VERSION_2_FILES="zfs-pool-v2.dat"
65 export ZPOOL_VERSION_2stripe_FILES="zfs-pool-v2stripe1.dat \
66 zfs-pool-v2stripe2.dat zfs-pool-v2stripe3.dat"
[all …]
/src/contrib/arm-optimized-routines/math/aarch64/advsimd/
H A Derf.c77 const struct data *dat = ptr_barrier (&data); in erf() local
82 uint64x2_t a_le_max = vcaleq_f64 (x, dat->max); in erf()
83 uint64x2_t a_gt_max = vcagtq_f64 (x, dat->max); in erf()
87 uint64x2_t cmp1 = vcgtq_f64 (a, dat->huge_bound); in erf()
88 uint64x2_t cmp2 = vcltq_f64 (a, dat->tiny_bound); in erf()
102 float64x2_t shift = dat->shift; in erf()
110 i = vbslq_u64 (a_le_max, i, dat->max_idx); in erf()
121 = vld1q_f64 (&dat->two_over_fifteen); in erf()
126 = vfmsq_f64 (dat->third, r2, vaddq_f64 (dat->third, dat->third)); in erf()
127 float64x2_t p3 = vmulq_f64 (r, vfmaq_f64 (v_f64 (-0.5), r2, dat->third)); in erf()
[all …]

1234567891011