Home
last modified time | relevance | path

Searched refs:t3 (Results 1 – 25 of 275) sorted by relevance

1234567891011

/OK3568_Linux_fs/external/security/librkcrypto/test/c_mode/
H A Daes_core.c792 u32 s0, s1, s2, s3, t0, t1, t2, t3; in rk_aes_encrypt() local
813 t3 = Te0[s3 >> 24] ^ Te1[(s0 >> 16) & 0xff] ^ Te2[(s1 >> 8) & 0xff] ^ Te3[s2 & 0xff] ^ rk[ 7]; in rk_aes_encrypt()
815 s0 = Te0[t0 >> 24] ^ Te1[(t1 >> 16) & 0xff] ^ Te2[(t2 >> 8) & 0xff] ^ Te3[t3 & 0xff] ^ rk[ 8]; in rk_aes_encrypt()
816 s1 = Te0[t1 >> 24] ^ Te1[(t2 >> 16) & 0xff] ^ Te2[(t3 >> 8) & 0xff] ^ Te3[t0 & 0xff] ^ rk[ 9]; in rk_aes_encrypt()
817 s2 = Te0[t2 >> 24] ^ Te1[(t3 >> 16) & 0xff] ^ Te2[(t0 >> 8) & 0xff] ^ Te3[t1 & 0xff] ^ rk[10]; in rk_aes_encrypt()
818 s3 = Te0[t3 >> 24] ^ Te1[(t0 >> 16) & 0xff] ^ Te2[(t1 >> 8) & 0xff] ^ Te3[t2 & 0xff] ^ rk[11]; in rk_aes_encrypt()
823 t3 = Te0[s3 >> 24] ^ Te1[(s0 >> 16) & 0xff] ^ Te2[(s1 >> 8) & 0xff] ^ Te3[s2 & 0xff] ^ rk[15]; in rk_aes_encrypt()
825 s0 = Te0[t0 >> 24] ^ Te1[(t1 >> 16) & 0xff] ^ Te2[(t2 >> 8) & 0xff] ^ Te3[t3 & 0xff] ^ rk[16]; in rk_aes_encrypt()
826 s1 = Te0[t1 >> 24] ^ Te1[(t2 >> 16) & 0xff] ^ Te2[(t3 >> 8) & 0xff] ^ Te3[t0 & 0xff] ^ rk[17]; in rk_aes_encrypt()
827 s2 = Te0[t2 >> 24] ^ Te1[(t3 >> 16) & 0xff] ^ Te2[(t0 >> 8) & 0xff] ^ Te3[t1 & 0xff] ^ rk[18]; in rk_aes_encrypt()
[all …]
/OK3568_Linux_fs/kernel/drivers/net/wireless/rockchip_wlan/mvl88w8977/mlan/esa/common/
H A Drijndael.c880 u32 s0, s1, s2, s3, t0, t1, t2, t3; in rijndaelEncrypt() local
901 t3 = Te0[s3 >> 24] ^ Te1[(s0 >> 16) & 0xff] ^ Te2[(s1 >> 8) & 0xff] ^ in rijndaelEncrypt()
905 Te3[t3 & 0xff] ^ rk[8]; in rijndaelEncrypt()
906 s1 = Te0[t1 >> 24] ^ Te1[(t2 >> 16) & 0xff] ^ Te2[(t3 >> 8) & 0xff] ^ in rijndaelEncrypt()
908 s2 = Te0[t2 >> 24] ^ Te1[(t3 >> 16) & 0xff] ^ Te2[(t0 >> 8) & 0xff] ^ in rijndaelEncrypt()
910 s3 = Te0[t3 >> 24] ^ Te1[(t0 >> 16) & 0xff] ^ Te2[(t1 >> 8) & 0xff] ^ in rijndaelEncrypt()
919 t3 = Te0[s3 >> 24] ^ Te1[(s0 >> 16) & 0xff] ^ Te2[(s1 >> 8) & 0xff] ^ in rijndaelEncrypt()
923 Te3[t3 & 0xff] ^ rk[16]; in rijndaelEncrypt()
924 s1 = Te0[t1 >> 24] ^ Te1[(t2 >> 16) & 0xff] ^ Te2[(t3 >> 8) & 0xff] ^ in rijndaelEncrypt()
926 s2 = Te0[t2 >> 24] ^ Te1[(t3 >> 16) & 0xff] ^ Te2[(t0 >> 8) & 0xff] ^ in rijndaelEncrypt()
[all …]
/OK3568_Linux_fs/external/security/rk_tee_user/v2/ta/crypt/
H A Daes_impl.c848 u32 t3 = 0; in rijndaelEncrypt() local
868 t3 = Te0[s3 >> 24] ^ Te1[(s0 >> 16) & 0xff] ^ in rijndaelEncrypt()
872 Te2[(t2 >> 8) & 0xff] ^ Te3[t3 & 0xff] ^ rk[8]; in rijndaelEncrypt()
874 Te2[(t3 >> 8) & 0xff] ^ Te3[t0 & 0xff] ^ rk[9]; in rijndaelEncrypt()
875 s2 = Te0[t2 >> 24] ^ Te1[(t3 >> 16) & 0xff] ^ in rijndaelEncrypt()
877 s3 = Te0[t3 >> 24] ^ Te1[(t0 >> 16) & 0xff] ^ in rijndaelEncrypt()
886 t3 = Te0[s3 >> 24] ^ Te1[(s0 >> 16) & 0xff] ^ in rijndaelEncrypt()
890 Te2[(t2 >> 8) & 0xff] ^ Te3[t3 & 0xff] ^ rk[16]; in rijndaelEncrypt()
892 Te2[(t3 >> 8) & 0xff] ^ Te3[t0 & 0xff] ^ rk[17]; in rijndaelEncrypt()
893 s2 = Te0[t2 >> 24] ^ Te1[(t3 >> 16) & 0xff] ^ in rijndaelEncrypt()
[all …]
/OK3568_Linux_fs/kernel/lib/mpi/
H A Dmpi-inv.c33 MPI u, v, u1, u2 = NULL, u3, v1, v2 = NULL, v3, t1, t2 = NULL, t3; in mpi_invm() local
68 t3 = mpi_copy(v); in mpi_invm()
69 t3->sign = !t3->sign; in mpi_invm()
75 t3 = mpi_copy(u); in mpi_invm()
88 mpi_rshift(t3, t3, 1); in mpi_invm()
93 mpi_rshift(t3, t3, 1); in mpi_invm()
97 } while (!mpi_test_bit(t3, 0)); /* while t3 is even */ in mpi_invm()
99 if (!t3->sign) { in mpi_invm()
103 mpi_set(u3, t3); in mpi_invm()
110 sign = t3->sign; t3->sign = !t3->sign; in mpi_invm()
[all …]
/OK3568_Linux_fs/kernel/arch/arm/crypto/
H A Dsha512-armv4.pl76 $t3="r12";
104 ldr $t3,[sp,#$Hoff+4] @ h.hi
119 adc $Thi,$Thi,$t3 @ T += h
120 ldr $t3,[sp,#$Goff+4] @ g.hi
124 eor $t1,$t1,$t3
132 eor $t1,$t1,$t3 @ Ch(e,f,g)
133 ldr $t3,[$Ktbl,#$hi] @ K[i].hi
141 adc $Thi,$Thi,$t3 @ T += K[i]
147 ldr $t3,[sp,#$Coff+0] @ c.lo
174 and $Alo,$Alo,$t3
[all …]
H A Dsha256-armv4.pl53 $T1="r3"; $t3="r3";
130 and $t3,$t3,$t2 @ (b^c)&=(a^b)
132 eor $t3,$t3,$b @ Maj(a,b,c)
134 @ add $h,$h,$t3 @ h+=Maj(a,b,c)
136 ($t2,$t3)=($t3,$t2);
239 eor $t3,$B,$C @ magic
249 ldreq $t3,[sp,#16*4] @ pull ctx
253 ldr $t0,[$t3,#0]
254 ldr $t1,[$t3,#4]
255 ldr $t2,[$t3,#8]
[all …]
H A Daes-neonbs-core.S169 y0, y1, y2, y3, t0, t1, t2, t3 argument
172 mul_gf4 \x0, \x1, \y0, \y1, \t2, \t3
175 mul_gf4_n_gf4 \t0, \t1, \y0, \y1, \t3, \x2, \x3, \y2, \y3, \t2
182 mul_gf4_n_gf4 \t0, \t1, \y0, \y1, \t3, \x6, \x7, \y2, \y3, \t2
185 mul_gf4 \x4, \x5, \y0, \y1, \t2, \t3
193 t0, t1, t2, t3, s0, s1, s2, s3
194 veor \t3, \x4, \x6
199 veor \s3, \t3, \t0
201 vand \s2, \t3, \s0
202 vorr \t3, \t3, \s0
[all …]
/OK3568_Linux_fs/kernel/arch/alpha/lib/
H A Dev67-strrchr.S42 sll t5, 8, t3 # U : 00000000ch000000
46 or t5, t3, t3 # E : 00000000chch0000
51 or t2, t3, t2 # E : 0000chchchch0000
60 cmpbge zero, t2, t3 # E : bits set iff byte == c
62 andnot t3, t4, t3 # E : clear garbage from char test
68 cmovne t3, v0, t6 # E : save previous comparisons match
72 cmovne t3, t3, t8 # E : Latency=2, extra map slot
78 cmpbge zero, t2, t3 # E : bits set iff byte == c
89 and t3, t4, t3 # E : mask out char matches after null
90 cmovne t3, t3, t8 # E : save it, if match found Latency=2, extra map slot
[all …]
H A Dstrrchr.S38 cmpbge zero, t2, t3 # e0 : bits set iff byte == c
40 andnot t3, t4, t3 # e0 : clear garbage from char test
46 cmovne t3, v0, t6 # .. e1 : save previous comparisons match
47 cmovne t3, t3, t8 # e0 :
51 cmpbge zero, t2, t3 # e0 : bits set iff byte == c
61 and t3, t4, t3 # e0 : mask out char matches after null
62 cmovne t3, t3, t8 # .. e1 : save it, if match found
63 cmovne t3, v0, t6 # e0 :
H A Dstrchr.S36 cmpbge zero, t1, t3 # e0 : bits set iff byte == c
37 or t2, t3, t0 # e1 : bits set iff char match or zero match
46 cmpbge zero, t1, t3 # .. e1 : bits set iff byte == c
47 or t2, t3, t0 # e0 :
53 and t0, t3, t1 # e0 : bit set iff byte was the char
57 and t0, 0xcc, t3 # .. e1 :
60 cmovne t3, 2, t3 # e0 :
62 addq t2, t3, t2 # e0 :
H A Dev67-strchr.S33 and a1, 0xff, t3 # E : 00000000000000ch
37 insbl t3, 6, a3 # U : 00ch000000000000
38 or t5, t3, a1 # E : 000000000000chch
55 cmpbge zero, t1, t3 # E : bits set iff byte == c
56 or t2, t3, t0 # E : bits set iff char match or zero match
74 cmpbge zero, t1, t3 # E : bits set iff byte == c
75 or t2, t3, t0 # E :
76 cttz t3, a2 # U0 : speculative (in case we get a match)
81 and t0, t3, t1 # E : bit set iff byte was the char
/OK3568_Linux_fs/kernel/arch/mips/kernel/
H A Docteon_switch.S125 dmfc2 t3, 0x0082
132 sd t3, OCTEON_CP2_3DES_KEY+16(a0)
133 dmfc2 t3, 0x0103
140 sd t3, OCTEON_CP2_AES_IV+8(a0)
141 dmfc2 t3, 0x0107
148 sd t3, OCTEON_CP2_AES_KEY+24(a0)
161 dmfc2 t3, 0x0242
168 sd t3, OCTEON_CP2_HSH_DATW+16(a0)
169 dmfc2 t3, 0x0246
176 sd t3, OCTEON_CP2_HSH_DATW+48(a0)
[all …]
/OK3568_Linux_fs/kernel/arch/x86/crypto/
H A Dglue_helper-asm-avx2.S56 t1x, t2, t2x, t3, t3x, t4, t5) \ argument
66 vinserti128 $1, t2x, t3, t2; /* ab: le0 ; cd: le1 */ \
70 add2_le128(t2, t0, t4, t3, t5); /* ab: le2 ; cd: le3 */ \
72 add2_le128(t2, t0, t4, t3, t5); \
74 add2_le128(t2, t0, t4, t3, t5); \
76 add2_le128(t2, t0, t4, t3, t5); \
78 add2_le128(t2, t0, t4, t3, t5); \
80 add2_le128(t2, t0, t4, t3, t5); \
82 add2_le128(t2, t0, t4, t3, t5); \
119 tivx, t0, t0x, t1, t1x, t2, t2x, t3, \ argument
[all …]
/OK3568_Linux_fs/buildroot/dl/qt5location/git/src/3rdparty/mapbox-gl-native/deps/boost/1.65.1/include/boost/tuple/detail/
H A Dtuple_basic.hpp298 cons( T1& t1, T2& t2, T3& t3, T4& t4, T5& t5, in cons()
301 tail (t2, t3, t4, t5, t6, t7, t8, t9, t10, detail::cnull()) in cons()
306 cons( const null_type& /*t1*/, T2& t2, T3& t3, T4& t4, T5& t5, in cons()
309 tail (t2, t3, t4, t5, t6, t7, t8, t9, t10, detail::cnull()) in cons()
508 typename access_traits<T3>::parameter_type t3) in tuple() argument
509 : inherited(t0, t1, t2, t3, detail::cnull(), detail::cnull(), in tuple()
516 typename access_traits<T3>::parameter_type t3, in tuple() argument
518 : inherited(t0, t1, t2, t3, t4, detail::cnull(), detail::cnull(), in tuple()
524 typename access_traits<T3>::parameter_type t3, in tuple() argument
527 : inherited(t0, t1, t2, t3, t4, t5, detail::cnull(), detail::cnull(), in tuple()
[all …]
/OK3568_Linux_fs/kernel/arch/arm64/crypto/
H A Dsha512-armv8.pl104 ($t0,$t1,$t2,$t3)=map("$reg_t$_",(16,17,19,28));
153 and $t3,$t3,$t2 // (b^c)&=(a^b)
155 eor $t3,$t3,$b // Maj(a,b,c)
157 add $h,$h,$t3 // h+=Maj(a,b,c)
158 ldr $t3,[$Ktbl],#$SZ // *K++, $t2 in next round
177 and $t3,$t3,$t2 // (b^c)&=(a^b)
181 eor $t3,$t3,$b // Maj(a,b,c)
186 add $h,$h,$t3 // h+=Maj(a,b,c)
187 ldr $t3,[$Ktbl],#$SZ // *K++, $t2 in next round
192 ($t2,$t3)=($t3,$t2);
[all …]
H A Daes-neonbs-core.S114 y0, y1, y2, y3, t0, t1, t2, t3 argument
117 mul_gf4 \x0, \x1, \y0, \y1, \t2, \t3
120 mul_gf4_n_gf4 \t0, \t1, \y0, \y1, \t3, \x2, \x3, \y2, \y3, \t2
127 mul_gf4_n_gf4 \t0, \t1, \y0, \y1, \t3, \x6, \x7, \y2, \y3, \t2
130 mul_gf4 \x4, \x5, \y0, \y1, \t2, \t3
138 t0, t1, t2, t3, s0, s1, s2, s3
139 eor \t3, \x4, \x6
144 eor \s3, \t3, \t0
146 and \s2, \t3, \s0
147 orr \t3, \t3, \s0
[all …]
/OK3568_Linux_fs/kernel/arch/mips/lib/
H A Dcsum_partial.S28 #undef t3
32 #define t3 $11 macro
182 CSUM_BIGCHUNK1(src, 0x00, sum, t0, t1, t3, t4)
193 CSUM_BIGCHUNK(src, 0x00, sum, t0, t1, t3, t4)
194 CSUM_BIGCHUNK(src, 0x20, sum, t0, t1, t3, t4)
195 CSUM_BIGCHUNK(src, 0x40, sum, t0, t1, t3, t4)
196 CSUM_BIGCHUNK(src, 0x60, sum, t0, t1, t3, t4)
208 CSUM_BIGCHUNK(src, 0x00, sum, t0, t1, t3, t4)
209 CSUM_BIGCHUNK(src, 0x20, sum, t0, t1, t3, t4)
217 CSUM_BIGCHUNK(src, 0x00, sum, t0, t1, t3, t4)
[all …]
/OK3568_Linux_fs/prebuilts/gcc/linux-x86/aarch64/gcc-arm-10.3-2021.07-x86_64-aarch64-none-linux-gnu/aarch64-none-linux-gnu/include/c++/10.3.1/ext/pb_ds/
H A Dassoc_container.hpp129 basic_hash_table(T0 t0, T1 t1, T2 t2, T3 t3) in basic_hash_table() argument
130 : base_type(t0, t1, t2, t3) { } in basic_hash_table()
133 basic_hash_table(T0 t0, T1 t1, T2 t2, T3 t3, T4 t4) in basic_hash_table() argument
134 : base_type(t0, t1, t2, t3, t4) { } in basic_hash_table()
138 basic_hash_table(T0 t0, T1 t1, T2 t2, T3 t3, T4 t4, T5 t5) in basic_hash_table() argument
139 : base_type(t0, t1, t2, t3, t4, t5) { } in basic_hash_table()
143 basic_hash_table(T0 t0, T1 t1, T2 t2, T3 t3, T4 t4, T5 t5, T6 t6) in basic_hash_table() argument
144 : base_type(t0, t1, t2, t3, t4, t5, t6) { } in basic_hash_table()
148 basic_hash_table(T0 t0, T1 t1, T2 t2, T3 t3, T4 t4, T5 t5, T6 t6, T7 t7) in basic_hash_table() argument
149 : base_type(t0, t1, t2, t3, t4, t5, t6, t7) { } in basic_hash_table()
[all …]
/OK3568_Linux_fs/prebuilts/gcc/linux-x86/arm/gcc-arm-10.3-2021.07-x86_64-arm-none-linux-gnueabihf/arm-none-linux-gnueabihf/include/c++/10.3.1/ext/pb_ds/
H A Dassoc_container.hpp129 basic_hash_table(T0 t0, T1 t1, T2 t2, T3 t3) in basic_hash_table() argument
130 : base_type(t0, t1, t2, t3) { } in basic_hash_table()
133 basic_hash_table(T0 t0, T1 t1, T2 t2, T3 t3, T4 t4) in basic_hash_table() argument
134 : base_type(t0, t1, t2, t3, t4) { } in basic_hash_table()
138 basic_hash_table(T0 t0, T1 t1, T2 t2, T3 t3, T4 t4, T5 t5) in basic_hash_table() argument
139 : base_type(t0, t1, t2, t3, t4, t5) { } in basic_hash_table()
143 basic_hash_table(T0 t0, T1 t1, T2 t2, T3 t3, T4 t4, T5 t5, T6 t6) in basic_hash_table() argument
144 : base_type(t0, t1, t2, t3, t4, t5, t6) { } in basic_hash_table()
148 basic_hash_table(T0 t0, T1 t1, T2 t2, T3 t3, T4 t4, T5 t5, T6 t6, T7 t7) in basic_hash_table() argument
149 : base_type(t0, t1, t2, t3, t4, t5, t6, t7) { } in basic_hash_table()
[all …]
/OK3568_Linux_fs/kernel/arch/alpha/include/asm/
H A Dword-at-a-time.h42 unsigned long t1, t2, t3; in find_zero()
48 t3 = bits & 0xaa; in find_zero()
51 if (t3) t3 = 1; in find_zero()
52 return t1 + t2 + t3; in find_zero()
/OK3568_Linux_fs/u-boot/arch/mips/mach-ath79/ar933x/
H A Dlowlevel_init.S80 li t3, 0x03
92 addi t3, t3, -1
93 bnez t3, 1b
223 li t3, 100
228 bgt t4, t3, 0b
231 li t3, 5
267 addi t3, t3, -1
268 bnez t3, 3b
/OK3568_Linux_fs/kernel/arch/mips/cavium-octeon/
H A Docteon-memcpy.S108 #undef t3
112 #define t3 $11 macro
188 EXC( LOAD t3, UNIT(3)(src), l_exc_copy)
193 EXC( STORE t3, UNIT(3)(dst), s_exc_p13u)
197 EXC( LOAD t3, UNIT(7)(src), l_exc_copy)
202 EXC( STORE t3, UNIT(7)(dst), s_exc_p9u)
207 EXC( LOAD t3, UNIT(-5)(src), l_exc_copy_rewind16)
211 EXC( STORE t3, UNIT(-5)(dst), s_exc_p5u)
215 EXC( LOAD t3, UNIT(-1)(src), l_exc_copy_rewind16)
219 EXC( STORE t3, UNIT(-1)(dst), s_exc_p1u)
[all …]
/OK3568_Linux_fs/kernel/tools/perf/tests/
H A Dthread-maps-share.c14 struct thread *t1, *t2, *t3; in test__thread_maps_share() local
37 t3 = machine__findnew_thread(machine, 0, 3); in test__thread_maps_share()
43 leader && t1 && t2 && t3 && other); in test__thread_maps_share()
51 TEST_ASSERT_VAL("maps don't match", maps == t3->maps); in test__thread_maps_share()
69 machine__remove_thread(machine, t3); in test__thread_maps_share()
88 thread__put(t3); in test__thread_maps_share()
/OK3568_Linux_fs/kernel/arch/mips/netlogic/common/
H A Dsmpboot.S110 li t3, CKSEG1ADDR(RESET_DATA_PHYS)
111 ADDIU t1, t3, BOOT_CPU_READY
113 li t3, 1
114 sw t3, 0(t1)
125 nor t3, t2, zero
133 and t2, t1, t3 /* mask out old thread mode */
/OK3568_Linux_fs/external/rknpu2/examples/3rdparty/opencv/opencv-linux-aarch64/include/opencv2/core/cuda/
H A Dreduce.hpp153 smem_tuple(T0* t0, T1* t1, T2* t2, T3* t3) in smem_tuple() argument
155 …urn thrust::make_tuple((volatile T0*) t0, (volatile T1*) t1, (volatile T2*) t2, (volatile T3*) t3); in smem_tuple()
161 smem_tuple(T0* t0, T1* t1, T2* t2, T3* t3, T4* t4) in smem_tuple() argument
163 …ple((volatile T0*) t0, (volatile T1*) t1, (volatile T2*) t2, (volatile T3*) t3, (volatile T4*) t4); in smem_tuple()
169 smem_tuple(T0* t0, T1* t1, T2* t2, T3* t3, T4* t4, T5* t5) in smem_tuple() argument
171 …le((volatile T0*) t0, (volatile T1*) t1, (volatile T2*) t2, (volatile T3*) t3, (volatile T4*) t4, … in smem_tuple()
177 smem_tuple(T0* t0, T1* t1, T2* t2, T3* t3, T4* t4, T5* t5, T6* t6) in smem_tuple() argument
179 …le((volatile T0*) t0, (volatile T1*) t1, (volatile T2*) t2, (volatile T3*) t3, (volatile T4*) t4, … in smem_tuple()
185 smem_tuple(T0* t0, T1* t1, T2* t2, T3* t3, T4* t4, T5* t5, T6* t6, T7* t7) in smem_tuple() argument
187 …le((volatile T0*) t0, (volatile T1*) t1, (volatile T2*) t2, (volatile T3*) t3, (volatile T4*) t4, … in smem_tuple()
[all …]

1234567891011