Home
last modified time | relevance | path

Searched full:v2 (Results 1 – 25 of 5266) sorted by relevance

12345678910>>...211

/kernel/linux/linux-4.19/tools/testing/selftests/powerpc/math/
Dvmx_asm.S13 # Should be safe from C, only touches r4, r5 and v0,v1,v2
21 vmr v2,v1
26 vand v2,v2,v1
31 vand v2,v2,v1
36 vand v2,v2,v1
41 vand v2,v2,v1
46 vand v2,v2,v1
51 vand v2,v2,v1
56 vand v2,v2,v1
61 vand v2,v2,v1
[all …]
/kernel/linux/linux-5.10/tools/testing/selftests/powerpc/math/
Dvmx_asm.S9 # 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 …]
/kernel/linux/linux-4.19/drivers/gpu/drm/amd/display/dc/inc/
Dreg_helper.h67 #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 …]
/kernel/linux/linux-5.10/include/uapi/linux/
Dnfs.h43 * Error codes that have a `--' in the v2 column are not part of the
47 NFS_OK = 0, /* v2 v3 v4 */
48 NFSERR_PERM = 1, /* v2 v3 v4 */
49 NFSERR_NOENT = 2, /* v2 v3 v4 */
50 NFSERR_IO = 5, /* v2 v3 v4 */
51 NFSERR_NXIO = 6, /* v2 v3 v4 */
52 NFSERR_EAGAIN = 11, /* v2 v3 */
53 NFSERR_ACCES = 13, /* v2 v3 v4 */
54 NFSERR_EXIST = 17, /* v2 v3 v4 */
56 NFSERR_NODEV = 19, /* v2 v3 v4 */
[all …]
/kernel/linux/linux-4.19/include/uapi/linux/
Dnfs.h43 * Error codes that have a `--' in the v2 column are not part of the
47 NFS_OK = 0, /* v2 v3 v4 */
48 NFSERR_PERM = 1, /* v2 v3 v4 */
49 NFSERR_NOENT = 2, /* v2 v3 v4 */
50 NFSERR_IO = 5, /* v2 v3 v4 */
51 NFSERR_NXIO = 6, /* v2 v3 v4 */
52 NFSERR_EAGAIN = 11, /* v2 v3 */
53 NFSERR_ACCES = 13, /* v2 v3 v4 */
54 NFSERR_EXIST = 17, /* v2 v3 v4 */
56 NFSERR_NODEV = 19, /* v2 v3 v4 */
[all …]
/kernel/linux/linux-5.10/arch/powerpc/lib/
Dxor_vmx.c44 #define XOR(V1, V2) \ argument
46 V1##_0 = vec_xor(V1##_0, V2##_0); \
47 V1##_1 = vec_xor(V1##_1, V2##_1); \
48 V1##_2 = vec_xor(V1##_2, V2##_2); \
49 V1##_3 = vec_xor(V1##_3, V2##_3); \
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()
[all …]
/kernel/linux/linux-5.10/drivers/gpu/drm/amd/display/dc/inc/
Dreg_helper.h67 #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 …]
/kernel/linux/linux-4.19/arch/powerpc/lib/
Dxor_vmx.c56 #define XOR(V1, V2) \ argument
58 V1##_0 = vec_xor(V1##_0, V2##_0); \
59 V1##_1 = vec_xor(V1##_1, V2##_1); \
60 V1##_2 = vec_xor(V1##_2, V2##_2); \
61 V1##_3 = vec_xor(V1##_3, V2##_3); \
68 DEFINE(v2); in __xor_altivec_2()
73 LOAD(v2); in __xor_altivec_2()
74 XOR(v1, v2); in __xor_altivec_2()
78 v2 += 4; in __xor_altivec_2()
86 DEFINE(v2); in __xor_altivec_3()
[all …]
/kernel/linux/linux-4.19/include/pcmcia/
Ddevice_id.h32 #define PCMCIA_DEVICE_PROD_ID2(v2, vh2) { \ argument
34 .prod_id = { NULL, (v2), NULL, NULL }, \
42 #define PCMCIA_DEVICE_PROD_ID12(v1, v2, vh1, vh2) { \ argument
45 .prod_id = { (v1), (v2), NULL, NULL }, \
60 #define PCMCIA_DEVICE_PROD_ID123(v1, v2, v3, vh1, vh2, vh3) { \ argument
64 .prod_id = { (v1), (v2), (v3), NULL },\
67 #define PCMCIA_DEVICE_PROD_ID124(v1, v2, v4, vh1, vh2, vh4) { \ argument
71 .prod_id = { (v1), (v2), NULL, (v4) }, \
81 #define PCMCIA_DEVICE_PROD_ID1234(v1, v2, v3, v4, vh1, vh2, vh3, vh4) { \ argument
86 .prod_id = { (v1), (v2), (v3), (v4) }, \
[all …]
/kernel/linux/linux-5.10/include/pcmcia/
Ddevice_id.h29 #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 …]
/kernel/linux/linux-4.19/arch/s390/include/asm/
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
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, \v3, \v4
[all …]
/kernel/linux/linux-5.10/arch/s390/include/asm/
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
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, \v3, \v4
[all …]
/kernel/linux/linux-5.10/arch/arm64/lib/
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 = veorq_u64(vld1q_u64(dp1 + 4), vld1q_u64(dp2 + 4)); in xor_arm64_neon_4()
96 v2 = veorq_u64(v2, vld1q_u64(dp3 + 4)); in xor_arm64_neon_4()
[all …]
/kernel/linux/linux-4.19/drivers/char/mwave/
Dmwavedd.h84 #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 …]
/kernel/linux/linux-5.10/drivers/char/mwave/
Dmwavedd.h84 #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 …]
/kernel/linux/linux-5.10/arch/s390/crypto/
Dcrc32le-vx.S132 VPERM %v2,%v2,%v2,CONST_PERM_LE2BE
156 * in V2, V3, and V4 respectively.
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_LE2BE
186 VGFMAG %v1,CONST_R4R3,%v1,%v2 /* Fold next data chunk */
224 * and store the result in V2 which is then accumulated. Use the
233 VSRLB %v2,%v1,%v9 /* Store remaining bits in V2 */
235 VGFMAG %v1,CONST_R5,%v1,%v2 /* V1 = (V1 * R5) XOR V2 */
[all …]
/kernel/linux/linux-4.19/arch/s390/crypto/
Dcrc32le-vx.S131 VPERM %v2,%v2,%v2,CONST_PERM_LE2BE
155 * in V2, V3, and V4 respectively.
158 VGFMAG %v2,CONST_R2R1,%v2,%v6
174 VGFMAG %v1,CONST_R4R3,%v1,%v2
183 VL %v2,0,,%r3 /* Load next data chunk */
184 VPERM %v2,%v2,%v2,CONST_PERM_LE2BE
185 VGFMAG %v1,CONST_R4R3,%v1,%v2 /* Fold next data chunk */
223 * and store the result in V2 which is then accumulated. Use the
232 VSRLB %v2,%v1,%v9 /* Store remaining bits in V2 */
234 VGFMAG %v1,CONST_R5,%v1,%v2 /* V1 = (V1 * R5) XOR V2 */
[all …]
/kernel/linux/linux-4.19/arch/arm64/crypto/
Dcrc32-ce-core.S149 pmull2 v6.1q, v2.2d, vCONSTANT.2d
154 pmull v2.1q, v2.1d, vCONSTANT.1d
160 eor v2.16b, v2.16b, v6.16b
168 eor v2.16b, v2.16b, v6.16b
192 eor v1.16b, v1.16b, v2.16b
209 ld1 {v2.16b}, [BUF], #0x10
213 eor v1.16b, v1.16b, v2.16b
220 ext v2.16b, v1.16b, v1.16b, #8
221 pmull2 v2.1q, v2.2d, vCONSTANT.2d
223 eor v1.16b, v1.16b, v2.16b
[all …]
/kernel/linux/linux-4.19/arch/arm64/boot/dts/exynos/
Dexynos5433-bus.dtsi14 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 …]
/kernel/linux/linux-5.10/arch/arm64/boot/dts/exynos/
Dexynos5433-bus.dtsi14 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 …]
/kernel/linux/linux-5.10/Documentation/powerpc/
Disa-versions.rst12 Power8 Power ISA v2.07
13 Power7 Power ISA v2.06
14 Power6 Power ISA v2.05
15 PA6T Power ISA v2.04
16 Cell PPU - Power ISA v2.02 with some minor exceptions
18 Power5++ Power ISA v2.04 (no VMX)
19 Power5+ Power ISA v2.03
20 Power5 - PowerPC User Instruction Set Architecture Book I v2.02
21 - PowerPC Virtual Environment Architecture Book II v2.02
22 - PowerPC Operating Environment Architecture Book III v2.02
[all …]
/kernel/linux/linux-5.10/include/linux/
Dprandom.h30 #define PRND_SIPROUND(v0, v1, v2, v3) ( \ argument
31 v0 += v1, v1 = rol64(v1, 13), v2 += v3, v3 = rol64(v3, 16), \
32 v1 ^= v0, v0 = rol64(v0, 32), v3 ^= v2, \
33 v0 += v3, v3 = rol64(v3, 21), v2 += v1, v1 = rol64(v1, 17), \
34 v3 ^= v0, v1 ^= v2, v2 = rol64(v2, 32) \
46 #define PRND_SIPROUND(v0, v1, v2, v3) ( \ argument
47 v0 += v1, v1 = rol32(v1, 5), v2 += v3, v3 = rol32(v3, 8), \
48 v1 ^= v0, v0 = rol32(v0, 16), v3 ^= v2, \
49 v0 += v3, v3 = rol32(v3, 7), v2 += v1, v1 = rol32(v1, 13), \
50 v3 ^= v0, v1 ^= v2, v2 = rol32(v2, 16) \
/kernel/linux/linux-5.10/lib/
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 = 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 …]
/kernel/linux/linux-4.19/lib/
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 = 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 …]
/kernel/linux/linux-4.19/drivers/staging/rtl8188eu/hal/
Drf_cfg.c143 #define READ_NEXT_PAIR(v1, v2, i) \ argument
146 v2 = array[i+1]; \
193 u32 v2 = array[i+1]; in rtl88e_phy_config_rf_with_headerfile() local
196 rtl8188e_config_rf_reg(adapt, v1, v2); in rtl88e_phy_config_rf_with_headerfile()
200 READ_NEXT_PAIR(v1, v2, i); in rtl88e_phy_config_rf_with_headerfile()
201 while (v2 != 0xDEAD && v2 != 0xCDEF && in rtl88e_phy_config_rf_with_headerfile()
202 v2 != 0xCDCD && i < array_len - 2) in rtl88e_phy_config_rf_with_headerfile()
203 READ_NEXT_PAIR(v1, v2, i); in rtl88e_phy_config_rf_with_headerfile()
206 READ_NEXT_PAIR(v1, v2, i); in rtl88e_phy_config_rf_with_headerfile()
207 while (v2 != 0xDEAD && v2 != 0xCDEF && in rtl88e_phy_config_rf_with_headerfile()
[all …]

12345678910>>...211