Home
last modified time | relevance | path

Searched +full:4 +full:s (Results 1 – 25 of 2457) sorted by relevance

12345678910>>...99

/freebsd/sys/crypto/openssl/aarch64/
H A Dsm3-armv8.S21 ld1 {v5.4s,v6.4s}, [x0]
22 rev64 v5.4s, v5.4s
23 rev64 v6.4s, v6.4s
32 ld1 {v0.4s,v1.4s,v2.4s,v3.4s}, [x1], #64
45 ext v20.16b, v16.16b, v16.16b, #4
52 .inst 0xce63c004 //sm3partw1 v4.4s, v0.4s, v3.4s
53 .inst 0xce76c6e4 //sm3partw2 v4.4s, v23.4s, v22.4s
55 .inst 0xce5418b7 //sm3ss1 v23.4s, v5.4s, v20.4s, v6.4s
56 shl v21.4s, v20.4s, #1
57 sri v21.4s, v20.4s, #31
[all …]
H A Dsm4-armv8.S43 ld1 {v0.4s},[x0]
46 ld1 {v24.4s},[x2]
49 ld1 {v16.4s,v17.4s,v18.4s,v19.4s},[x2],64
53 ld1 {v20.4s,v21.4s,v22.4s,v23.4s},[x2]
55 .inst 0xce70c800 //sm4ekey v0.4S,v0.4S,v16.4S
56 .inst 0xce71c801 //sm4ekey v1.4S,v0.4S,v17.4S
57 .inst 0xce72c822 //sm4ekey v2.4S,v1.4S,v18.4S
58 .inst 0xce73c843 //sm4ekey v3.4S,v2.4S,v19.4S
59 .inst 0xce74c864 //sm4ekey v4.4S,v3.4S,v20.4S
60 st1 {v0.4s,v1.4s,v2.4s,v3.4s},[x1],64
[all …]
H A Dchacha-armv8.S16 .long 1,2,3,4
256 .align 4
372 ld1 {v0.4s},[x5],#16
375 ld1 {v1.4s,v2.4s},[x3]
377 ld1 {v3.4s},[x4]
379 ld1 {v8.4s,v9.4s},[x5]
381 rev64 v0.4s,v0.4s
391 dup v16.4s,v0.s[0] // unpack key block
393 dup v20.4s,v0.s[1]
395 dup v24.4s,v0.s[2]
[all …]
H A Dvpsm4_ex-armv8.S49 .align 4
52 ld1 {v5.4s},[x0]
77 mov w7,v5.s[1]
78 ldr w8,[x5],#4
80 mov w7,v5.s[2]
82 mov w7,v5.s[3]
85 mov v4.s[0],w8
87 ushr v2.16b, v0.16b, 4
94 ushr v2.16b, v0.16b, 4
99 mov w7,v0.s[0]
[all …]
H A Dvpsm4-armv8.S63 .align 4
66 ld1 {v5.4s},[x0]
90 mov w7,v5.s[1]
91 ldr w8,[x5],#4
93 mov w7,v5.s[2]
95 mov w7,v5.s[3]
98 mov v4.s[0],w8
106 mov w7,v1.s[0]
109 mov w7,v5.s[0]
111 mov v5.s[0],w8
[all …]
H A Dsha256-armv8.S35 // (**) The result is a trade-off: it's possible to improve it by
37 // on Cortex-A53 (or by 4 cycles per round).
89 sub sp,sp,#4*4
92 ldp w22,w23,[x0,#2*4]
93 ldp w24,w25,[x0,#4*4]
95 ldp w26,w27,[x0,#6*4]
101 ldp w3,w4,[x1],#2*4
102 ldr w19,[x30],#4 // *K++
126 ldr w28,[x30],#4 // *K++, w19 in next round
131 ldp w5,w6,[x1],#2*4
[all …]
H A Darmv8-mont.S69 // by adding -1 to x6. That's what next instruction does.
243 .align 4
248 sub x7,x7,x5,lsl#4
269 ld1 {v0.4s,v1.4s},[x1],#32
271 ldr s30,[x4],#4
275 .align 4
277 ldr s28,[x2],#4 // *b++
278 uxtl v28.4s,v28.4h
280 ld1 {v2.4s,v3.4s},[x3],#32
282 umlal v6.2d,v28.2s,v0.s[0]
[all …]
H A Dpoly1305-armv8.S38 and x9,x9,#-4
119 and x10,x14,#-4 // final reduction
150 tst x14,#-4 // see if it's carried/borrowed
196 and x10,x14,#-4 // final reduction
223 str w13,[x0,#16*4] // s2
277 and x10,x14,#-4 // ... so reduce
311 .align 4
317 .align 4
368 sub x0,x0,#4
372 sub x0,x0,#4
[all …]
/freebsd/sys/contrib/openzfs/module/icp/asm-aarch64/blake3/
H A Db3_aarch64_sse2.S47 .word 4
52 .word 4
95 .p2align 4
110 mov v1.s[1], w5
120 uzp1 v1.4s, v0.4s, v6.4s
121 uzp2 v0.4s, v0.4s, v6.4s
122 add v2.4s, v2.4s, v1.4s
123 uzp1 v18.4s, v1.4s, v1.4s
124 add v2.4s, v2.4s, v5.4s
126 add v2.4s, v2.4s, v0.4s
[all …]
H A Db3_aarch64_sse41.S47 .word 4
52 .word 4
95 .p2align 4
106 .byte 4
124 .byte 4
143 mov v1.s[1], w5
154 uzp1 v3.4s, v6.4s, v7.4s
155 add v0.4s, v2.4s, v3.4s
156 uzp2 v2.4s, v6.4s, v7.4s
157 add v16.4s, v0.4s, v5.4s
[all …]
/freebsd/crypto/openssl/crypto/sm4/asm/
H A Dsm4-armv8.pl44 sm4e $data.4s,@rks[0].4s
45 sm4e $data.4s,@rks[1].4s
46 sm4e $data.4s,@rks[2].4s
47 sm4e $data.4s,@rks[3].4s
48 sm4e $data.4s,@rks[4].4s
49 sm4e $data.4s,@rks[5].4s
50 sm4e $data.4s,@rks[6].4s
51 sm4e $data.4s,@rks[7].4s
52 rev64 $data.4S,$data.4S
63 sm4e $data0.4s,@rks[0].4s
[all …]
H A Dvpsm4_ex-armv8.pl32 my @data=map("v$_",(4..7));
117 zip1 $vt0.4s,$dat0.4s,$dat1.4s
118 zip2 $vt1.4s,$dat0.4s,$dat1.4s
119 zip1 $vt2.4s,$dat2.4s,$dat3.4s
120 zip2 $vt3.4s,$dat2.4s,$dat3.4s
135 ushr $tmp.16b, $x.16b, 4
143 # sbox operations for 4-lane of words
144 # sbox operation for 4-lane of words
162 ushr @vtmp[0].4s,$dat.4s,32-2
163 ushr @vtmp[1].4s,$dat.4s,32-10
[all …]
H A Dvpsm4-armv8.pl32 my @data=map("v$_",(4..7));
114 zip1 $vt0.4s,$dat0.4s,$dat1.4s
115 zip2 $vt1.4s,$dat0.4s,$dat1.4s
116 zip1 $vt2.4s,$dat2.4s,$dat3.4s
117 zip2 $vt3.4s,$dat2.4s,$dat3.4s
125 # sbox operations for 4-lane of words
137 tbl @vtmp[0].16b,{@sbox[4].16b,@sbox[5].16b,@sbox[6].16b,@sbox[7].16b},@vtmp[0].16b
144 ushr @vtmp[0].4s,$dat.4s,32-2
145 sli @vtmp[0].4s,$dat.4s,2
146 ushr @vtmp[2].4s,$dat.4s,32-10
[all …]
/freebsd/lib/libmd/aarch64/
H A Dsha1block.S141 ldp w_0, w_1, [buf, #0*4]
145 ldp w_2, w_3, [buf, #2*4]
149 ldp w_4, w_5, [buf, #4*4]
153 ldp w_6, w_7, [buf, #6*4]
157 ldp w_8, w_9, [buf, #8*4]
161 ldp w_10, w_11, [buf, #10*4]
165 ldp w_12, w_13, [buf, #12*4]
169 ldp w_14, w_15, [buf, #14*4]
232 movz k, #0xc1d6 // round constant 4
324 ld4r {k0.4s, k1.4s, k2.4s, k3.4s}, [kaddr]
[all …]
/freebsd/sys/dev/ath/ath_rate/sample/
H A Dtx_schedules.h45 (((_r) == 18) ? 3 : (((_r) == 24) ? 4 : (((_r) == 36) ? 5 : \
48 { 3,A( 6), 3,A( 6), 0,A( 6), 0,A( 6) }, /* 6Mb/s */
49 { 4,A( 9), 3,A( 6), 4,A( 6), 0,A( 6) }, /* 9Mb/s */
50 { 4,A(12), 3,A( 6), 4,A( 6), 0,A( 6) }, /* 12Mb/s */
51 { 4,A(18), 3,A( 12), 4,A( 6), 2,A( 6) }, /* 18Mb/s */
52 { 4,A(24), 3,A( 18), 4,A( 12), 2,A( 6) }, /* 24Mb/s */
53 { 4,A(36), 3,A( 24), 4,A( 18), 2,A( 6) }, /* 36Mb/s */
54 { 4,A(48), 3,A( 36), 4,A( 24), 2,A(12) }, /* 48Mb/s */
55 { 4,A(54), 3,A( 48), 4,A( 36), 2,A(24) } /* 54Mb/s */
71 { 3,A( 6), 3,A( 6), 0,A( 6), 0,A( 6) }, /* 6Mb/s */
[all …]
/freebsd/sys/contrib/openzfs/module/icp/asm-aarch64/sha2/
H A Dsha256-armv8.S27 .word 4
32 .word 4
72 sub sp,sp,#4*4
75 ldp w22,w23,[x0,#2*4]
76 ldp w24,w25,[x0,#4*4]
78 ldp w26,w27,[x0,#6*4]
83 ldp w3,w4,[x1],#2*4
84 ldr w19,[x30],#4 // *K++
108 ldr w28,[x30],#4 // *K++, w19 in next round
113 ldp w5,w6,[x1],#2*4
[all …]
/freebsd/secure/lib/libcrypto/man/man7/
H A DOSSL_PROVIDER-default.729 .\" Escape single quotes in literal strings from groff's Unicode transform.
58 .TH OSSL_PROVIDER-DEFAULT 7ossl 2025-09-30 3.5.4 OpenSSL
67 The OpenSSL default provider supplies the majority of OpenSSL's diverse
85 .IP """provider=default""" 4
103 .IP "SHA1, see \fBEVP_MD\-SHA1\fR\|(7)" 4
106 .IP "SHA2, see \fBEVP_MD\-SHA2\fR\|(7)" 4
108 .IP "SHA3, see \fBEVP_MD\-SHA3\fR\|(7)" 4
110 .IP "KECCAK, see \fBEVP_MD\-KECCAK\fR\|(7)" 4
112 .IP "KECCAK-KMAC, see \fBEVP_MD\-KECCAK\-KMAC\fR\|(7)" 4
114 .IP "SHAKE, see \fBEVP_MD\-SHAKE\fR\|(7)" 4
[all …]
H A DOSSL_PROVIDER-base.729 .\" Escape single quotes in literal strings from groff's Unicode transform.
58 .TH OSSL_PROVIDER-BASE 7ossl 2025-09-30 3.5.4 OpenSSL
67 The OpenSSL base provider supplies the encoding for OpenSSL's
73 .IP """provider=base""" 4
80 .IP """type=parameters""" 4
83 .IP """type=private""" 4
85 .IP """type=public""" 4
92 .IP """format=der""" 4
95 .IP """format=pem""" 4
97 .IP """format=text""" 4
[all …]
/freebsd/contrib/llvm-project/llvm/lib/Target/AArch64/
H A DAArch64SchedA53.td57 // ALU - Despite having a full latency of 4, most of the ALU instructions can
69 def : WriteRes<WriteIM32, [A53UnitMAC]> { let Latency = 4; }
70 def : WriteRes<WriteIM64, [A53UnitMAC]> { let Latency = 4; }
73 def : WriteRes<WriteID32, [A53UnitDiv]> { let Latency = 4; }
74 def : WriteRes<WriteID64, [A53UnitDiv]> { let Latency = 4; }
77 def : WriteRes<WriteLD, [A53UnitLdSt]> { let Latency = 4; }
78 def : WriteRes<WriteLDIdx, [A53UnitLdSt]> { let Latency = 4; }
79 def : WriteRes<WriteLDHi, [A53UnitLdSt]> { let Latency = 4; }
87 def A53WriteVLD1 : SchedWriteRes<[A53UnitLdSt]> { let Latency = 4; }
93 let ReleaseAtCycles = [4]; }
[all...]
H A DAArch64SchedThunderX.td61 let Latency = 4;
66 let Latency = 4;
274 def : InstRW<[THXT8XWriteVLD1], (instregex "LD1Rv(8b|4h|2s|1d|16b|8h|4s|2d)$")>;
275 def : InstRW<[THXT8XWriteVLD1], (instregex "LD1Onev(8b|4h|2s|1d|16b|8h|4s|
[all...]
H A DAArch64SchedA55.td24 let LoadLatency = 4; // Cycles for loads to access the cache. The
26 // a latency of 3, but some have a latency of 4
27 // or 5. Setting it 4 looked to be good trade-off.
52 // instructions, which can mostly be dual-issued; that's why for now we model
74 def : WriteRes<WriteIM32, [CortexA55UnitMAC]> { let Latency = 4; } // 32-bit Multiply
75 def : WriteRes<WriteIM64, [CortexA55UnitMAC]> { let Latency = 4; } // 64-bit Multiply
87 def : WriteRes<WriteLDIdx, [CortexA55UnitLd]> { let Latency = 4; }
95 def CortexA55WriteVLD1 : SchedWriteRes<[CortexA55UnitLd]> { let Latency = 4; }
96 def CortexA55WriteVLD1SI : SchedWriteRes<[CortexA55UnitLd]> { let Latency = 4; let SingleIssue = 1; }
102 let ReleaseAtCycles = [4]; }
[all...]
/freebsd/sys/crypto/sha2/
H A Dsha512c_arm64.c41 uint64x2_t S[4]; in SHA512_Transform_arm64_impl() local
42 uint64x2_t S_start[4]; in SHA512_Transform_arm64_impl()
55 A64_LOAD_W(4); in SHA512_Transform_arm64_impl()
61 S[0] = vld1q_u64(&state[0]); in SHA512_Transform_arm64_impl()
62 S[1] = vld1q_u64(&state[2]); in SHA512_Transform_arm64_impl()
63 S[2] = vld1q_u64(&state[4]); in SHA512_Transform_arm64_impl()
64 S[3] = vld1q_u64(&state[6]); in SHA512_Transform_arm64_impl()
66 S_start[0] = S[0]; in SHA512_Transform_arm64_impl()
67 S_start[1] = S[1]; in SHA512_Transform_arm64_impl()
68 S_start[2] = S[2]; in SHA512_Transform_arm64_impl()
[all …]
/freebsd/usr.bin/rs/tests/
H A Drs_test.sh36 atf_check -s exit:0 -o inline:"1 2 3 4
39 1,2,3,4,5,6,7,8
46 atf_set "descr" "Verify the usage of option 's'"
51 atf_check -s exit:0 -o inline:"1 2 3 4
53 " rs -s% 2 <<EOF
54 1%%2%%3%4%5%%%6%%%7%8
67 atf_check -s exit:0 -o inline:"1,2,3,4,
70 1 2 3 4 5 6 7 8
77 atf_set "descr" "Verify the usage of option 'S'"
82 atf_check -s exit:0 -o inline:"1,,2,,3,,4
[all …]
/freebsd/crypto/openssl/test/recipes/04-test_pem_reading_data/
H A Ddsa-onecolumn.pem2 Proc-Type: 4,ENCRYPTED
19 s
33 4
65 s
73 s
89 4
124 S
135 s
167 4
196 S
[all …]
/freebsd/crypto/openssl/crypto/bn/asm/
H A Dvia-mont.pl21 # Below are interleaved outputs from 'openssl speed rsa dsa' for 4
31 # sign verify sign/s verify/s
32 # rsa 512 bits 0.001720s 0.000140s 581.4 7149.7 software integer
33 # rsa 512 bits 0.000690s 0.000086s 1450.3 11606.0 software SSE2
34 # rsa 512 bits 0.006136s 0.000201s 163.0 4974.5 hardware VIA SDK
35 # rsa 512 bits 0.000712s 0.000050s 1404.9 19858.5 hardware this
37 # rsa 1024 bits 0.008518s 0.000413s 117.4 2420.8 software integer
38 # rsa 1024 bits 0.004275s 0.000277s 233.9 3609.7 software SSE2
39 # rsa 1024 bits 0.012136s 0.000260s 82.4 3844.5 hardware VIA SDK
40 # rsa 1024 bits 0.002522s 0.000116s 396.5 8650.9 hardware this
[all …]

12345678910>>...99