/kernel/linux/linux-5.10/arch/loongarch/lib/ |
H A D | xor_template.c | 17 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 D | xor_template.c | 18 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 D | messenger_v2.c | 114 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 D | crc32le-vx.S | 132 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 D | crc32be-vx.S | 124 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 D | crc32le-vx.S | 134 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 D | crc32be-vx.S | 125 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 D | device_id.h | 29 #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 D | device_id.h | 29 #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 D | mwavedd.h | 84 #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 D | mwavedd.h | 84 #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 D | xor-neon.c | 19 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 D | xor_vmx.c | 56 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 D | xor_vmx.c | 57 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 D | xor-neon.c | 19 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 D | xxhash.c | 111 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 D | xxhash.c | 111 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 D | vx-insn-asm.h | 100 .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 D | vx-insn.h | 97 .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 D | reg_helper.h | 67 #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 D | reg_helper.h | 67 #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 D | r4k-bugs64.c | 43 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 D | dmub_reg.h | 65 #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 D | r4k-bugs64.c | 43 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 D | dmub_reg.h | 65 #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...] |