| /Linux-v5.10/arch/powerpc/lib/ |
| D | xor_vmx.c | 44 #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); \
55 DEFINE(v1); in __xor_altivec_2()
60 LOAD(v1); in __xor_altivec_2()
62 XOR(v1, v2); in __xor_altivec_2()
63 STORE(v1); in __xor_altivec_2()
65 v1 += 4; in __xor_altivec_2()
[all …]
|
| /Linux-v5.10/arch/s390/include/asm/ |
| D | vx-insn.h | 94 .ifc \vxr,%v1
195 * @v1: First vector register designated operand
200 .macro RXB rxb v1 v2=0 v3=0 v4=0
202 .if \v1 & 0x10
219 * @v1: First vector register designated operand (for RXB)
224 .macro MRXB m v1 v2=0 v3=0 v4=0
226 RXB rxb, \v1, \v2, \v3, \v4
234 * @v1: First 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 …]
|
| /Linux-v5.10/arch/arm64/crypto/ |
| D | aes-ce-ccm-core.S | 23 eor v1.16b, v1.16b, v1.16b
27 ins v1.b[0], w7
28 ext v1.16b, v1.16b, v1.16b, #1 /* rotate in the input bytes */
31 eor v0.16b, v0.16b, v1.16b
58 ld1 {v1.16b}, [x1], #16 /* load next input block */
59 eor v0.16b, v0.16b, v1.16b /* xor with mac */
77 9: ext v1.16b, v1.16b, v1.16b, #1
80 91: eor v0.16b, v0.16b, v1.16b
95 ld1 {v1.16b}, [x1] /* load 1st ctriv */
104 aese v1.16b, v4.16b
[all …]
|
| D | aes-ce-core.S | 14 ld1 {v1.4s}, [x0], #16
18 mov v3.16b, v1.16b
20 0: mov v2.16b, v1.16b
24 2: ld1 {v1.4s}, [x0], #16
29 aese v0.16b, v1.16b
42 ld1 {v1.4s}, [x0], #16
46 mov v3.16b, v1.16b
48 0: mov v2.16b, v1.16b
52 2: ld1 {v1.4s}, [x0], #16
57 aesd v0.16b, v1.16b
[all …]
|
| D | aes-modes.S | 26 encrypt_block4x v0, v1, v2, v3, w3, x2, x8, w7
31 decrypt_block4x v0, v1, v2, v3, w3, x2, x8, w7
37 encrypt_block5x v0, v1, v2, v3, v4, w3, x2, x8, w7
42 decrypt_block5x v0, v1, v2, v3, v4, w3, x2, x8, w7
148 eor v1.16b, v1.16b, v0.16b
149 encrypt_block v1, w3, x2, x6, w7
150 eor v2.16b, v2.16b, v1.16b
199 mov v6.16b, v1.16b
204 eor v1.16b, v1.16b, v5.16b
212 mov v5.16b, v1.16b
[all …]
|
| /Linux-v5.10/arch/s390/crypto/ |
| D | crc32le-vx.S | 98 * V1..V4: Data for CRC computation.
130 VLM %v1,%v4,0,%r3 /* 64-bytes into V1..V4 */
131 VPERM %v1,%v1,%v1,CONST_PERM_LE2BE
136 VX %v1,%v0,%v1 /* V1 ^= CRC */
152 * Perform a GF(2) multiplication of the doublewords in V1 with
155 * stored in V1. Repeat this step for the register contents
158 VGFMAG %v1,CONST_R2R1,%v1,%v5
171 * Fold V1 to V4 into a single 128-bit value in V1. Multiply V1 with R3
175 VGFMAG %v1,CONST_R4R3,%v1,%v2
176 VGFMAG %v1,CONST_R4R3,%v1,%v3
[all …]
|
| D | crc32be-vx.S | 88 * V1..V4: Data for CRC computation.
103 VLM %v1,%v4,0,%r3 /* 64-bytes into V1..V4 */
104 VX %v1,%v0,%v1 /* V1 ^= CRC */
117 * Perform a GF(2) multiplication of the doublewords in V1 with
120 * stored in V1. Repeat this step for the register contents
123 VGFMAG %v1,CONST_R1R2,%v1,%v5
136 /* Fold V1 to V4 into a single 128-bit value in V1 */
137 VGFMAG %v1,CONST_R3R4,%v1,%v2
138 VGFMAG %v1,CONST_R3R4,%v1,%v3
139 VGFMAG %v1,CONST_R3R4,%v1,%v4
[all …]
|
| /Linux-v5.10/tools/testing/selftests/powerpc/math/ |
| D | vmx_asm.S | 9 # Should be safe from C, only touches r4, r5 and v0,v1,v2
16 vcmpequd. v1,v0,v20
17 vmr v2,v1
21 vcmpequd. v1,v0,v21
22 vand v2,v2,v1
26 vcmpequd. v1,v0,v22
27 vand v2,v2,v1
31 vcmpequd. v1,v0,v23
32 vand v2,v2,v1
36 vcmpequd. v1,v0,v24
[all …]
|
| /Linux-v5.10/include/pcmcia/ |
| D | device_id.h | 24 #define PCMCIA_DEVICE_PROD_ID1(v1, vh1) { \ argument
26 .prod_id = { (v1), NULL, NULL, NULL }, \
39 #define PCMCIA_DEVICE_PROD_ID12(v1, v2, vh1, vh2) { \ argument
42 .prod_id = { (v1), (v2), NULL, NULL }, \
45 #define PCMCIA_DEVICE_PROD_ID13(v1, v3, vh1, vh3) { \ argument
48 .prod_id = { (v1), NULL, (v3), NULL }, \
51 #define PCMCIA_DEVICE_PROD_ID14(v1, v4, vh1, vh4) { \ argument
54 .prod_id = { (v1), NULL, NULL, (v4) }, \
57 #define PCMCIA_DEVICE_PROD_ID123(v1, v2, v3, vh1, vh2, vh3) { \ argument
61 .prod_id = { (v1), (v2), (v3), NULL },\
[all …]
|
| /Linux-v5.10/arch/x86/lib/ |
| D | x86-opcode-map.txt | 28 # (v1): this opcode only supports 128bit VEX.
349 # Many AVX instructions lack v1 superscript, according to Intel AVX-Prgramming
351 10: vmovups Vps,Wps | vmovupd Vpd,Wpd (66) | vmovss Vx,Hx,Wss (F3),(v1) | vmovsd Vx,Hx,Wsd (F2),(v1)
352 … vmovups Wps,Vps | vmovupd Wpd,Vpd (66) | vmovss Wss,Hx,Vss (F3),(v1) | vmovsd Wsd,Hx,Vsd (F2),(v1)
353 12: vmovlps Vq,Hq,Mq (v1) | vmovhlps Vq,Hq,Uq (v1) | vmovlpd Vq,Hq,Mq (66),(v1) | vmovsldup Vx,Wx (…
354 13: vmovlps Mq,Vq (v1) | vmovlpd Mq,Vq (66),(v1)
357 16: vmovhps Vdq,Hq,Mq (v1) | vmovlhps Vdq,Hq,Uq (v1) | vmovhpd Vdq,Hq,Mq (66),(v1) | vmovshdup Vx,W…
358 17: vmovhps Mq,Vq (v1) | vmovhpd Mq,Vq (66),(v1)
382 …s Vps,Qpi | cvtpi2pd Vpd,Qpi (66) | vcvtsi2ss Vss,Hss,Ey (F3),(v1) | vcvtsi2sd Vsd,Hsd,Ey (F2),(v1)
384 …tps2pi Ppi,Wps | cvttpd2pi Ppi,Wpd (66) | vcvttss2si Gy,Wss (F3),(v1) | vcvttsd2si Gy,Wsd (F2),(v1)
[all …]
|
| /Linux-v5.10/tools/arch/x86/lib/ |
| D | x86-opcode-map.txt | 28 # (v1): this opcode only supports 128bit VEX.
349 # Many AVX instructions lack v1 superscript, according to Intel AVX-Prgramming
351 10: vmovups Vps,Wps | vmovupd Vpd,Wpd (66) | vmovss Vx,Hx,Wss (F3),(v1) | vmovsd Vx,Hx,Wsd (F2),(v1)
352 … vmovups Wps,Vps | vmovupd Wpd,Vpd (66) | vmovss Wss,Hx,Vss (F3),(v1) | vmovsd Wsd,Hx,Vsd (F2),(v1)
353 12: vmovlps Vq,Hq,Mq (v1) | vmovhlps Vq,Hq,Uq (v1) | vmovlpd Vq,Hq,Mq (66),(v1) | vmovsldup Vx,Wx (…
354 13: vmovlps Mq,Vq (v1) | vmovlpd Mq,Vq (66),(v1)
357 16: vmovhps Vdq,Hq,Mq (v1) | vmovlhps Vdq,Hq,Uq (v1) | vmovhpd Vdq,Hq,Mq (66),(v1) | vmovshdup Vx,W…
358 17: vmovhps Mq,Vq (v1) | vmovhpd Mq,Vq (66),(v1)
382 …s Vps,Qpi | cvtpi2pd Vpd,Qpi (66) | vcvtsi2ss Vss,Hss,Ey (F3),(v1) | vcvtsi2sd Vsd,Hsd,Ey (F2),(v1)
384 …tps2pi Ppi,Wps | cvttpd2pi Ppi,Wpd (66) | vcvttss2si Gy,Wss (F3),(v1) | vcvttsd2si Gy,Wsd (F2),(v1)
[all …]
|
| /Linux-v5.10/arch/powerpc/boot/dts/fsl/ |
| D | interlaken-lac-portals.dtsi | 39 compatible = "fsl,interlaken-lac-portal-v1.0";
44 compatible = "fsl,interlaken-lac-portal-v1.0";
49 compatible = "fsl,interlaken-lac-portal-v1.0";
54 compatible = "fsl,interlaken-lac-portal-v1.0";
59 compatible = "fsl,interlaken-lac-portal-v1.0";
64 compatible = "fsl,interlaken-lac-portal-v1.0";
69 compatible = "fsl,interlaken-lac-portal-v1.0";
74 compatible = "fsl,interlaken-lac-portal-v1.0";
79 compatible = "fsl,interlaken-lac-portal-v1.0";
84 compatible = "fsl,interlaken-lac-portal-v1.0";
[all …]
|
| /Linux-v5.10/drivers/gpu/drm/amd/display/dc/inc/ |
| D | reg_helper.h | 67 #define REG_SET_2(reg, init_value, f1, v1, f2, v2) \ argument
69 FN(reg, f1), v1,\
72 #define REG_SET_3(reg, init_value, f1, v1, f2, v2, f3, v3) \ argument
74 FN(reg, f1), v1,\
78 #define REG_SET_4(reg, init_value, f1, v1, f2, v2, f3, v3, f4, v4) \ argument
80 FN(reg, f1), v1,\
85 #define REG_SET_5(reg, init_value, f1, v1, f2, v2, f3, v3, f4, v4, \ argument
88 FN(reg, f1), v1,\
94 #define REG_SET_6(reg, init_value, f1, v1, f2, v2, f3, v3, f4, v4, \ argument
97 FN(reg, f1), v1,\
[all …]
|
| /Linux-v5.10/drivers/char/mwave/ |
| D | mwavedd.h | 79 #define PRINTK_2(f,s,v1) \ argument
81 printk(s,v1); \
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); \
[all …]
|
| /Linux-v5.10/arch/arm64/lib/ |
| D | xor-neon.c | 19 register uint64x2_t v0, v1, v2, v3; in xor_arm64_neon_2() local
25 v1 = veorq_u64(vld1q_u64(dp1 + 2), vld1q_u64(dp2 + 2)); in xor_arm64_neon_2()
31 vst1q_u64(dp1 + 2, v1); in xor_arm64_neon_2()
47 register uint64x2_t v0, v1, v2, v3; in xor_arm64_neon_3() local
53 v1 = veorq_u64(vld1q_u64(dp1 + 2), vld1q_u64(dp2 + 2)); in xor_arm64_neon_3()
59 v1 = veorq_u64(v1, vld1q_u64(dp3 + 2)); in xor_arm64_neon_3()
65 vst1q_u64(dp1 + 2, v1); in xor_arm64_neon_3()
83 register uint64x2_t v0, v1, v2, v3; in xor_arm64_neon_4() local
89 v1 = veorq_u64(vld1q_u64(dp1 + 2), vld1q_u64(dp2 + 2)); in xor_arm64_neon_4()
95 v1 = veorq_u64(v1, vld1q_u64(dp3 + 2)); in xor_arm64_neon_4()
[all …]
|
| /Linux-v5.10/drivers/hid/ |
| D | wacom.h | 26 * v1.8 (vp) - Submit URB only when operating, moved to CVS,
29 * v1.11 (vp) - Add URB ->dev setting for new kernels
30 * v1.11 (jb) - Add support for the 4D Mouse & Lens
31 * v1.12 (de) - Add support for two more inking pen IDs
32 * v1.14 (vp) - Use new USB device id probing scheme.
34 * v1.18 (vp) - Fix mouse wheel direction
36 * v1.20 (fl) - Report tool id for Intuos devices
41 * v1.21 (vp) - Removed protocol descriptions
44 * v1.21.1 (fl) - added Graphire2 support
45 * v1.21.2 (fl) - added Intuos2 support
[all …]
|
| /Linux-v5.10/include/linux/ |
| D | prandom.h | 30 #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) \
|
| /Linux-v5.10/tools/perf/pmu-events/arch/arm64/ |
| D | mapfile.csv | 15 0x00000000410fd030,v1,arm/cortex-a53,core
16 0x00000000420f1000,v1,arm/cortex-a53,core
17 0x00000000410fd070,v1,arm/cortex-a57-a72,core
18 0x00000000410fd080,v1,arm/cortex-a57-a72,core
19 0x00000000410fd0b0,v1,arm/cortex-a76-n1,core
20 0x00000000410fd0c0,v1,arm/cortex-a76-n1,core
21 0x00000000420f5160,v1,cavium/thunderx2,core
22 0x00000000430f0af0,v1,cavium/thunderx2,core
23 0x00000000480fd010,v1,hisilicon/hip08,core
24 0x00000000500f0000,v1,ampere/emag,core
|
| /Linux-v5.10/lib/ |
| D | atomic64_test.c | 107 int v1 = 0xdeadbeef; in test_atomic() local
118 TEST(, or, |=, v1); in test_atomic()
119 TEST(, and, &=, v1); in test_atomic()
120 TEST(, xor, ^=, v1); in test_atomic()
121 TEST(, andnot, &= ~, v1); in test_atomic()
133 FETCH_FAMILY_TEST(, fetch_or, |=, v1); in test_atomic()
134 FETCH_FAMILY_TEST(, fetch_and, &=, v1); in test_atomic()
135 FETCH_FAMILY_TEST(, fetch_andnot, &= ~, v1); in test_atomic()
136 FETCH_FAMILY_TEST(, fetch_xor, ^=, v1); in test_atomic()
141 XCHG_FAMILY_TEST(, v0, v1); in test_atomic()
[all …]
|
| /Linux-v5.10/arch/mips/include/asm/ |
| D | stackframe.h | 60 mflhxu v1
61 LONG_S v1, PT_LO(sp)
62 mflhxu v1
63 LONG_S v1, PT_HI(sp)
64 mflhxu v1
65 LONG_S v1, PT_ACX(sp)
67 mfhi v1
77 LONG_S v1, PT_HI(sp)
78 mflo v1
85 LONG_S v1, PT_LO(sp)
[all …]
|
| /Linux-v5.10/Documentation/devicetree/bindings/arm/bcm/ |
| D | brcm,bcm4708.yaml | 29 - linksys,ea6300-v1
31 - luxul,xap-1510v1
45 - luxul,xap-1410v1
46 - luxul,xwr-1200v1
59 - tplink,archer-c9-v1
69 - luxul,abr-4500-v1
70 - luxul,xap-1610-v1
71 - luxul,xbr-4500-v1
72 - luxul,xwc-2000-v1
73 - luxul,xwr-3100v1
[all …]
|
| /Linux-v5.10/arch/powerpc/crypto/ |
| D | crc32-vpmsum_core.S | 161 vxor v1,v1,v1
265 vxor v1,v1,v9
320 vxor v1,v1,v9
351 vxor v1,v1,v9
367 vsldoi v1,v1,zeroes,4
397 vxor v17,v1,v9
426 lvx v1,off16,r3
436 VPMSUMW(v1,v17,v1)
497 1: vxor v0,v0,v1
515 vsldoi v1,v0,v0,8
[all …]
|
| /Linux-v5.10/drivers/staging/rtl8723bs/hal/ |
| D | HalHWImg8723B_BB.c | 274 u32 v1 = Array[i]; in ODM_ReadAndConfig_MP_8723B_AGC_TAB() local
278 if (v1 < 0x40000000) { in ODM_ReadAndConfig_MP_8723B_AGC_TAB()
279 odm_ConfigBB_AGC_8723B(pDM_Odm, v1, bMaskDWord, v2); in ODM_ReadAndConfig_MP_8723B_AGC_TAB()
284 u8 cCond = (u8)((v1 & (BIT29|BIT28)) >> 28); in ODM_ReadAndConfig_MP_8723B_AGC_TAB()
288 READ_NEXT_PAIR(v1, v2, i); in ODM_ReadAndConfig_MP_8723B_AGC_TAB()
289 } else if (!CheckPositive(pDM_Odm, v1, v2)) { in ODM_ReadAndConfig_MP_8723B_AGC_TAB()
291 READ_NEXT_PAIR(v1, v2, i); in ODM_ReadAndConfig_MP_8723B_AGC_TAB()
292 READ_NEXT_PAIR(v1, v2, i); in ODM_ReadAndConfig_MP_8723B_AGC_TAB()
294 READ_NEXT_PAIR(v1, v2, i); in ODM_ReadAndConfig_MP_8723B_AGC_TAB()
295 if (!CheckNegative(pDM_Odm, v1, v2)) in ODM_ReadAndConfig_MP_8723B_AGC_TAB()
[all …]
|
| /Linux-v5.10/arch/powerpc/platforms/ps3/ |
| D | repository.c | 54 u64 v1, u64 v2, const char *func, int line) in _dump_node() argument
61 pr_devel("%s:%d: v1: %016llx\n", func, line, v1); in _dump_node()
104 * @v1: First repository value (high word).
113 u64 v1; in read_node() local
122 result = lv1_read_repository_node(lpar_id, n1, n2, n3, n4, &v1, in read_node()
132 dump_node(lpar_id, n1, n2, n3, n4, v1, v2); in read_node()
135 *_v1 = v1; in read_node()
139 if (v1 && !_v1) in read_node()
140 pr_devel("%s:%d: warning: discarding non-zero v1: %016llx\n", in read_node()
141 __func__, __LINE__, v1); in read_node()
[all …]
|
| /Linux-v5.10/arch/mips/bcm47xx/ |
| D | board.c | 58 {{BCM47XX_BOARD_ASUS_WL500GPV1, "Asus WL500GP V1"}, "WL500gp-"},
126 {{BCM47XX_BOARD_LINKSYS_E900V1, "Linksys E900 V1"}, "E900", "1.0"},
128 {{BCM47XX_BOARD_LINKSYS_E1000V1, "Linksys E1000 V1"}, "E100", "1.0"},
132 {{BCM47XX_BOARD_LINKSYS_E2000V1, "Linksys E2000 V1"}, "Linksys E2000", "1.0"},
134 {{BCM47XX_BOARD_LINKSYS_E3000V1, "Linksys E3000 V1"}, "E300", "1.0"},
135 {{BCM47XX_BOARD_LINKSYS_E3200V1, "Linksys E3200 V1"}, "E3200", "1.0"},
136 {{BCM47XX_BOARD_LINKSYS_E4200V1, "Linksys E4200 V1"}, "E4200", "1.0"},
137 {{BCM47XX_BOARD_LINKSYS_WRT150NV11, "Linksys WRT150N V1.1"}, "WRT150N", "1.1"},
138 {{BCM47XX_BOARD_LINKSYS_WRT150NV1, "Linksys WRT150N V1"}, "WRT150N", "1"},
139 {{BCM47XX_BOARD_LINKSYS_WRT160NV1, "Linksys WRT160N V1"}, "WRT160N", "1.0"},
[all …]
|
