| /linux-6.6.21/net/ceph/ |
| 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.out_iter)); in ceph_tcp_send()
213 BUG_ON(con->v2.in_kvec_cnt >= ARRAY_SIZE(con->v2.in_kvecs)); in add_in_kvec()
[all …]
|
| /linux-6.6.21/arch/loongarch/lib/ |
| 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,
45 LD_AND_XOR_LINE(v2)
48 : : [v1] "r"(v1), [v2] "r"(v2), [v3] "r"(v3) : "memory"
52 v2 += LINE_WIDTH / sizeof(unsigned long);
59 const unsigned long * __restrict v2,
68 LD_AND_XOR_LINE(v2)
[all …]
|
| /linux-6.6.21/drivers/staging/rtl8723bs/hal/ |
| D | HalHWImg8723B_BB.c | 227 u32 v2 = Array[i+1]; in ODM_ReadAndConfig_MP_8723B_AGC_TAB() local
231 odm_ConfigBB_AGC_8723B(pDM_Odm, v1, bMaskDWord, v2); in ODM_ReadAndConfig_MP_8723B_AGC_TAB()
240 READ_NEXT_PAIR(v1, v2, i); in ODM_ReadAndConfig_MP_8723B_AGC_TAB()
241 } else if (!CheckPositive(pDM_Odm, v1, v2)) { in ODM_ReadAndConfig_MP_8723B_AGC_TAB()
243 READ_NEXT_PAIR(v1, v2, i); in ODM_ReadAndConfig_MP_8723B_AGC_TAB()
244 READ_NEXT_PAIR(v1, v2, i); in ODM_ReadAndConfig_MP_8723B_AGC_TAB()
246 READ_NEXT_PAIR(v1, v2, i); in ODM_ReadAndConfig_MP_8723B_AGC_TAB()
247 if (!CheckNegative(pDM_Odm, v1, v2)) in ODM_ReadAndConfig_MP_8723B_AGC_TAB()
251 READ_NEXT_PAIR(v1, v2, i); in ODM_ReadAndConfig_MP_8723B_AGC_TAB()
259 READ_NEXT_PAIR(v1, v2, i); in ODM_ReadAndConfig_MP_8723B_AGC_TAB()
[all …]
|
| D | HalHWImg8723B_MAC.c | 197 u32 v2 = Array[i+1]; in ODM_ReadAndConfig_MP_8723B_MAC_REG() local
201 odm_ConfigMAC_8723B(pDM_Odm, v1, (u8)v2); in ODM_ReadAndConfig_MP_8723B_MAC_REG()
210 READ_NEXT_PAIR(v1, v2, i); in ODM_ReadAndConfig_MP_8723B_MAC_REG()
211 } else if (!CheckPositive(pDM_Odm, v1, v2)) { in ODM_ReadAndConfig_MP_8723B_MAC_REG()
213 READ_NEXT_PAIR(v1, v2, i); in ODM_ReadAndConfig_MP_8723B_MAC_REG()
214 READ_NEXT_PAIR(v1, v2, i); in ODM_ReadAndConfig_MP_8723B_MAC_REG()
216 READ_NEXT_PAIR(v1, v2, i); in ODM_ReadAndConfig_MP_8723B_MAC_REG()
217 if (!CheckNegative(pDM_Odm, v1, v2)) in ODM_ReadAndConfig_MP_8723B_MAC_REG()
221 READ_NEXT_PAIR(v1, v2, i); in ODM_ReadAndConfig_MP_8723B_MAC_REG()
227 READ_NEXT_PAIR(v1, v2, i); in ODM_ReadAndConfig_MP_8723B_MAC_REG()
[all …]
|
| D | HalHWImg8723B_RF.c | 228 u32 v2 = Array[i+1]; in ODM_ReadAndConfig_MP_8723B_RadioA() local
232 odm_ConfigRF_RadioA_8723B(pDM_Odm, v1, v2); in ODM_ReadAndConfig_MP_8723B_RadioA()
241 READ_NEXT_PAIR(v1, v2, i); in ODM_ReadAndConfig_MP_8723B_RadioA()
242 } else if (!CheckPositive(pDM_Odm, v1, v2)) { in ODM_ReadAndConfig_MP_8723B_RadioA()
244 READ_NEXT_PAIR(v1, v2, i); in ODM_ReadAndConfig_MP_8723B_RadioA()
245 READ_NEXT_PAIR(v1, v2, i); in ODM_ReadAndConfig_MP_8723B_RadioA()
247 READ_NEXT_PAIR(v1, v2, i); in ODM_ReadAndConfig_MP_8723B_RadioA()
248 if (!CheckNegative(pDM_Odm, v1, v2)) in ODM_ReadAndConfig_MP_8723B_RadioA()
252 READ_NEXT_PAIR(v1, v2, i); in ODM_ReadAndConfig_MP_8723B_RadioA()
260 READ_NEXT_PAIR(v1, v2, i); in ODM_ReadAndConfig_MP_8723B_RadioA()
[all …]
|
| /linux-6.6.21/arch/s390/crypto/ |
| 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_LE2BE
188 VGFMAG %v1,CONST_R4R3,%v1,%v2 /* Fold next data chunk */
235 VSRLB %v2,%v1,%v9 /* Store remaining bits in V2 */
237 VGFMAG %v1,CONST_R5,%v1,%v2 /* V1 = (V1 * R5) XOR V2 */
259 VUPLLF %v2,%v1
260 VGFMG %v2,CONST_RU_POLY,%v2
[all …]
|
| 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
206 VGFMAG %v2,CONST_CRC_POLY,%v2,%v1
209 VLGVF %r2,%v2,3
|
| /linux-6.6.21/drivers/char/mwave/ |
| D | mwavedd.h | 84 #define PRINTK_3(f,s,v1,v2) \ argument
86 printk(s,v1,v2); \
89 #define PRINTK_4(f,s,v1,v2,v3) \ argument
91 printk(s,v1,v2,v3); \
94 #define PRINTK_5(f,s,v1,v2,v3,v4) \ argument
96 printk(s,v1,v2,v3,v4); \
99 #define PRINTK_6(f,s,v1,v2,v3,v4,v5) \ argument
101 printk(s,v1,v2,v3,v4,v5); \
104 #define PRINTK_7(f,s,v1,v2,v3,v4,v5,v6) \ argument
106 printk(s,v1,v2,v3,v4,v5,v6); \
[all …]
|
| /linux-6.6.21/Documentation/powerpc/ |
| D | isa-versions.rst | 14 Power8 Power ISA v2.07
15 e6500 Power ISA v2.06 with some exceptions
16 e5500 Power ISA v2.06 with some exceptions, no Altivec
17 Power7 Power ISA v2.06
18 Power6 Power ISA v2.05
19 PA6T Power ISA v2.04
20 Cell PPU - Power ISA v2.02 with some minor exceptions
22 Power5++ Power ISA v2.04 (no VMX)
23 Power5+ Power ISA v2.03
24 Power5 - PowerPC User Instruction Set Architecture Book I v2.02
[all …]
|
| /linux-6.6.21/tools/testing/selftests/powerpc/math/ |
| D | vmx_asm.S | 9 # Should be safe from C, only touches r4, r5 and v0,v1,v2
17 vmr v2,v1
22 vand v2,v2,v1
27 vand v2,v2,v1
32 vand v2,v2,v1
37 vand v2,v2,v1
42 vand v2,v2,v1
47 vand v2,v2,v1
52 vand v2,v2,v1
57 vand v2,v2,v1
[all …]
|
| /linux-6.6.21/arch/arm64/lib/ |
| 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 = veorq_u64(vld1q_u64(dp1 + 4), vld1q_u64(dp2 + 4)); in xor_arm64_neon_4()
99 v2 = veorq_u64(v2, vld1q_u64(dp3 + 4)); in xor_arm64_neon_4()
[all …]
|
| /linux-6.6.21/include/pcmcia/ |
| D | device_id.h | 29 #define PCMCIA_DEVICE_PROD_ID2(v2, vh2) { \ argument
31 .prod_id = { NULL, (v2), NULL, NULL }, \
39 #define PCMCIA_DEVICE_PROD_ID12(v1, v2, vh1, vh2) { \ argument
42 .prod_id = { (v1), (v2), NULL, NULL }, \
57 #define PCMCIA_DEVICE_PROD_ID123(v1, v2, v3, vh1, vh2, vh3) { \ argument
61 .prod_id = { (v1), (v2), (v3), NULL },\
64 #define PCMCIA_DEVICE_PROD_ID124(v1, v2, v4, vh1, vh2, vh4) { \ argument
68 .prod_id = { (v1), (v2), NULL, (v4) }, \
78 #define PCMCIA_DEVICE_PROD_ID1234(v1, v2, v3, v4, vh1, vh2, vh3, vh4) { \ argument
83 .prod_id = { (v1), (v2), (v3), (v4) }, \
[all …]
|
| /linux-6.6.21/arch/powerpc/lib/ |
| 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 …]
|
| /linux-6.6.21/arch/s390/include/asm/ |
| D | vx-insn-asm.h | 100 .ifc \vxr,%v2
203 .macro RXB rxb v1 v2=0 v3=0 v4=0
208 .if \v2 & 0x10
227 .macro MRXB m v1 v2=0 v3=0 v4=0
229 RXB rxb, \v1, \v2, \v3, \v4
242 .macro MRXBOPC m opc v1 v2=0 v3=0 v4=0
243 MRXB \m, \v1, \v2, \v3, \v4
286 .macro VLR v1, v2
288 VX_NUM v2, \v2
289 .word 0xE700 | ((v1&15) << 4) | (v2&15)
[all …]
|
| /linux-6.6.21/drivers/gpu/drm/amd/display/dc/inc/ |
| D | reg_helper.h | 67 #define REG_SET_2(reg, init_value, f1, v1, f2, v2) \ argument
70 FN(reg, f2), v2)
72 #define REG_SET_3(reg, init_value, f1, v1, f2, v2, f3, v3) \ argument
75 FN(reg, f2), v2,\
78 #define REG_SET_4(reg, init_value, f1, v1, f2, v2, f3, v3, f4, v4) \ argument
81 FN(reg, f2), v2,\
85 #define REG_SET_5(reg, init_value, f1, v1, f2, v2, f3, v3, f4, v4, \ argument
89 FN(reg, f2), v2,\
94 #define REG_SET_6(reg, init_value, f1, v1, f2, v2, f3, v3, f4, v4, \ argument
98 FN(reg, f2), v2,\
[all …]
|
| /linux-6.6.21/lib/ |
| 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 = seed + PRIME32_2; in xxh32_reset()
263 state.v2 = seed + PRIME64_2; in xxh64_reset()
295 state->v2 = xxh32_round(state->v2, get_unaligned_le32(p32)); in xxh32_update()
[all …]
|
| /linux-6.6.21/arch/arm64/boot/dts/exynos/ |
| D | exynos5433-bus.dtsi | 14 operating-points-v2 = <&bus_g2d_400_opp_table>;
22 operating-points-v2 = <&bus_g2d_266_opp_table>;
30 operating-points-v2 = <&bus_gscl_opp_table>;
38 operating-points-v2 = <&bus_hevc_opp_table>;
46 operating-points-v2 = <&bus_g2d_400_opp_table>;
54 operating-points-v2 = <&bus_g2d_400_opp_table>;
62 operating-points-v2 = <&bus_g2d_400_opp_table>;
70 operating-points-v2 = <&bus_hevc_opp_table>;
78 operating-points-v2 = <&bus_hevc_opp_table>;
86 operating-points-v2 = <&bus_noc2_opp_table>;
[all …]
|
| /linux-6.6.21/arch/mips/kernel/ |
| 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[6], &w[6], 32, 6); in check_mult_sh()
[all …]
|
| /linux-6.6.21/arch/arm64/boot/dts/rockchip/ |
| D | rk3399-op1-opp.dtsi | 8 compatible = "operating-points-v2";
43 compatible = "operating-points-v2";
86 compatible = "operating-points-v2";
115 compatible = "operating-points-v2";
137 operating-points-v2 = <&cluster0_opp>;
141 operating-points-v2 = <&cluster0_opp>;
145 operating-points-v2 = <&cluster0_opp>;
149 operating-points-v2 = <&cluster0_opp>;
153 operating-points-v2 = <&cluster1_opp>;
157 operating-points-v2 = <&cluster1_opp>;
[all …]
|
| D | rk3399-t-opp.dtsi | 9 compatible = "operating-points-v2";
32 compatible = "operating-points-v2";
67 compatible = "operating-points-v2";
89 operating-points-v2 = <&cluster0_opp>;
93 operating-points-v2 = <&cluster0_opp>;
97 operating-points-v2 = <&cluster0_opp>;
101 operating-points-v2 = <&cluster0_opp>;
105 operating-points-v2 = <&cluster1_opp>;
109 operating-points-v2 = <&cluster1_opp>;
113 operating-points-v2 = <&gpu_opp_table>;
|
| D | rk3399-opp.dtsi | 8 compatible = "operating-points-v2";
39 compatible = "operating-points-v2";
78 compatible = "operating-points-v2";
108 operating-points-v2 = <&cluster0_opp>;
112 operating-points-v2 = <&cluster0_opp>;
116 operating-points-v2 = <&cluster0_opp>;
120 operating-points-v2 = <&cluster0_opp>;
124 operating-points-v2 = <&cluster1_opp>;
128 operating-points-v2 = <&cluster1_opp>;
132 operating-points-v2 = <&gpu_opp_table>;
|
| /linux-6.6.21/Documentation/devicetree/bindings/opp/ |
| D | opp-v2.yaml | 4 $id: http://devicetree.org/schemas/opp/opp-v2.yaml#
13 - $ref: opp-v2-base.yaml#
17 const: operating-points-v2
39 operating-points-v2 = <&cpu0_opp_table0>;
50 operating-points-v2 = <&cpu0_opp_table0>;
55 compatible = "operating-points-v2";
96 operating-points-v2 = <&cpu_opp_table>;
107 operating-points-v2 = <&cpu_opp_table>;
118 operating-points-v2 = <&cpu_opp_table>;
129 operating-points-v2 = <&cpu_opp_table>;
[all …]
|
| /linux-6.6.21/drivers/gpu/drm/amd/display/dmub/src/ |
| D | dmub_reg.h | 65 #define REG_SET_2(reg, init_value, f1, v1, f2, v2) \ argument
68 FN(reg, f2), v2)
70 #define REG_SET_3(reg, init_value, f1, v1, f2, v2, f3, v3) \ argument
73 FN(reg, f2), v2, \
76 #define REG_SET_4(reg, init_value, f1, v1, f2, v2, f3, v3, f4, v4) \ argument
79 FN(reg, f2), v2, \
92 #define REG_UPDATE_2(reg, f1, v1, f2, v2) \ argument
95 FN(reg, f2), v2)
97 #define REG_UPDATE_3(reg, f1, v1, f2, v2, f3, v3) \ argument
100 FN(reg, f2), v2, \
[all …]
|
| /linux-6.6.21/drivers/firmware/google/ |
| D | memconsole-x86-legacy.c | 39 } __packed v2; member
70 hdr->v2.buffer_addr, hdr->v2.start, in found_v2_header()
71 hdr->v2.end, hdr->v2.num_bytes); in found_v2_header()
73 memconsole_baseaddr = phys_to_virt(hdr->v2.buffer_addr + hdr->v2.start); in found_v2_header()
74 memconsole_length = hdr->v2.end - hdr->v2.start; in found_v2_header()
|
| /linux-6.6.21/tools/power/cpupower/debug/kernel/ |
| D | cpufreq-test_tsc.c | 37 u32 v1=0,v2=0,v3=0; in read_pmtmr() local
45 v2 = inl(pm_tmr_ioport); in read_pmtmr()
47 } while ((v1 > v2 && v1 < v3) || (v2 > v3 && v2 < v1) in read_pmtmr()
48 || (v3 > v1 && v3 < v2)); in read_pmtmr()
51 return (v2 & 0xFFFFFF); in read_pmtmr()
|