Home
last modified time | relevance | path

Searched refs:v3 (Results 1 - 25 of 281) sorted by relevance

12345678910>>...12

/kernel/linux/linux-5.10/drivers/pci/controller/
H A Dpci-v3-semi.c315 struct v3_pci *v3 = bus->sysdata; in v3_map_bus() local
367 writel(v3_addr_to_lb_base(v3->non_pre_mem) | in v3_map_bus()
369 v3->base + V3_LB_BASE0); in v3_map_bus()
375 writel(v3_addr_to_lb_base(v3->config_mem) | in v3_map_bus()
377 v3->base + V3_LB_BASE1); in v3_map_bus()
378 writew(mapaddress, v3->base + V3_LB_MAP1); in v3_map_bus()
380 return v3->config_base + address + offset; in v3_map_bus()
383 static void v3_unmap_bus(struct v3_pci *v3) in v3_unmap_bus() argument
388 writel(v3_addr_to_lb_base(v3->pre_mem) | in v3_unmap_bus()
391 v3 in v3_unmap_bus()
407 struct v3_pci *v3 = bus->sysdata; v3_pci_read_config() local
421 struct v3_pci *v3 = bus->sysdata; v3_pci_write_config() local
440 struct v3_pci *v3 = data; v3_irq() local
482 v3_integrator_init(struct v3_pci *v3) v3_integrator_init() argument
519 v3_pci_setup_resource(struct v3_pci *v3, struct pci_host_bridge *host, struct resource_entry *win) v3_pci_setup_resource() argument
597 v3_get_dma_range_config(struct v3_pci *v3, struct resource_entry *entry, u32 *pci_base, u32 *pci_map) v3_get_dma_range_config() argument
675 v3_pci_parse_map_dma_ranges(struct v3_pci *v3, struct device_node *np) v3_pci_parse_map_dma_ranges() argument
712 struct v3_pci *v3; v3_pci_probe() local
[all...]
/kernel/linux/linux-6.6/drivers/pci/controller/
H A Dpci-v3-semi.c313 struct v3_pci *v3 = bus->sysdata; in v3_map_bus() local
365 writel(v3_addr_to_lb_base(v3->non_pre_mem) | in v3_map_bus()
367 v3->base + V3_LB_BASE0); in v3_map_bus()
373 writel(v3_addr_to_lb_base(v3->config_mem) | in v3_map_bus()
375 v3->base + V3_LB_BASE1); in v3_map_bus()
376 writew(mapaddress, v3->base + V3_LB_MAP1); in v3_map_bus()
378 return v3->config_base + address + offset; in v3_map_bus()
381 static void v3_unmap_bus(struct v3_pci *v3) in v3_unmap_bus() argument
386 writel(v3_addr_to_lb_base(v3->pre_mem) | in v3_unmap_bus()
389 v3 in v3_unmap_bus()
405 struct v3_pci *v3 = bus->sysdata; v3_pci_read_config() local
419 struct v3_pci *v3 = bus->sysdata; v3_pci_write_config() local
438 struct v3_pci *v3 = data; v3_irq() local
480 v3_integrator_init(struct v3_pci *v3) v3_integrator_init() argument
517 v3_pci_setup_resource(struct v3_pci *v3, struct pci_host_bridge *host, struct resource_entry *win) v3_pci_setup_resource() argument
595 v3_get_dma_range_config(struct v3_pci *v3, struct resource_entry *entry, u32 *pci_base, u32 *pci_map) v3_get_dma_range_config() argument
673 v3_pci_parse_map_dma_ranges(struct v3_pci *v3, struct device_node *np) v3_pci_parse_map_dma_ranges() argument
710 struct v3_pci *v3; v3_pci_probe() local
[all...]
/kernel/linux/linux-5.10/arch/loongarch/lib/
H A Dxor_template.c36 unsigned long *v3)
44 LD_AND_XOR_LINE(v3)
46 : : [v1] "r"(v1), [v2] "r"(v2), [v3] "r"(v3) : "memory"
51 v3 += LINE_WIDTH / sizeof(unsigned long);
57 unsigned long *v3, unsigned long *v4) variable
65 LD_AND_XOR_LINE(v3)
68 : : [v1] "r"(v1), [v2] "r"(v2), [v3] "r"(v3), [v4] "r"(v4)
74 v3
81 unsigned long *v3, unsigned long *v4, global() variable
[all...]
/kernel/linux/linux-6.6/arch/loongarch/lib/
H A Dxor_template.c38 const unsigned long * __restrict v3)
46 LD_AND_XOR_LINE(v3)
48 : : [v1] "r"(v1), [v2] "r"(v2), [v3] "r"(v3) : "memory"
53 v3 += LINE_WIDTH / sizeof(unsigned long);
60 const unsigned long * __restrict v3, variable
69 LD_AND_XOR_LINE(v3)
72 : : [v1] "r"(v1), [v2] "r"(v2), [v3] "r"(v3), [v4] "r"(v4)
78 v3
86 const unsigned long * __restrict v3, global() variable
[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
27 v3 = veorq_u64(vld1q_u64(dp1 + 6), vld1q_u64(dp2 + 6)); in xor_arm64_neon_2()
33 vst1q_u64(dp1 + 6, v3); in xor_arm64_neon_2()
47 register uint64x2_t v0, v1, v2, v3; in xor_arm64_neon_3() local
55 v3 = veorq_u64(vld1q_u64(dp1 + 6), vld1q_u64(dp2 + 6)); in xor_arm64_neon_3()
61 v3 = veorq_u64(v3, vld1q_u64(dp3 + 6)); in xor_arm64_neon_3()
67 vst1q_u64(dp1 + 6, v3); in xor_arm64_neon_3()
83 register uint64x2_t v0, v1, v2, v3; in xor_arm64_neon_4() local
91 v3 in xor_arm64_neon_4()
128 register uint64x2_t v0, v1, v2, v3; xor_arm64_neon_5() local
[all...]
/kernel/linux/linux-5.10/lib/
H A Dsiphash.c21 #define SIPROUND SIPHASH_PERMUTATION(v0, v1, v2, v3)
27 u64 v3 = SIPHASH_CONST_3; \
29 v3 ^= key->key[1]; \
35 v3 ^= b; \
44 return (v0 ^ v1) ^ (v2 ^ v3);
55 v3 ^= m; in __siphash_aligned()
88 v3 ^= m; in __siphash_unaligned()
120 v3 ^= first; in siphash_1u64()
137 v3 ^= first; in siphash_2u64()
141 v3 in siphash_2u64()
[all...]
H A Dxxhash.c112 uint32_t v3 = seed + 0; in xxh32() local
120 v3 = xxh32_round(v3, get_unaligned_le32(p)); in xxh32()
127 xxh_rotl32(v3, 12) + xxh_rotl32(v4, 18); in xxh32()
182 uint64_t v3 = seed + 0; in xxh64() local
190 v3 = xxh64_round(v3, get_unaligned_le64(p)); in xxh64()
197 xxh_rotl64(v3, 12) + xxh_rotl64(v4, 18); in xxh64()
200 h64 = xxh64_merge_round(h64, v3); in xxh64()
250 state.v3 in xxh32_reset()
310 uint32_t v3 = state->v3; xxh32_update() local
415 uint64_t v3 = state->v3; xxh64_update() local
454 const uint64_t v3 = state->v3; xxh64_digest() local
[all...]
H A Drandom32.c338 unsigned long v3; member
356 * - Rather than returning v0^v1^v2^v3, return v1+v3.
357 * If you look at the SipHash round, the last operation on v3 is
358 * "v3 ^= v0", so "v0 ^ v3" just undoes that, a waste of time.
366 unsigned long v0 = s->v0, v1 = s->v1, v2 = s->v2, v3 = s->v3; in siprand_u32() local
369 v3 ^= n; in siprand_u32()
370 PRND_SIPROUND(v0, v1, v2, v3); in siprand_u32()
441 unsigned long v2 = state->v2, v3 = state->v3; prandom_seed() local
465 unsigned long v0, v1, v2, v3; prandom_init_early() local
510 unsigned long v1 = get_random_long(), v3 = v1 ^ PRND_K1; prandom_reseed() local
[all...]
/kernel/linux/linux-6.6/lib/
H A Dsiphash.c20 #define SIPROUND SIPHASH_PERMUTATION(v0, v1, v2, v3)
26 u64 v3 = SIPHASH_CONST_3; \
28 v3 ^= key->key[1]; \
34 v3 ^= b; \
43 return (v0 ^ v1) ^ (v2 ^ v3);
54 v3 ^= m; in __siphash_aligned()
87 v3 ^= m; in __siphash_unaligned()
119 v3 ^= first; in siphash_1u64()
136 v3 ^= first; in siphash_2u64()
140 v3 in siphash_2u64()
[all...]
H A Dxxhash.c112 uint32_t v3 = seed + 0; in xxh32() local
120 v3 = xxh32_round(v3, get_unaligned_le32(p)); in xxh32()
127 xxh_rotl32(v3, 12) + xxh_rotl32(v4, 18); in xxh32()
182 uint64_t v3 = seed + 0; in xxh64() local
190 v3 = xxh64_round(v3, get_unaligned_le64(p)); in xxh64()
197 xxh_rotl64(v3, 12) + xxh_rotl64(v4, 18); in xxh64()
200 h64 = xxh64_merge_round(h64, v3); in xxh64()
250 state.v3 in xxh32_reset()
310 uint32_t v3 = state->v3; xxh32_update() local
415 uint64_t v3 = state->v3; xxh64_update() local
454 const uint64_t v3 = state->v3; xxh64_digest() local
[all...]
/kernel/linux/linux-5.10/drivers/char/mwave/
H A Dmwavedd.h89 #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,v3,v4,v5,v6); \
109 #define PRINTK_8(f,s,v1,v2,v3,v4,v5,v6,v7) \
111 printk(s,v1,v2,v3,v
[all...]
/kernel/linux/linux-6.6/drivers/char/mwave/
H A Dmwavedd.h89 #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,v3,v4,v5,v6); \
109 #define PRINTK_8(f,s,v1,v2,v3,v4,v5,v6,v7) \
111 printk(s,v1,v2,v3,v
[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
27 v3 = veorq_u64(vld1q_u64(dp1 + 6), vld1q_u64(dp2 + 6)); in xor_arm64_neon_2()
33 vst1q_u64(dp1 + 6, v3); in xor_arm64_neon_2()
48 register uint64x2_t v0, v1, v2, v3; in xor_arm64_neon_3() local
56 v3 = veorq_u64(vld1q_u64(dp1 + 6), vld1q_u64(dp2 + 6)); in xor_arm64_neon_3()
62 v3 = veorq_u64(v3, vld1q_u64(dp3 + 6)); in xor_arm64_neon_3()
68 vst1q_u64(dp1 + 6, v3); in xor_arm64_neon_3()
86 register uint64x2_t v0, v1, v2, v3; in xor_arm64_neon_4() local
94 v3 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-6.6/arch/s390/include/asm/
H A Dvx-insn-asm.h103 .ifc \vxr,%v3
200 * @v3: Third vector register designated operand
203 .macro RXB rxb v1 v2=0 v3=0 v4=0
211 .if \v3 & 0x10
224 * @v3: Third 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
239 * @v3: Third vector register designated operand (for RXB)
242 .macro MRXBOPC m opc v1 v2=0 v3=0 v4=0
243 MRXB \m, \v1, \v2, \v3, \v variable
350 VX_NUM v3, \\vr global() variable
371 VX_NUM v3, \\vto global() variable
391 VX_NUM v3, \\vto global() variable
402 VX_NUM v3, \\vr3 global() variable
431 VX_NUM v3, \\vr3 global() variable
440 VX_NUM v3, \\vr3 global() variable
462 VX_NUM v3, \\vr3 global() variable
484 VX_NUM v3, \\vr3 global() variable
509 VX_NUM v3, \\vr3 global() variable
519 VX_NUM v3, \\vr3 global() variable
529 VX_NUM v3, \\vr3 global() variable
551 VX_NUM v3, \\vr3 global() variable
574 VX_NUM v3, \\vr3 global() variable
604 VX_NUM v3, \\vr3 global() variable
629 VX_NUM v3, \\vr3 global() variable
651 VX_NUM v3, \\vr3 global() variable
674 VX_NUM v3, \\vr3 global() variable
[all...]
/kernel/linux/linux-5.10/arch/powerpc/lib/
H A Dxor_vmx.c75 DEFINE(v3); in __xor_altivec_3()
81 LOAD(v3); in __xor_altivec_3()
83 XOR(v1, v3); in __xor_altivec_3()
88 v3 += 4; in __xor_altivec_3()
98 DEFINE(v3); in __xor_altivec_4()
105 LOAD(v3); in __xor_altivec_4()
108 XOR(v3, v4); in __xor_altivec_4()
109 XOR(v1, v3); in __xor_altivec_4()
114 v3 += 4; in __xor_altivec_4()
125 DEFINE(v3); in __xor_altivec_5()
[all...]
/kernel/linux/linux-6.6/arch/powerpc/lib/
H A Dxor_vmx.c78 DEFINE(v3); in __xor_altivec_3()
84 LOAD(v3); in __xor_altivec_3()
86 XOR(v1, v3); in __xor_altivec_3()
91 v3 += 4; in __xor_altivec_3()
103 DEFINE(v3); in __xor_altivec_4()
110 LOAD(v3); in __xor_altivec_4()
113 XOR(v3, v4); in __xor_altivec_4()
114 XOR(v1, v3); in __xor_altivec_4()
119 v3 += 4; in __xor_altivec_4()
133 DEFINE(v3); in __xor_altivec_5()
[all...]
/kernel/linux/linux-5.10/arch/s390/include/asm/
H A Dvx-insn.h100 .ifc \vxr,%v3
197 * @v3: Third vector register designated operand
200 .macro RXB rxb v1 v2=0 v3=0 v4=0
208 .if \v3 & 0x10
221 * @v3: Third 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
236 * @v3: Third vector register designated operand (for RXB)
239 .macro MRXBOPC m opc v1 v2=0 v3=0 v4=0
240 MRXB \m, \v1, \v2, \v3, \v variable
347 VX_NUM v3, \\vr global() variable
368 VX_NUM v3, \\vto global() variable
378 VX_NUM v3, \\vto global() variable
389 VX_NUM v3, \\vr3 global() variable
421 VX_NUM v3, \\vr3 global() variable
431 VX_NUM v3, \\vr3 global() variable
441 VX_NUM v3, \\vr3 global() variable
463 VX_NUM v3, \\vr3 global() variable
486 VX_NUM v3, \\vr3 global() variable
516 VX_NUM v3, \\vr3 global() variable
541 VX_NUM v3, \\vr3 global() variable
[all...]
/kernel/linux/linux-5.10/include/pcmcia/
H A Ddevice_id.h34 #define PCMCIA_DEVICE_PROD_ID3(v3, vh3) { \
36 .prod_id = { NULL, NULL, (v3), NULL }, \
45 #define PCMCIA_DEVICE_PROD_ID13(v1, v3, vh1, vh3) { \
48 .prod_id = { (v1), NULL, (v3), NULL }, \
57 #define PCMCIA_DEVICE_PROD_ID123(v1, v2, v3, vh1, vh2, vh3) { \
61 .prod_id = { (v1), (v2), (v3), NULL },\
71 #define PCMCIA_DEVICE_PROD_ID134(v1, v3, v4, vh1, vh3, vh4) { \
75 .prod_id = { (v1), NULL, (v3), (v4) }, \
78 #define PCMCIA_DEVICE_PROD_ID1234(v1, v2, v3, v4, vh1, vh2, vh3, vh4) { \
83 .prod_id = { (v1), (v2), (v3), (v
[all...]
/kernel/linux/linux-6.6/include/pcmcia/
H A Ddevice_id.h34 #define PCMCIA_DEVICE_PROD_ID3(v3, vh3) { \
36 .prod_id = { NULL, NULL, (v3), NULL }, \
45 #define PCMCIA_DEVICE_PROD_ID13(v1, v3, vh1, vh3) { \
48 .prod_id = { (v1), NULL, (v3), NULL }, \
57 #define PCMCIA_DEVICE_PROD_ID123(v1, v2, v3, vh1, vh2, vh3) { \
61 .prod_id = { (v1), (v2), (v3), NULL },\
71 #define PCMCIA_DEVICE_PROD_ID134(v1, v3, v4, vh1, vh3, vh4) { \
75 .prod_id = { (v1), NULL, (v3), (v4) }, \
78 #define PCMCIA_DEVICE_PROD_ID1234(v1, v2, v3, v4, vh1, vh2, vh3, vh4) { \
83 .prod_id = { (v1), (v2), (v3), (v
[all...]
/kernel/linux/linux-6.6/arch/arm64/crypto/
H A Daes-modes.S26 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
62 ld1 {v0.16b-v3.16b}, [x1], #64 /* get 4 pt blocks */
66 st1 {v0.16b-v3.16b}, [x0], #64
92 ld1 {v0.16b-v3.16b}, [x1], #64 /* get 4 ct blocks */
96 st1 {v0.16b-v3.16b}, [x0], #64
143 ld1 {v0.16b-v3.16b}, [x1], #64 /* get 4 pt blocks */
150 eor v3
[all...]
H A Dsm4-ce-core.S64 sm4ekey v3.4s, v2.4s, v27.4s;
65 sm4ekey v4.4s, v3.4s, v28.4s;
73 st1 {v0.16b-v3.16b}, [x1], #64;
80 tbl v20.16b, {v3.16b}, v24.16b
121 ld1 {v0.16b-v3.16b}, [x2], #64;
124 SM4_CRYPT_BLK8(v0, v1, v2, v3, v4, v5, v6, v7);
126 st1 {v0.16b-v3.16b}, [x1], #64;
139 ld1 {v0.16b-v3.16b}, [x2], #64;
140 SM4_CRYPT_BLK4(v0, v1, v2, v3);
141 st1 {v0.16b-v3
[all...]
/kernel/linux/linux-5.10/drivers/gpu/drm/amd/amdgpu/
H A Datombios_crtc.c238 ENABLE_SPREAD_SPECTRUM_ON_PPLL_V3 v3; member
278 args.v3.usSpreadSpectrumAmountFrac = cpu_to_le16(0); in amdgpu_atombios_crtc_program_ss()
279 args.v3.ucSpreadSpectrumType = ss->type & ATOM_SS_CENTRE_SPREAD_MODE_MASK; in amdgpu_atombios_crtc_program_ss()
282 args.v3.ucSpreadSpectrumType |= ATOM_PPLL_SS_TYPE_V3_P1PLL; in amdgpu_atombios_crtc_program_ss()
285 args.v3.ucSpreadSpectrumType |= ATOM_PPLL_SS_TYPE_V3_P2PLL; in amdgpu_atombios_crtc_program_ss()
288 args.v3.ucSpreadSpectrumType |= ATOM_PPLL_SS_TYPE_V3_DCPLL; in amdgpu_atombios_crtc_program_ss()
293 args.v3.usSpreadSpectrumAmount = cpu_to_le16(ss->amount); in amdgpu_atombios_crtc_program_ss()
294 args.v3.usSpreadSpectrumStep = cpu_to_le16(ss->step); in amdgpu_atombios_crtc_program_ss()
295 args.v3.ucEnable = enable; in amdgpu_atombios_crtc_program_ss()
302 ADJUST_DISPLAY_PLL_PS_ALLOCATION_V3 v3; member
462 PIXEL_CLOCK_PARAMETERS_V3 v3; global() member
[all...]
/kernel/linux/linux-6.6/drivers/gpu/drm/amd/amdgpu/
H A Datombios_crtc.c237 ENABLE_SPREAD_SPECTRUM_ON_PPLL_V3 v3; member
277 args.v3.usSpreadSpectrumAmountFrac = cpu_to_le16(0); in amdgpu_atombios_crtc_program_ss()
278 args.v3.ucSpreadSpectrumType = ss->type & ATOM_SS_CENTRE_SPREAD_MODE_MASK; in amdgpu_atombios_crtc_program_ss()
281 args.v3.ucSpreadSpectrumType |= ATOM_PPLL_SS_TYPE_V3_P1PLL; in amdgpu_atombios_crtc_program_ss()
284 args.v3.ucSpreadSpectrumType |= ATOM_PPLL_SS_TYPE_V3_P2PLL; in amdgpu_atombios_crtc_program_ss()
287 args.v3.ucSpreadSpectrumType |= ATOM_PPLL_SS_TYPE_V3_DCPLL; in amdgpu_atombios_crtc_program_ss()
292 args.v3.usSpreadSpectrumAmount = cpu_to_le16(ss->amount); in amdgpu_atombios_crtc_program_ss()
293 args.v3.usSpreadSpectrumStep = cpu_to_le16(ss->step); in amdgpu_atombios_crtc_program_ss()
294 args.v3.ucEnable = enable; in amdgpu_atombios_crtc_program_ss()
301 ADJUST_DISPLAY_PLL_PS_ALLOCATION_V3 v3; member
461 PIXEL_CLOCK_PARAMETERS_V3 v3; global() member
[all...]
/kernel/linux/linux-5.10/drivers/gpu/drm/amd/display/dc/inc/
H A Dreg_helper.h72 #define REG_SET_3(reg, init_value, f1, v1, f2, v2, f3, v3) \
76 FN(reg, f3), v3)
78 #define REG_SET_4(reg, init_value, f1, v1, f2, v2, f3, v3, f4, v4) \
82 FN(reg, f3), v3,\
85 #define REG_SET_5(reg, init_value, f1, v1, f2, v2, f3, v3, f4, v4, \
90 FN(reg, f3), v3,\
94 #define REG_SET_6(reg, init_value, f1, v1, f2, v2, f3, v3, f4, v4, \
99 FN(reg, f3), v3,\
104 #define REG_SET_7(reg, init_value, f1, v1, f2, v2, f3, v3, f4, v4, \
109 FN(reg, f3), v3,\
[all...]
/kernel/linux/linux-6.6/drivers/gpu/drm/amd/display/dc/inc/
H A Dreg_helper.h72 #define REG_SET_3(reg, init_value, f1, v1, f2, v2, f3, v3) \
76 FN(reg, f3), v3)
78 #define REG_SET_4(reg, init_value, f1, v1, f2, v2, f3, v3, f4, v4) \
82 FN(reg, f3), v3,\
85 #define REG_SET_5(reg, init_value, f1, v1, f2, v2, f3, v3, f4, v4, \
90 FN(reg, f3), v3,\
94 #define REG_SET_6(reg, init_value, f1, v1, f2, v2, f3, v3, f4, v4, \
99 FN(reg, f3), v3,\
104 #define REG_SET_7(reg, init_value, f1, v1, f2, v2, f3, v3, f4, v4, \
109 FN(reg, f3), v3,\
[all...]

Completed in 14 milliseconds

12345678910>>...12