Home
last modified time | relevance | path

Searched full:dat (Results 1 – 25 of 339) sorted by relevance

12345678910>>...14

/freebsd/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_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_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 …]
H A Dcipher_aes_hw_aesni.inc21 static int cipher_hw_aesni_initkey(PROV_CIPHER_CTX *dat,
25 PROV_AES_CTX *adat = (PROV_AES_CTX *)dat;
28 dat->ks = ks;
30 if ((dat->mode == EVP_CIPH_ECB_MODE || dat->mode == EVP_CIPH_CBC_MODE)
31 && !dat->enc) {
33 dat->block = (block128_f) aesni_decrypt;
34 dat->stream.cbc = dat->mode == EVP_CIPH_CBC_MODE ?
38 dat->block = (block128_f) aesni_encrypt;
39 if (dat->mode == EVP_CIPH_CBC_MODE)
40 dat->stream.cbc = (cbc128_f) aesni_cbc_encrypt;
[all …]
/freebsd/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 …]
/freebsd/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 …]
/freebsd/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 …]
/freebsd/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 …]
/freebsd/crypto/openssl/crypto/evp/
H A De_camellia.c55 EVP_CAMELLIA_KEY *dat = in cmll_t4_init_key() local
61 cmll_t4_set_key(key, bits, &dat->ks); in cmll_t4_init_key()
66 dat->block = (block128_f) cmll_t4_decrypt; in cmll_t4_init_key()
69 dat->stream.cbc = mode == EVP_CIPH_CBC_MODE ? in cmll_t4_init_key()
74 dat->stream.cbc = mode == EVP_CIPH_CBC_MODE ? in cmll_t4_init_key()
82 dat->block = (block128_f) cmll_t4_encrypt; in cmll_t4_init_key()
86 dat->stream.cbc = (cbc128_f) cmll128_t4_cbc_encrypt; in cmll_t4_init_key()
88 dat->stream.ctr = (ctr128_f) cmll128_t4_ctr32_encrypt; in cmll_t4_init_key()
90 dat->stream.cbc = NULL; in cmll_t4_init_key()
95 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()
228 DES_EDE_KEY *dat = data(ctx); in des_ede_init_key() local
230 dat->stream.cbc = NULL; in des_ede_init_key()
236 des_t4_key_expand(&deskey[0], &dat->ks1); in des_ede_init_key()
237 des_t4_key_expand(&deskey[1], &dat->ks2); in des_ede_init_key()
238 memcpy(&dat->ks3, &dat->ks1, sizeof(dat->ks1)); in des_ede_init_key()
[all …]
/freebsd/contrib/netbsd-tests/lib/libc/regex/
H A Dt_regex_att.c74 { "a[-]?c", "ac" }, // basic.dat in bug()
75 { "(a*)*", "a" }, // categorization.dat in bug()
76 { "(aba|a*b)*", "ababa" }, // categorization.dat in bug()
77 { "\\(a\\(b\\)*\\)*\\2", "abab" }, // categorization.dat in bug()
78 { "(a*)*", "aaaaaa" }, // nullsubexpression.dat in bug()
79 { "(a*)*", "aaaaaax" }, // nullsubexpression.dat in bug()
80 { "(a*)+", "a" }, // nullsubexpression.dat in bug()
81 { "(a*)+", "aaaaaa" }, // nullsubexpression.dat in bug()
82 { "(a*)+", "aaaaaax" }, // nullsubexpression.dat in bug()
83 { "([a]*)*", "a" }, // nullsubexpression.dat in bug()
[all …]
/freebsd/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 …]
/freebsd/crypto/openssl/crypto/chacha/asm/
H A Dchacha-c64xplus.pl36 @DAT=("A6", "A7", "B6", "B7", "A8", "A9", "B8", "B9",
39 # yes, overlaps with @DAT, used only in 2x interleave code path...
400 || LDNDW *${INP}++[8],@DAT[1]:@DAT[0]
405 || LDNDW *${INP}[-7],@DAT[3]:@DAT[2]
410 || LDNDW *${INP}[-6],@DAT[5]:@DAT[4]
415 || LDNDW *${INP}[-5],@DAT[7]:@DAT[6]
420 || LDNDW *${INP}[-4],@DAT[9]:@DAT[8]
425 || LDNDW *${INP}[-3],@DAT[11]:@DAT[10]
430 || LDNDW *${INP}[-2],@DAT[13]:@DAT[12]
433 || LDNDW *${INP}[-1],@DAT[15]:@DAT[14]
[all …]
/freebsd/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 …]
/freebsd/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
/freebsd/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 …]
/freebsd/contrib/arm-optimized-routines/math/aarch64/advsimd/
H A Derf.c77 const struct data *dat = ptr_barrier (&data); in V_NAME_D1() local
82 uint64x2_t a_le_max = vcaleq_f64 (x, dat->max); in V_NAME_D1()
83 uint64x2_t a_gt_max = vcagtq_f64 (x, dat->max); in V_NAME_D1()
87 uint64x2_t cmp1 = vcgtq_f64 (a, dat->huge_bound); in V_NAME_D1()
88 uint64x2_t cmp2 = vcltq_f64 (a, dat->tiny_bound); in V_NAME_D1()
102 float64x2_t shift = dat->shift; in V_NAME_D1()
110 i = vbslq_u64 (a_le_max, i, dat->max_idx); in V_NAME_D1()
121 = vld1q_f64 (&dat->two_over_fifteen); in V_NAME_D1()
126 = vfmsq_f64 (dat->third, r2, vaddq_f64 (dat->third, dat->third)); in V_NAME_D1()
127 float64x2_t p3 = vmulq_f64 (r, vfmaq_f64 (v_f64 (-0.5), r2, dat->third)); in V_NAME_D1()
[all …]
H A Derfc.c106 const struct data *dat = ptr_barrier (&data); in V_NAME_D1() local
115 vreinterpretq_s64_f64 (dat->uflow_bound)); in V_NAME_D1()
126 a = vminq_f64 (a, dat->max); in V_NAME_D1()
130 float64x2_t shift = dat->shift; in V_NAME_D1()
136 uint64x2_t i = vqaddq_u64 (vreinterpretq_u64_f64 (z), dat->offset); in V_NAME_D1()
147 float64x2_t p2 = vfmsq_f64 (dat->p20, r2, vaddq_f64 (dat->p20, dat->p20)); in V_NAME_D1()
148 float64x2_t p3 = vmulq_f64 (r, vfmaq_f64 (v_f64 (-0.5), r2, dat->p20)); in V_NAME_D1()
149 float64x2_t p42_p52 = vld1q_f64 (&dat->p42); in V_NAME_D1()
150 float64x2_t p4 = vfmaq_laneq_f64 (dat->p41, r2, p42_p52, 0); in V_NAME_D1()
151 p4 = vfmsq_f64 (dat->p40, r2, p4); in V_NAME_D1()
[all …]

12345678910>>...14