| /Linux-v6.1/arch/x86/lib/ |
| D | atomic64_386_32.S | 27 IRQ_SAVE v;
32 IRQ_RESTORE v; \
35 #define v %ecx macro
37 movl (v), %eax
38 movl 4(v), %edx
41 #undef v
43 #define v %esi macro
45 movl %ebx, (v)
46 movl %ecx, 4(v)
49 #undef v
[all …]
|
| /Linux-v6.1/sound/soc/fsl/ |
| D | fsl_easrc.h | 17 #define REG_EASRC_WRFIFO(ctx) (0x000 + 4 * (ctx))
19 #define REG_EASRC_RDFIFO(ctx) (0x010 + 4 * (ctx))
21 #define REG_EASRC_CC(ctx) (0x020 + 4 * (ctx))
23 #define REG_EASRC_CCE1(ctx) (0x030 + 4 * (ctx))
25 #define REG_EASRC_CCE2(ctx) (0x040 + 4 * (ctx))
27 #define REG_EASRC_CIA(ctx) (0x050 + 4 * (ctx))
29 #define REG_EASRC_DPCS0R0(ctx) (0x060 + 4 * (ctx))
30 #define REG_EASRC_DPCS0R1(ctx) (0x070 + 4 * (ctx))
31 #define REG_EASRC_DPCS0R2(ctx) (0x080 + 4 * (ctx))
32 #define REG_EASRC_DPCS0R3(ctx) (0x090 + 4 * (ctx))
[all …]
|
| /Linux-v6.1/lib/crypto/ |
| D | blake2s-generic.c | 21 { 0, 1, 2, 3, 4, 5, 6, 7, 8, 9, 10, 11, 12, 13, 14, 15 },
22 { 14, 10, 4, 8, 9, 15, 13, 6, 1, 12, 0, 2, 11, 7, 5, 3 },
23 { 11, 8, 12, 0, 5, 2, 15, 13, 10, 14, 3, 6, 7, 1, 9, 4 },
24 { 7, 9, 3, 1, 13, 12, 11, 14, 2, 6, 5, 10, 4, 0, 15, 8 },
25 { 9, 0, 5, 7, 2, 4, 10, 15, 14, 1, 11, 12, 6, 8, 3, 13 },
26 { 2, 12, 6, 10, 0, 11, 8, 3, 4, 13, 7, 5, 15, 14, 1, 9 },
27 { 12, 5, 1, 15, 14, 13, 4, 10, 0, 7, 6, 3, 9, 2, 8, 11 },
28 { 13, 11, 7, 14, 12, 1, 3, 9, 5, 0, 15, 4, 8, 6, 2, 10 },
29 { 6, 15, 14, 9, 11, 3, 0, 8, 12, 2, 13, 7, 1, 4, 10, 5 },
30 { 10, 2, 8, 4, 7, 6, 1, 5, 15, 11, 9, 14, 3, 12, 13, 0 },
[all …]
|
| /Linux-v6.1/arch/microblaze/lib/ |
| D | fastcopy.S | 43 addi r4, r0, 4 /* n = 4 */
51 /* n = 4 - n (yields 3, 2, 1 transfers for 1, 2, 3 addr offset) */
52 rsubi r4, r4, 4
81 lwi r10, r6, 4 /* t2 = *(s + 4) */
85 swi r10, r5, 4 /* *(d + 4) = t2 */
115 lwi r12, r8, 4 /* v = *(as + 4) */
116 bsrli r9, r12, 8 /* t1 = v >> 8 */
119 bslli r11, r12, 24 /* h = v << 24 */
120 lwi r12, r8, 8 /* v = *(as + 8) */
121 bsrli r9, r12, 8 /* t1 = v >> 8 */
[all …]
|
| /Linux-v6.1/Documentation/userspace-api/media/v4l/ |
| D | subdev-formats.rst | 123 :widths: 3 1 4
260 - 4
476 - r\ :sub:`4`
481 - g\ :sub:`4`
513 - b\ :sub:`4`
550 - b\ :sub:`4`
583 - r\ :sub:`4`
588 - g\ :sub:`4`
611 - r\ :sub:`4`
617 - g\ :sub:`4`
[all …]
|
| D | pixfmt-packed-hsv.rst | 14 The *saturation* (s) and the *value* (v) are measured in percentage of the
48 - 4
57 - 4
66 - 4
75 - 4
97 - h\ :sub:`4`
106 - s\ :sub:`4`
112 - v\ :sub:`7`
113 - v\ :sub:`6`
114 - v\ :sub:`5`
[all …]
|
| /Linux-v6.1/arch/powerpc/lib/ |
| D | xor_vmx.c | 24 #define DEFINE(V) \ argument
25 unative_t *V = (unative_t *)V##_in; \
26 unative_t V##_0, V##_1, V##_2, V##_3
28 #define LOAD(V) \ argument
30 V##_0 = V[0]; \
31 V##_1 = V[1]; \
32 V##_2 = V[2]; \
33 V##_3 = V[3]; \
36 #define STORE(V) \ argument
38 V[0] = V##_0; \
[all …]
|
| /Linux-v6.1/drivers/staging/media/sunxi/cedrus/ |
| D | cedrus_regs.h | 13 #define SHIFT_AND_MASK_BITS(v, h, l) \ argument
14 (((unsigned long)(v) << (l)) & GENMASK(h, l))
76 #define VE_PRIMARY_OUT_FMT_TILED_32_NV12 (0x00 << 4)
77 #define VE_PRIMARY_OUT_FMT_TILED_128_NV12 (0x01 << 4)
78 #define VE_PRIMARY_OUT_FMT_YU12 (0x02 << 4)
79 #define VE_PRIMARY_OUT_FMT_YV12 (0x03 << 4)
80 #define VE_PRIMARY_OUT_FMT_NV12 (0x04 << 4)
81 #define VE_PRIMARY_OUT_FMT_NV21 (0x05 << 4)
96 #define VE_DEC_MPEG_MP12HDR_F_CODE_SHIFT(x, y) (24 - 4 * (y) - 8 * (x))
104 #define VE_DEC_MPEG_MP12HDR_TOP_FIELD_FIRST(v) \ argument
[all …]
|
| /Linux-v6.1/arch/arm/crypto/ |
| D | blake2s-core.S | 29 ldr \b, [\src, #\offset + 4]
38 str \b, [\dst, #\offset + 4]
70 ldr M_0, [sp, #32 + 4 * \s0]
71 ldr M_1, [sp, #32 + 4 * \s2]
91 ldr M_0, [sp, #32 + 4 * \s1]
92 ldr M_1, [sp, #32 + 4 * \s3]
113 // Execute one round of BLAKE2s by updating the state matrix v[0..15]. v[0..9]
115 // spilling v[8..9], then to v[9..15], then to the message block. r10-r12 and
132 // (v[0], v[4], v[8], v[12]) and (v[1], v[5], v[9], v[13]).
133 __ldrd r10, r11, sp, 16 // load v[12] and v[13]
[all …]
|
| D | blake2b-neon-core.S | 47 .align 4
53 .byte 3, 4, 5, 6, 7, 0, 1, 2
55 .byte 2, 3, 4, 5, 6, 7, 0, 1
63 // Execute one round of BLAKE2b by updating the state matrix v[0..15] in the
73 // (v[0], v[4], v[8], v[12]), (v[1], v[5], v[9], v[13]),
74 // (v[2], v[6], v[10], v[14]), and (v[3], v[7], v[11], v[15]).
145 // (v[0], v[5], v[10], v[15]), (v[1], v[6], v[11], v[12]),
146 // (v[2], v[7], v[8], v[13]), and (v[3], v[4], v[9], v[14]).
260 vld1.64 {q2-q3}, [ip]! // Load h[4..7]
266 vld1.64 {q6-q7}, [r10] // Load IV[4..7]
[all …]
|
| /Linux-v6.1/drivers/mtd/nand/raw/ |
| D | nand_ids.c | 29 {"TC58NVG0S3E 1G 3.3V 8-bit",
32 {"TC58NVG2S0F 4G 3.3V 8-bit",
34 SZ_4K, SZ_512, SZ_256K, 0, 8, 224, NAND_ECC_INFO(4, SZ_512) },
35 {"TC58NVG2S0H 4G 3.3V 8-bit",
38 {"TC58NVG3S0F 8G 3.3V 8-bit",
40 SZ_4K, SZ_1K, SZ_256K, 0, 8, 232, NAND_ECC_INFO(4, SZ_512) },
41 {"TC58NVG5D2 32G 3.3V 8-bit",
44 {"TC58NVG6D2 64G 3.3V 8-bit",
47 {"SDTNRGAMA 64G 3.3V 8-bit",
50 {"H27UCG8T2ATR-BC 64G 3.3V 8-bit",
[all …]
|
| /Linux-v6.1/crypto/ |
| D | blake2b_generic.c | 26 { 0, 1, 2, 3, 4, 5, 6, 7, 8, 9, 10, 11, 12, 13, 14, 15 },
27 { 14, 10, 4, 8, 9, 15, 13, 6, 1, 12, 0, 2, 11, 7, 5, 3 },
28 { 11, 8, 12, 0, 5, 2, 15, 13, 10, 14, 3, 6, 7, 1, 9, 4 },
29 { 7, 9, 3, 1, 13, 12, 11, 14, 2, 6, 5, 10, 4, 0, 15, 8 },
30 { 9, 0, 5, 7, 2, 4, 10, 15, 14, 1, 11, 12, 6, 8, 3, 13 },
31 { 2, 12, 6, 10, 0, 11, 8, 3, 4, 13, 7, 5, 15, 14, 1, 9 },
32 { 12, 5, 1, 15, 14, 13, 4, 10, 0, 7, 6, 3, 9, 2, 8, 11 },
33 { 13, 11, 7, 14, 12, 1, 3, 9, 5, 0, 15, 4, 8, 6, 2, 10 },
34 { 6, 15, 14, 9, 11, 3, 0, 8, 12, 2, 13, 7, 1, 4, 10, 5 },
35 { 10, 2, 8, 4, 7, 6, 1, 5, 15, 11, 9, 14, 3, 12, 13, 0 },
[all …]
|
| D | aegis128-neon-inner.c | 25 uint8x16_t v[5]; member
43 vst1q_u8(state, st.v[0]); in aegis128_save_state_neon()
44 vst1q_u8(state + 16, st.v[1]); in aegis128_save_state_neon()
45 vst1q_u8(state + 32, st.v[2]); in aegis128_save_state_neon()
46 vst1q_u8(state + 48, st.v[3]); in aegis128_save_state_neon()
47 vst1q_u8(state + 64, st.v[4]); in aegis128_save_state_neon()
65 uint8x16_t v; in aegis_aes_round() local
72 v = vqtbl4q_u8(vld1q_u8_x4(crypto_aes_sbox), w); in aegis_aes_round()
73 v = vqtbx4q_u8(v, vld1q_u8_x4(crypto_aes_sbox + 0x40), w - 0x40); in aegis_aes_round()
74 v = vqtbx4q_u8(v, vld1q_u8_x4(crypto_aes_sbox + 0x80), w - 0x80); in aegis_aes_round()
[all …]
|
| /Linux-v6.1/drivers/media/platform/verisilicon/ |
| D | rockchip_vpu2_hw_h264_dec.c | 21 #define VDPU_SWREG(nr) ((nr) * 4)
28 #define VDPU_REG_DEC_E(v) ((v) ? BIT(0) : 0) argument
30 #define VDPU_REG_DEC_ADV_PRE_DIS(v) ((v) ? BIT(11) : 0) argument
31 #define VDPU_REG_DEC_SCMD_DIS(v) ((v) ? BIT(10) : 0) argument
32 #define VDPU_REG_FILTERING_DIS(v) ((v) ? BIT(8) : 0) argument
33 #define VDPU_REG_PIC_FIXED_QUANT(v) ((v) ? BIT(7) : 0) argument
34 #define VDPU_REG_DEC_LATENCY(v) (((v) << 1) & GENMASK(6, 1)) argument
36 #define VDPU_REG_INIT_QP(v) (((v) << 25) & GENMASK(30, 25)) argument
37 #define VDPU_REG_STREAM_LEN(v) (((v) << 0) & GENMASK(23, 0)) argument
39 #define VDPU_REG_APF_THRESHOLD(v) (((v) << 17) & GENMASK(30, 17)) argument
[all …]
|
| /Linux-v6.1/tools/testing/selftests/rseq/ |
| D | rseq-arm64.h | 42 case 4: \
58 #define rseq_smp_store_release(p, v) \ argument
64 : "r" ((__u8)v) \
70 : "r" ((__u16)v) \
73 case 4: \
76 : "r" ((__u32)v) \
82 : "r" ((__u64)v) \
208 int rseq_cmpeqv_storev(intptr_t *v, intptr_t expect, intptr_t newv, int cpu) in rseq_cmpeqv_storev() argument
213 RSEQ_ASM_DEFINE_TABLE(1, 2f, 3f, 4f) in rseq_cmpeqv_storev()
220 RSEQ_ASM_CMP_CPU_ID(cpu_id, current_cpu_id, 4f) in rseq_cmpeqv_storev()
[all …]
|
| D | rseq-riscv.h | 46 #define rseq_smp_store_release(p, v) \ argument
49 RSEQ_WRITE_ONCE(*(p), v); \
95 ".balign 4\n" \
173 int rseq_cmpeqv_storev(intptr_t *v, intptr_t expect, intptr_t newv, int cpu) in rseq_cmpeqv_storev() argument
177 __asm__ __volatile__ goto(RSEQ_ASM_DEFINE_TABLE(1, 2f, 3f, 4f) in rseq_cmpeqv_storev()
184 RSEQ_ASM_CMP_CPU_ID(cpu_id, current_cpu_id, 4f) in rseq_cmpeqv_storev()
186 RSEQ_ASM_OP_CMPEQ(v, expect, "%l[cmpfail]") in rseq_cmpeqv_storev()
187 RSEQ_INJECT_ASM(4) in rseq_cmpeqv_storev()
190 RSEQ_ASM_OP_CMPEQ(v, expect, "%l[error2]") in rseq_cmpeqv_storev()
192 RSEQ_ASM_OP_FINAL_STORE(newv, v, 3) in rseq_cmpeqv_storev()
[all …]
|
| D | rseq-mips.h | 57 #define rseq_smp_store_release(p, v) \ argument
60 RSEQ_WRITE_ONCE(*p, v); \
123 LONG_LA " $4, " __rseq_str(cs_label) "\n\t" \
124 LONG_S " $4, %[" __rseq_str(rseq_cs) "]\n\t" \
129 "lw $4, %[" __rseq_str(current_cpu_id) "]\n\t" \
130 "bne $4, %[" __rseq_str(cpu_id) "], " __rseq_str(label) "\n\t"
158 int rseq_cmpeqv_storev(intptr_t *v, intptr_t expect, intptr_t newv, int cpu) in rseq_cmpeqv_storev() argument
163 RSEQ_ASM_DEFINE_TABLE(9, 1f, 2f, 4f) /* start, commit, abort */ in rseq_cmpeqv_storev()
171 RSEQ_ASM_CMP_CPU_ID(cpu_id, current_cpu_id, 4f) in rseq_cmpeqv_storev()
173 LONG_L " $4, %[v]\n\t" in rseq_cmpeqv_storev()
[all …]
|
| D | rseq-x86.h | 26 #define RSEQ_CPU_ID_OFFSET 4
47 #define rseq_smp_store_release(p, v) \ argument
50 RSEQ_WRITE_ONCE(*p, v); \
116 int rseq_cmpeqv_storev(intptr_t *v, intptr_t expect, intptr_t newv, int cpu) in rseq_cmpeqv_storev() argument
121 RSEQ_ASM_DEFINE_TABLE(3, 1f, 2f, 4f) /* start, commit, abort */ in rseq_cmpeqv_storev()
129 RSEQ_ASM_CMP_CPU_ID(cpu_id, RSEQ_ASM_TP_SEGMENT:RSEQ_CPU_ID_OFFSET(%[rseq_offset]), 4f) in rseq_cmpeqv_storev()
131 "cmpq %[v], %[expect]\n\t" in rseq_cmpeqv_storev()
133 RSEQ_INJECT_ASM(4) in rseq_cmpeqv_storev()
136 "cmpq %[v], %[expect]\n\t" in rseq_cmpeqv_storev()
140 "movq %[newv], %[v]\n\t" in rseq_cmpeqv_storev()
[all …]
|
| D | rseq-ppc.h | 33 #define rseq_smp_store_release(p, v) \ argument
36 RSEQ_WRITE_ONCE(*p, v); \
213 int rseq_cmpeqv_storev(intptr_t *v, intptr_t expect, intptr_t newv, int cpu) in rseq_cmpeqv_storev() argument
218 RSEQ_ASM_DEFINE_TABLE(3, 1f, 2f, 4f) /* start, commit, abort */ in rseq_cmpeqv_storev()
227 RSEQ_ASM_CMP_CPU_ID(cpu_id, current_cpu_id, 4f) in rseq_cmpeqv_storev()
229 /* cmp @v equal to @expect */ in rseq_cmpeqv_storev()
230 RSEQ_ASM_OP_CMPEQ(v, expect, %l[cmpfail]) in rseq_cmpeqv_storev()
231 RSEQ_INJECT_ASM(4) in rseq_cmpeqv_storev()
235 /* cmp @v equal to @expect */ in rseq_cmpeqv_storev()
236 RSEQ_ASM_OP_CMPEQ(v, expect, %l[error2]) in rseq_cmpeqv_storev()
[all …]
|
| D | rseq-s390.h | 25 #define rseq_smp_store_release(p, v) \ argument
28 RSEQ_WRITE_ONCE(*p, v); \
138 int rseq_cmpeqv_storev(intptr_t *v, intptr_t expect, intptr_t newv, int cpu) in rseq_cmpeqv_storev() argument
143 RSEQ_ASM_DEFINE_TABLE(3, 1f, 2f, 4f) /* start, commit, abort */ in rseq_cmpeqv_storev()
151 RSEQ_ASM_CMP_CPU_ID(cpu_id, current_cpu_id, 4f) in rseq_cmpeqv_storev()
153 LONG_CMP " %[expect], %[v]\n\t" in rseq_cmpeqv_storev()
155 RSEQ_INJECT_ASM(4) in rseq_cmpeqv_storev()
158 LONG_CMP " %[expect], %[v]\n\t" in rseq_cmpeqv_storev()
162 LONG_S " %[newv], %[v]\n\t" in rseq_cmpeqv_storev()
165 RSEQ_ASM_DEFINE_ABORT(4, "", abort) in rseq_cmpeqv_storev()
[all …]
|
| D | rseq-arm.h | 76 #define rseq_smp_store_release(p, v) \ argument
79 RSEQ_WRITE_ONCE(*p, v); \
151 int rseq_cmpeqv_storev(intptr_t *v, intptr_t expect, intptr_t newv, int cpu) in rseq_cmpeqv_storev() argument
156 RSEQ_ASM_DEFINE_TABLE(9, 1f, 2f, 4f) /* start, commit, abort */ in rseq_cmpeqv_storev()
164 RSEQ_ASM_CMP_CPU_ID(cpu_id, current_cpu_id, 4f) in rseq_cmpeqv_storev()
166 "ldr r0, %[v]\n\t" in rseq_cmpeqv_storev()
169 RSEQ_INJECT_ASM(4) in rseq_cmpeqv_storev()
172 "ldr r0, %[v]\n\t" in rseq_cmpeqv_storev()
177 "str %[newv], %[v]\n\t" in rseq_cmpeqv_storev()
181 RSEQ_ASM_DEFINE_ABORT(3, 4, "", abort, 1b, 2b, 4f) in rseq_cmpeqv_storev()
[all …]
|
| /Linux-v6.1/drivers/gpu/drm/msm/disp/dpu1/ |
| D | msm_media_info.h | 20 * YUV 4:2:0 image with a plane of 8 bit Y samples followed
21 * by an interleaved U/V plane containing 8 bit 2x2 subsampled
33 * Y Y Y Y Y Y Y Y Y Y Y Y . . . . V |
37 * . . . . . . . . . . . . . . . . V
38 * U V U V U V U V U V U V . . . . ^
39 * U V U V U V U V U V U V . . . . |
40 * U V U V U V U V U V U V . . . . |
41 * U V U V U V U V U V U V . . . . UV_Scanlines
43 * . . . . . . . . . . . . . . . . V
58 * YUV 4:2:0 image with a plane of 8 bit Y samples followed
[all …]
|
| /Linux-v6.1/sound/soc/codecs/ |
| D | cs43130.h | 46 #define CS43130_PLL_SET_4 0x030004 /* PLL Setting 4 */
120 #define CS43130_INT_STATUS_4 0x0F0003 /* Interrupt Status 4 */
125 #define CS43130_INT_MASK_4 0x0F0013 /* Interrupt Mask 4 */
149 #define CS43130_XTAL_RDY_INT_SHIFT 4
164 #define CS43130_HPLOAD_OOR_INT_SHIFT 4
177 #define CS43130_HPLOAD_CHN_SEL_SHIFT 4
203 #define CS43130_SP_STP_SHIFT 4
209 #define CS43130_SP_MODE_SHIFT 4
227 #define CS43130_PDN_HP_SHIFT 4
305 #define CS43130_DSD_EN_SHIFT 4
[all …]
|
| /Linux-v6.1/arch/arm/include/asm/ |
| D | atomic.h | 25 #define arch_atomic_read(v) READ_ONCE((v)->counter) argument
26 #define arch_atomic_set(v,i) WRITE_ONCE(((v)->counter), (i)) argument
37 static inline void arch_atomic_##op(int i, atomic_t *v) \
42 prefetchw(&v->counter); \
45 " " #asm_op " %0, %0, %4\n" \
49 : "=&r" (result), "=&r" (tmp), "+Qo" (v->counter) \
50 : "r" (&v->counter), "Ir" (i) \
55 static inline int arch_atomic_##op##_return_relaxed(int i, atomic_t *v) \
60 prefetchw(&v->counter); \
64 " " #asm_op " %0, %0, %4\n" \
[all …]
|
| /Linux-v6.1/tools/perf/util/arm-spe-decoder/ |
| D | arm-spe-pkt-decoder.h | 71 #define SPE_ADDR_PKT_ADDR_GET_BYTES_0_6(v) ((v) & GENMASK_ULL(55, 0)) argument
72 #define SPE_ADDR_PKT_ADDR_GET_BYTE_6(v) (((v) & GENMASK_ULL(55, 48)) >> 48) argument
74 #define SPE_ADDR_PKT_GET_NS(v) (((v) & BIT_ULL(63)) >> 63) argument
75 #define SPE_ADDR_PKT_GET_EL(v) (((v) & GENMASK_ULL(62, 61)) >> 61) argument
76 #define SPE_ADDR_PKT_GET_CH(v) (((v) & BIT_ULL(62)) >> 62) argument
77 #define SPE_ADDR_PKT_GET_PAT(v) (((v) & GENMASK_ULL(59, 56)) >> 56) argument
98 EV_TLB_ACCESS = 4,
116 #define SPE_OP_PKT_IS_OTHER_SVE_OP(v) (((v) & (BIT(7) | BIT(3) | BIT(0))) == 0x8) argument
120 #define SPE_OP_PKT_LDST_SUBCLASS_GET(v) ((v) & GENMASK_ULL(7, 1)) argument
126 #define SPE_OP_PKT_IS_LDST_ATOMIC(v) (((v) & (GENMASK_ULL(7, 5) | BIT(1))) == 0x2) argument
[all …]
|
