Home
last modified time | relevance | path

Searched refs:v2 (Results 1 - 25 of 496) sorted by relevance

12345678910>>...20

/kernel/linux/linux-5.10/arch/loongarch/lib/
H A Dxor_template.c17 unsigned long *v1, unsigned long *v2)
24 LD_AND_XOR_LINE(v2)
26 : : [v1] "r"(v1), [v2] "r"(v2) : "memory"
30 v2 += LINE_WIDTH / sizeof(unsigned long);
35 unsigned long *v1, unsigned long *v2, variable
43 LD_AND_XOR_LINE(v2)
46 : : [v1] "r"(v1), [v2] "r"(v2), [v3] "r"(v3) : "memory"
50 v2
56 unsigned long *v1, unsigned long *v2, global() variable
80 unsigned long *v1, unsigned long *v2, global() variable
[all...]
/kernel/linux/linux-6.6/arch/loongarch/lib/
H A Dxor_template.c18 const unsigned long * __restrict v2)
25 LD_AND_XOR_LINE(v2)
27 : : [v1] "r"(v1), [v2] "r"(v2) : "memory"
31 v2 += LINE_WIDTH / sizeof(unsigned long);
37 const unsigned long * __restrict v2, variable
45 LD_AND_XOR_LINE(v2)
48 : : [v1] "r"(v1), [v2] "r"(v2), [v3] "r"(v3) : "memory"
52 v2
59 const unsigned long * __restrict v2, global() variable
85 const unsigned long * __restrict v2, global() variable
[all...]
/kernel/linux/linux-6.6/net/ceph/
H A Dmessenger_v2.c114 iov_iter_is_discard(&con->v2.in_iter) ? "discard" : "need", in ceph_tcp_recv()
115 iov_iter_count(&con->v2.in_iter)); in ceph_tcp_recv()
116 ret = do_recvmsg(con->sock, &con->v2.in_iter); in ceph_tcp_recv()
118 iov_iter_count(&con->v2.in_iter)); in ceph_tcp_recv()
201 iov_iter_count(&con->v2.out_iter), con->v2.out_iter_sendpage); in ceph_tcp_send()
202 if (con->v2.out_iter_sendpage) in ceph_tcp_send()
203 ret = do_try_sendpage(con->sock, &con->v2.out_iter); in ceph_tcp_send()
205 ret = do_sendmsg(con->sock, &con->v2.out_iter); in ceph_tcp_send()
207 iov_iter_count(&con->v2 in ceph_tcp_send()
[all...]
/kernel/linux/linux-5.10/arch/s390/crypto/
H A Dcrc32le-vx.S132 VPERM %v2,%v2,%v2,CONST_PERM_LE2BE
159 VGFMAG %v2,CONST_R2R1,%v2,%v6
175 VGFMAG %v1,CONST_R4R3,%v1,%v2
184 VL %v2,0,,%r3 /* Load next data chunk */
185 VPERM %v2,%v2,%v2,CONST_PERM_LE2B
[all...]
H A Dcrc32be-vx.S124 VGFMAG %v2,CONST_R1R2,%v2,%v6
137 VGFMAG %v1,CONST_R3R4,%v1,%v2
147 VL %v2,0,,%r3 /* Load next data chunk */
148 VGFMAG %v1,CONST_R3R4,%v1,%v2 /* Fold next data chunk */
196 VUPLLF %v2,%v1
197 VGFMG %v2,CONST_RU_POLY,%v2
204 VUPLLF %v2,%v2
[all...]
/kernel/linux/linux-6.6/arch/s390/crypto/
H A Dcrc32le-vx.S134 VPERM %v2,%v2,%v2,CONST_PERM_LE2BE
161 VGFMAG %v2,CONST_R2R1,%v2,%v6
177 VGFMAG %v1,CONST_R4R3,%v1,%v2
186 VL %v2,0,,%r3 /* Load next data chunk */
187 VPERM %v2,%v2,%v2,CONST_PERM_LE2B
[all...]
H A Dcrc32be-vx.S125 VGFMAG %v2,CONST_R1R2,%v2,%v6
138 VGFMAG %v1,CONST_R3R4,%v1,%v2
148 VL %v2,0,,%r3 /* Load next data chunk */
149 VGFMAG %v1,CONST_R3R4,%v1,%v2 /* Fold next data chunk */
197 VUPLLF %v2,%v1
198 VGFMG %v2,CONST_RU_POLY,%v2
205 VUPLLF %v2,%v2
[all...]
/kernel/linux/linux-5.10/include/pcmcia/
H A Ddevice_id.h29 #define PCMCIA_DEVICE_PROD_ID2(v2, vh2) { \
31 .prod_id = { NULL, (v2), NULL, NULL }, \
39 #define PCMCIA_DEVICE_PROD_ID12(v1, v2, vh1, vh2) { \
42 .prod_id = { (v1), (v2), NULL, NULL }, \
57 #define PCMCIA_DEVICE_PROD_ID123(v1, v2, v3, vh1, vh2, vh3) { \
61 .prod_id = { (v1), (v2), (v3), NULL },\
64 #define PCMCIA_DEVICE_PROD_ID124(v1, v2, v4, vh1, vh2, vh4) { \
68 .prod_id = { (v1), (v2), NULL, (v4) }, \
78 #define PCMCIA_DEVICE_PROD_ID1234(v1, v2, v3, v4, vh1, vh2, vh3, vh4) { \
83 .prod_id = { (v1), (v2), (v
[all...]
/kernel/linux/linux-6.6/include/pcmcia/
H A Ddevice_id.h29 #define PCMCIA_DEVICE_PROD_ID2(v2, vh2) { \
31 .prod_id = { NULL, (v2), NULL, NULL }, \
39 #define PCMCIA_DEVICE_PROD_ID12(v1, v2, vh1, vh2) { \
42 .prod_id = { (v1), (v2), NULL, NULL }, \
57 #define PCMCIA_DEVICE_PROD_ID123(v1, v2, v3, vh1, vh2, vh3) { \
61 .prod_id = { (v1), (v2), (v3), NULL },\
64 #define PCMCIA_DEVICE_PROD_ID124(v1, v2, v4, vh1, vh2, vh4) { \
68 .prod_id = { (v1), (v2), NULL, (v4) }, \
78 #define PCMCIA_DEVICE_PROD_ID1234(v1, v2, v3, v4, vh1, vh2, vh3, vh4) { \
83 .prod_id = { (v1), (v2), (v
[all...]
/kernel/linux/linux-5.10/drivers/char/mwave/
H A Dmwavedd.h84 #define PRINTK_3(f,s,v1,v2) \
86 printk(s,v1,v2); \
89 #define PRINTK_4(f,s,v1,v2,v3) \
91 printk(s,v1,v2,v3); \
94 #define PRINTK_5(f,s,v1,v2,v3,v4) \
96 printk(s,v1,v2,v3,v4); \
99 #define PRINTK_6(f,s,v1,v2,v3,v4,v5) \
101 printk(s,v1,v2,v3,v4,v5); \
104 #define PRINTK_7(f,s,v1,v2,v3,v4,v5,v6) \
106 printk(s,v1,v2,v
[all...]
/kernel/linux/linux-6.6/drivers/char/mwave/
H A Dmwavedd.h84 #define PRINTK_3(f,s,v1,v2) \
86 printk(s,v1,v2); \
89 #define PRINTK_4(f,s,v1,v2,v3) \
91 printk(s,v1,v2,v3); \
94 #define PRINTK_5(f,s,v1,v2,v3,v4) \
96 printk(s,v1,v2,v3,v4); \
99 #define PRINTK_6(f,s,v1,v2,v3,v4,v5) \
101 printk(s,v1,v2,v3,v4,v5); \
104 #define PRINTK_7(f,s,v1,v2,v3,v4,v5,v6) \
106 printk(s,v1,v2,v
[all...]
/kernel/linux/linux-5.10/arch/arm64/lib/
H A Dxor-neon.c19 register uint64x2_t v0, v1, v2, v3; in xor_arm64_neon_2() local
26 v2 = veorq_u64(vld1q_u64(dp1 + 4), vld1q_u64(dp2 + 4)); in xor_arm64_neon_2()
32 vst1q_u64(dp1 + 4, v2); in xor_arm64_neon_2()
47 register uint64x2_t v0, v1, v2, v3; in xor_arm64_neon_3() local
54 v2 = veorq_u64(vld1q_u64(dp1 + 4), vld1q_u64(dp2 + 4)); in xor_arm64_neon_3()
60 v2 = veorq_u64(v2, vld1q_u64(dp3 + 4)); in xor_arm64_neon_3()
66 vst1q_u64(dp1 + 4, v2); in xor_arm64_neon_3()
83 register uint64x2_t v0, v1, v2, v3; in xor_arm64_neon_4() local
90 v2 in xor_arm64_neon_4()
128 register uint64x2_t v0, v1, v2, v3; xor_arm64_neon_5() local
[all...]
/kernel/linux/linux-5.10/arch/powerpc/lib/
H A Dxor_vmx.c56 DEFINE(v2); in __xor_altivec_2()
61 LOAD(v2); in __xor_altivec_2()
62 XOR(v1, v2); in __xor_altivec_2()
66 v2 += 4; in __xor_altivec_2()
74 DEFINE(v2); in __xor_altivec_3()
80 LOAD(v2); in __xor_altivec_3()
82 XOR(v1, v2); in __xor_altivec_3()
87 v2 += 4; in __xor_altivec_3()
97 DEFINE(v2); in __xor_altivec_4()
104 LOAD(v2); in __xor_altivec_4()
[all...]
/kernel/linux/linux-6.6/arch/powerpc/lib/
H A Dxor_vmx.c57 DEFINE(v2); in __xor_altivec_2()
62 LOAD(v2); in __xor_altivec_2()
63 XOR(v1, v2); in __xor_altivec_2()
67 v2 += 4; in __xor_altivec_2()
77 DEFINE(v2); in __xor_altivec_3()
83 LOAD(v2); in __xor_altivec_3()
85 XOR(v1, v2); in __xor_altivec_3()
90 v2 += 4; in __xor_altivec_3()
102 DEFINE(v2); in __xor_altivec_4()
109 LOAD(v2); in __xor_altivec_4()
[all...]
/kernel/linux/linux-6.6/arch/arm64/lib/
H A Dxor-neon.c19 register uint64x2_t v0, v1, v2, v3; in xor_arm64_neon_2() local
26 v2 = veorq_u64(vld1q_u64(dp1 + 4), vld1q_u64(dp2 + 4)); in xor_arm64_neon_2()
32 vst1q_u64(dp1 + 4, v2); in xor_arm64_neon_2()
48 register uint64x2_t v0, v1, v2, v3; in xor_arm64_neon_3() local
55 v2 = veorq_u64(vld1q_u64(dp1 + 4), vld1q_u64(dp2 + 4)); in xor_arm64_neon_3()
61 v2 = veorq_u64(v2, vld1q_u64(dp3 + 4)); in xor_arm64_neon_3()
67 vst1q_u64(dp1 + 4, v2); in xor_arm64_neon_3()
86 register uint64x2_t v0, v1, v2, v3; in xor_arm64_neon_4() local
93 v2 in xor_arm64_neon_4()
133 register uint64x2_t v0, v1, v2, v3; xor_arm64_neon_5() local
203 register uint64x2_t v0, v1, v2, v3; xor_arm64_eor3_3() local
240 register uint64x2_t v0, v1, v2, v3; xor_arm64_eor3_4() local
286 register uint64x2_t v0, v1, v2, v3; xor_arm64_eor3_5() local
[all...]
/kernel/linux/linux-5.10/lib/
H A Dxxhash.c111 uint32_t v2 = seed + PRIME32_2; in xxh32() local
118 v2 = xxh32_round(v2, get_unaligned_le32(p)); in xxh32()
126 h32 = xxh_rotl32(v1, 1) + xxh_rotl32(v2, 7) + in xxh32()
181 uint64_t v2 = seed + PRIME64_2; in xxh64() local
188 v2 = xxh64_round(v2, get_unaligned_le64(p)); in xxh64()
196 h64 = xxh_rotl64(v1, 1) + xxh_rotl64(v2, 7) + in xxh64()
199 h64 = xxh64_merge_round(h64, v2); in xxh64()
249 state.v2 in xxh32_reset()
309 uint32_t v2 = state->v2; xxh32_update() local
414 uint64_t v2 = state->v2; xxh64_update() local
453 const uint64_t v2 = state->v2; xxh64_digest() local
[all...]
/kernel/linux/linux-6.6/lib/
H A Dxxhash.c111 uint32_t v2 = seed + PRIME32_2; in xxh32() local
118 v2 = xxh32_round(v2, get_unaligned_le32(p)); in xxh32()
126 h32 = xxh_rotl32(v1, 1) + xxh_rotl32(v2, 7) + in xxh32()
181 uint64_t v2 = seed + PRIME64_2; in xxh64() local
188 v2 = xxh64_round(v2, get_unaligned_le64(p)); in xxh64()
196 h64 = xxh_rotl64(v1, 1) + xxh_rotl64(v2, 7) + in xxh64()
199 h64 = xxh64_merge_round(h64, v2); in xxh64()
249 state.v2 in xxh32_reset()
309 uint32_t v2 = state->v2; xxh32_update() local
414 uint64_t v2 = state->v2; xxh64_update() local
453 const uint64_t v2 = state->v2; xxh64_digest() local
[all...]
/kernel/linux/linux-6.6/arch/s390/include/asm/
H A Dvx-insn-asm.h100 .ifc \vxr,%v2
199 * @v2: Second vector register designated operand
203 .macro RXB rxb v1 v2=0 v3=0 v4=0
208 .if \v2 & 0x10
223 * @v2: Second vector register designated operand (for RXB)
227 .macro MRXB m v1 v2=0 v3=0 v4=0
229 RXB rxb, \v1, \v2, \v3, \v4 variable
238 * @v2: Second vector register designated operand (for RXB)
242 .macro MRXBOPC m opc v1 v2=0 v3=0 v4=0
243 MRXB \m, \v1, \v2, \v variable
288 VX_NUM v2, \\v2 global() variable
401 VX_NUM v2, \\vr2 global() variable
412 VX_NUM v2, \\vr2 global() variable
430 VX_NUM v2, \\vr2 global() variable
434 MRXBOPC \\m4, 0x84, v1, v2, v3 global() variable
461 VX_NUM v2, \\vr2 global() variable
465 MRXBOPC \\m4, 0x61, v1, v2, v3 global() variable
483 VX_NUM v2, \\vr2 global() variable
487 MRXBOPC \\m4, 0x60, v1, v2, v3 global() variable
508 VX_NUM v2, \\vr2 global() variable
518 VX_NUM v2, \\vr2 global() variable
528 VX_NUM v2, \\vr2 global() variable
532 MRXBOPC \\m4, 0xB4, v1, v2, v3 global() variable
550 VX_NUM v2, \\vr2 global() variable
573 VX_NUM v2, \\vr2 global() variable
603 VX_NUM v2, \\vr2 global() variable
607 MRXBOPC \\m4, 0xF3, v1, v2, v3 global() variable
628 VX_NUM v2, \\vr2 global() variable
632 MRXBOPC \\m4, 0x7A, v1, v2, v3 global() variable
673 VX_NUM v2, \\vr2 global() variable
[all...]
/kernel/linux/linux-5.10/arch/s390/include/asm/
H A Dvx-insn.h97 .ifc \vxr,%v2
196 * @v2: Second vector register designated operand
200 .macro RXB rxb v1 v2=0 v3=0 v4=0
205 .if \v2 & 0x10
220 * @v2: Second vector register designated operand (for RXB)
224 .macro MRXB m v1 v2=0 v3=0 v4=0
226 RXB rxb, \v1, \v2, \v3, \v4 variable
235 * @v2: Second vector register designated operand (for RXB)
239 .macro MRXBOPC m opc v1 v2=0 v3=0 v4=0
240 MRXB \m, \v1, \v2, \v variable
285 VX_NUM v2, \\v2 global() variable
388 VX_NUM v2, \\vr2 global() variable
399 VX_NUM v2, \\vr2 global() variable
420 VX_NUM v2, \\vr2 global() variable
430 VX_NUM v2, \\vr2 global() variable
440 VX_NUM v2, \\vr2 global() variable
444 MRXBOPC \\m4, 0xB4, v1, v2, v3 global() variable
462 VX_NUM v2, \\vr2 global() variable
485 VX_NUM v2, \\vr2 global() variable
515 VX_NUM v2, \\vr2 global() variable
519 MRXBOPC \\m4, 0xF3, v1, v2, v3 global() variable
540 VX_NUM v2, \\vr2 global() variable
544 MRXBOPC \\m4, 0x7A, v1, v2, v3 global() variable
[all...]
/kernel/linux/linux-6.6/drivers/gpu/drm/amd/display/dc/inc/
H A Dreg_helper.h67 #define REG_SET_2(reg, init_value, f1, v1, f2, v2) \
70 FN(reg, f2), v2)
72 #define REG_SET_3(reg, init_value, f1, v1, f2, v2, f3, v3) \
75 FN(reg, f2), v2,\
78 #define REG_SET_4(reg, init_value, f1, v1, f2, v2, f3, v3, f4, v4) \
81 FN(reg, f2), v2,\
85 #define REG_SET_5(reg, init_value, f1, v1, f2, v2, f3, v3, f4, v4, \
89 FN(reg, f2), v2,\
94 #define REG_SET_6(reg, init_value, f1, v1, f2, v2, f3, v3, f4, v4, \
98 FN(reg, f2), v2,\
[all...]
/kernel/linux/linux-5.10/drivers/gpu/drm/amd/display/dc/inc/
H A Dreg_helper.h67 #define REG_SET_2(reg, init_value, f1, v1, f2, v2) \
70 FN(reg, f2), v2)
72 #define REG_SET_3(reg, init_value, f1, v1, f2, v2, f3, v3) \
75 FN(reg, f2), v2,\
78 #define REG_SET_4(reg, init_value, f1, v1, f2, v2, f3, v3, f4, v4) \
81 FN(reg, f2), v2,\
85 #define REG_SET_5(reg, init_value, f1, v1, f2, v2, f3, v3, f4, v4, \
89 FN(reg, f2), v2,\
94 #define REG_SET_6(reg, init_value, f1, v1, f2, v2, f3, v3, f4, v4, \
98 FN(reg, f2), v2,\
[all...]
/kernel/linux/linux-5.10/arch/mips/kernel/
H A Dr4k-bugs64.c43 void mult_sh_align_mod(long *v1, long *v2, long *w, in mult_sh_align_mod() argument
114 *v2 = lv2; in mult_sh_align_mod()
120 long v1[8], v2[8], w[8]; in check_mult_sh() local
134 mult_sh_align_mod(&v1[0], &v2[0], &w[0], 32, 0); in check_mult_sh()
135 mult_sh_align_mod(&v1[1], &v2[1], &w[1], 32, 1); in check_mult_sh()
136 mult_sh_align_mod(&v1[2], &v2[2], &w[2], 32, 2); in check_mult_sh()
137 mult_sh_align_mod(&v1[3], &v2[3], &w[3], 32, 3); in check_mult_sh()
138 mult_sh_align_mod(&v1[4], &v2[4], &w[4], 32, 4); in check_mult_sh()
139 mult_sh_align_mod(&v1[5], &v2[5], &w[5], 32, 5); in check_mult_sh()
140 mult_sh_align_mod(&v1[6], &v2[ in check_mult_sh()
[all...]
/kernel/linux/linux-5.10/drivers/gpu/drm/amd/display/dmub/src/
H A Ddmub_reg.h65 #define REG_SET_2(reg, init_value, f1, v1, f2, v2) \
68 FN(reg, f2), v2)
70 #define REG_SET_3(reg, init_value, f1, v1, f2, v2, f3, v3) \
73 FN(reg, f2), v2, \
76 #define REG_SET_4(reg, init_value, f1, v1, f2, v2, f3, v3, f4, v4) \
79 FN(reg, f2), v2, \
92 #define REG_UPDATE_2(reg, f1, v1, f2, v2) \
95 FN(reg, f2), v2)
97 #define REG_UPDATE_3(reg, f1, v1, f2, v2, f3, v3) \
100 FN(reg, f2), v2, \
[all...]
/kernel/linux/linux-6.6/arch/mips/kernel/
H A Dr4k-bugs64.c43 void mult_sh_align_mod(long *v1, long *v2, long *w, in mult_sh_align_mod() argument
114 *v2 = lv2; in mult_sh_align_mod()
120 long v1[8], v2[8], w[8]; in check_mult_sh() local
134 mult_sh_align_mod(&v1[0], &v2[0], &w[0], 32, 0); in check_mult_sh()
135 mult_sh_align_mod(&v1[1], &v2[1], &w[1], 32, 1); in check_mult_sh()
136 mult_sh_align_mod(&v1[2], &v2[2], &w[2], 32, 2); in check_mult_sh()
137 mult_sh_align_mod(&v1[3], &v2[3], &w[3], 32, 3); in check_mult_sh()
138 mult_sh_align_mod(&v1[4], &v2[4], &w[4], 32, 4); in check_mult_sh()
139 mult_sh_align_mod(&v1[5], &v2[5], &w[5], 32, 5); in check_mult_sh()
140 mult_sh_align_mod(&v1[6], &v2[ in check_mult_sh()
[all...]
/kernel/linux/linux-6.6/drivers/gpu/drm/amd/display/dmub/src/
H A Ddmub_reg.h65 #define REG_SET_2(reg, init_value, f1, v1, f2, v2) \
68 FN(reg, f2), v2)
70 #define REG_SET_3(reg, init_value, f1, v1, f2, v2, f3, v3) \
73 FN(reg, f2), v2, \
76 #define REG_SET_4(reg, init_value, f1, v1, f2, v2, f3, v3, f4, v4) \
79 FN(reg, f2), v2, \
92 #define REG_UPDATE_2(reg, f1, v1, f2, v2) \
95 FN(reg, f2), v2)
97 #define REG_UPDATE_3(reg, f1, v1, f2, v2, f3, v3) \
100 FN(reg, f2), v2, \
[all...]

Completed in 12 milliseconds

12345678910>>...20