| /linux-5.10/arch/powerpc/include/asm/ |
| D | atomic.h | 25 static __inline__ int atomic_read(const atomic_t *v) in atomic_read() argument
29 __asm__ __volatile__("lwz%U1%X1 %0,%1" : "=r"(t) : "m"(v->counter)); in atomic_read()
34 static __inline__ void atomic_set(atomic_t *v, int i) in atomic_set() argument
36 __asm__ __volatile__("stw%U0%X0 %1,%0" : "=m"(v->counter) : "r"(i)); in atomic_set()
40 static __inline__ void atomic_##op(int a, atomic_t *v) \
46 #asm_op " %0,%2,%0\n" \
49 : "=&r" (t), "+m" (v->counter) \
50 : "r" (a), "r" (&v->counter) \
55 static inline int atomic_##op##_return_relaxed(int a, atomic_t *v) \
61 #asm_op " %0,%2,%0\n" \
[all …]
|
| /linux-5.10/drivers/gpu/drm/amd/display/dc/dml/dcn30/ |
| D | display_mode_vba_30.c | 425 double RequiredDPPCLK[][2][DC__NUM_DPP__MAX],
426 double RequiredDISPCLK[][2],
428 unsigned int NoOfDPP[][2][DC__NUM_DPP__MAX],
429 double ProjectedDCFCLKDeepSleep[][2],
430 double MaximumVStartup[][2][DC__NUM_DPP__MAX],
431 double TotalVActivePixelBandwidth[][2],
432 double TotalVActiveCursorBandwidth[][2],
433 double TotalMetaRowBandwidth[][2],
434 double TotalDPTERowBandwidth[][2],
435 unsigned int TotalNumberOfActiveDPP[][2],
[all …]
|
| /linux-5.10/drivers/media/dvb-frontends/ |
| D | mb86a16.c | 40 #define MB86A16_INFO 2
71 .len = 2 in mb86a16_write()
102 ret = i2c_transfer(state->i2c_adap, msg, 2); in mb86a16_read()
103 if (ret != 2) { in mb86a16_read()
123 val = (timint1 << 4) | (timint2 << 2) | cnext; in CNTM_set()
141 tmp = (8192 * state->master_clk - 2 * m * rate * 8192 + state->master_clk / 2) / state->master_clk; in smrt_set()
146 if (mb86a16_write(state, MB86A16_SRATE1, (state->deci << 2) | in smrt_set()
292 val = 0x7a | (cren << 7) | (afcen << 2); in EN_set()
313 AFCA = 2; in AFCEXEN_set()
317 if (mb86a16_write(state, 0x2a, 0x02 | (afcexen << 5) | (AFCA << 2)) < 0) in AFCEXEN_set()
[all …]
|
| /linux-5.10/arch/alpha/include/asm/ |
| D | atomic.h | 29 #define atomic_read(v) READ_ONCE((v)->counter) argument
30 #define atomic64_read(v) READ_ONCE((v)->counter) argument
32 #define atomic_set(v,i) WRITE_ONCE((v)->counter, (i)) argument
33 #define atomic64_set(v,i) WRITE_ONCE((v)->counter, (i)) argument
42 static __inline__ void atomic_##op(int i, atomic_t * v) \
47 " " #asm_op " %0,%2,%0\n" \
49 " beq %0,2f\n" \
50 ".subsection 2\n" \
51 "2: br 1b\n" \
53 :"=&r" (temp), "=m" (v->counter) \
[all …]
|
| /linux-5.10/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-5.10/Documentation/userspace-api/media/v4l/ |
| D | subdev-formats.rst | 15 :widths: 1 1 2
179 1 and 2.
195 green and 5-bit blue values padded on the high bit, transferred as 2
215 \setlength{\tabcolsep}{2pt}
218 :header-rows: 2
220 :widths: 36 7 3 2 2 2 2 2 2 2 2 2 2 2 2 2 2 2 2 2 2 2 2 2 2 2 2 2 2 2 2 2 2 2 2
258 - 2
287 - r\ :sub:`2`
291 - g\ :sub:`2`
295 - b\ :sub:`2`
[all …]
|
| /linux-5.10/drivers/iommu/ |
| D | msm_iommu_hw-8xxx.h | 20 #define SET_GLOBAL_REG_N(b, n, r, v) SET_GLOBAL_REG(b, ((r) + (n << 2)), (v)) argument
21 #define GET_GLOBAL_REG_N(b, n, r) GET_GLOBAL_REG(b, ((r) + (n << 2)))
28 #define SET_GLOBAL_FIELD(b, r, F, v) \ argument
29 SET_FIELD(((b) + (r)), F##_MASK, F##_SHIFT, (v))
30 #define SET_CONTEXT_FIELD(b, c, r, F, v) \ argument
31 SET_FIELD(((b) + (r) + ((c) << CTX_SHIFT)), F##_MASK, F##_SHIFT, (v))
35 #define SET_FIELD(addr, mask, shift, v) \ argument
38 writel((t & ~((mask) << (shift))) + (((v) & (mask)) << (shift)), addr);\
49 #define FL_TYPE_SECT (2 << 0)
54 #define FL_BUFFERABLE (1 << 2)
[all …]
|
| /linux-5.10/tools/testing/selftests/net/forwarding/ |
| D | ip6gre_inner_v6_multipath.sh | 13 # | 2001:db8:1::2/64 | |
23 # | rem=2001:db8:40::2 --. |
25 # | v |
33 # | 2001:db8:80::2/64 |
46 # | | 2001:db8:81::2/64 | 2001:db8:82::2/64 |
52 # | 2001:db8:83::2/64 | SW3 |
59 # | loc=2001:db8:40::2 | |
64 # | 2001:db8:2::1/64 | SW4 |
70 # | 2001:db8:2::2/64 H2 |
83 simple_if_init $h1 2001:db8:1::2/64
[all …]
|
| D | gre_inner_v6_multipath.sh | 13 # | 2001:db8:1::2/64 | |
25 # | v |
65 # | 2001:db8:2::1/64 | SW4 |
71 # | 2001:db8:2::2/64 H2 |
84 simple_if_init $h1 2001:db8:1::2/64
85 ip -6 route add vrf v$h1 2001:db8:2::/64 via 2001:db8:1::1
90 ip -6 route del vrf v$h1 2001:db8:2::/64 via 2001:db8:1::1
91 simple_if_fini $h1 2001:db8:1::2/64
97 __simple_if_init $ul1 v$ol1 192.0.2.129/28
99 tunnel_create g1 gre 192.0.2.65 192.0.2.66 tos inherit dev v$ol1
[all …]
|
| D | ip6gre_inner_v4_multipath.sh | 13 # | 192.0.3.{2-62}/24 | |
23 # | rem=2001:db8:40::2 --. |
25 # | v |
33 # | 2001:db8:80::2/64 |
46 # | | 2001:db8:81::2/64 | 2001:db8:82::2/64 |
52 # | 2001:db8:83::2/64 | SW3 |
59 # | loc=2001:db8:40::2 | |
70 # | 192.0.4.{2-62}/24 H2 |
84 ip route add vrf v$h1 192.0.4.0/24 via 192.0.3.1
89 ip route del vrf v$h1 192.0.4.0/24 via 192.0.3.1
[all …]
|
| /linux-5.10/Documentation/hwmon/ |
| D | mc13783-adc.rst | 47 0 Battery Voltage (BATT) 2.50 - 4.65V -2.40V
49 2 Application Supply (BP) 2.50 - 4.65V -2.40V
50 3 Charger Voltage (CHRGRAW) 0 - 10V / /5
51 0 - 20V /10
52 4 Charger Current (CHRGISNSP-CHRGISNSN) -0.25 - 0.25V x4
53 5 General Purpose ADIN5 / Battery Pack Thermistor 0 - 2.30V No
54 6 General Purpose ADIN6 / Backup Voltage (LICELL) 0 - 2.30V / No /
55 1.50 - 3.50V -1.20V
56 7 General Purpose ADIN7 / UID / Die Temperature 0 - 2.30V / No /
57 0 - 2.55V / x0.9 / No
[all …]
|
| D | dme1737.rst | 64 temp[1-3] (2 remote diodes and 1 internal), 8 voltages in[0-7] (7 external and
69 For the DME1737, A8000 and SCH5027, fan[1-2] and pwm[1-2] are always present.
94 in0: +5VTR (+5V standby) 0V - 6.64V
95 in1: Vccp (processor core) 0V - 3V
96 in2: VCC (internal +3.3V) 0V - 4.38V
97 in3: +5V 0V - 6.64V
98 in4: +12V 0V - 16V
99 in5: VTR (+3.3V standby) 0V - 4.38V
100 in6: Vbat (+3.0V) 0V - 4.38V
104 in0: +2.5V 0V - 3.32V
[all …]
|
| /linux-5.10/arch/arm/include/asm/ |
| D | atomic.h | 25 #define atomic_read(v) READ_ONCE((v)->counter) argument
26 #define atomic_set(v,i) WRITE_ONCE(((v)->counter), (i)) argument
37 static inline void atomic_##op(int i, atomic_t *v) \
42 prefetchw(&v->counter); \
49 : "=&r" (result), "=&r" (tmp), "+Qo" (v->counter) \
50 : "r" (&v->counter), "Ir" (i) \
55 static inline int atomic_##op##_return_relaxed(int i, atomic_t *v) \
60 prefetchw(&v->counter); \
68 : "=&r" (result), "=&r" (tmp), "+Qo" (v->counter) \
69 : "r" (&v->counter), "Ir" (i) \
[all …]
|
| /linux-5.10/arch/m68k/include/asm/ |
| D | atomic.h | 19 #define atomic_read(v) READ_ONCE((v)->counter) argument
20 #define atomic_set(v, i) WRITE_ONCE(((v)->counter), (i)) argument
33 static inline void atomic_##op(int i, atomic_t *v) \
35 __asm__ __volatile__(#asm_op "l %1,%0" : "+m" (*v) : ASM_DI (i));\
41 static inline int atomic_##op##_return(int i, atomic_t *v) \
46 "1: movel %2,%1\n" \
48 " casl %2,%1,%0\n" \
50 : "+m" (*v), "=&d" (t), "=&d" (tmp) \
51 : "g" (i), "2" (atomic_read(v))); \
56 static inline int atomic_fetch_##op(int i, atomic_t *v) \
[all …]
|
| /linux-5.10/tools/testing/selftests/rseq/ |
| D | rseq-arm64.h | 37 case 2: \
58 #define rseq_smp_store_release(p, v) \ argument
64 : "r" ((__u8)v) \
67 case 2: \
70 : "r" ((__u16)v) \
76 : "r" ((__u32)v) \
82 : "r" ((__u64)v) \
175 RSEQ_INJECT_ASM(2) \
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()
[all …]
|
| /linux-5.10/drivers/iio/adc/ |
| D | stm32-dfsdm.h | 31 * | 0x300 | FILTER 2 |
48 #define DFSDM_CHCFGR1_SITP(v) FIELD_PREP(DFSDM_CHCFGR1_SITP_MASK, v) argument
49 #define DFSDM_CHCFGR1_SPICKSEL_MASK GENMASK(3, 2)
50 #define DFSDM_CHCFGR1_SPICKSEL(v) FIELD_PREP(DFSDM_CHCFGR1_SPICKSEL_MASK, v) argument
52 #define DFSDM_CHCFGR1_SCDEN(v) FIELD_PREP(DFSDM_CHCFGR1_SCDEN_MASK, v) argument
54 #define DFSDM_CHCFGR1_CKABEN(v) FIELD_PREP(DFSDM_CHCFGR1_CKABEN_MASK, v) argument
56 #define DFSDM_CHCFGR1_CHEN(v) FIELD_PREP(DFSDM_CHCFGR1_CHEN_MASK, v) argument
58 #define DFSDM_CHCFGR1_CHINSEL(v) FIELD_PREP(DFSDM_CHCFGR1_CHINSEL_MASK, v) argument
60 #define DFSDM_CHCFGR1_DATMPX(v) FIELD_PREP(DFSDM_CHCFGR1_DATMPX_MASK, v) argument
62 #define DFSDM_CHCFGR1_DATPACK(v) FIELD_PREP(DFSDM_CHCFGR1_DATPACK_MASK, v) argument
[all …]
|
| /linux-5.10/drivers/gpu/drm/arm/display/komeda/d71/ |
| D | d71_component.c | 79 addr = offset + (i << 2); in get_values_from_reg()
194 if (info->num_planes > 2) in d71_layer_update_fb()
195 malidp_write64(reg, BLK_P2_PTR_LOW, addr[2]); in d71_layer_update_fb()
288 u32 v[15], i; in d71_layer_dump() local
292 get_values_from_reg(c->reg, LAYER_INFO, 1, &v[14]); in d71_layer_dump()
293 if (v[14] & 0x1) { in d71_layer_dump()
301 rgb2rgb = !!(v[14] & L_INFO_CM); in d71_layer_dump()
305 seq_printf(sf, "%sLAYER_INFO:\t\t0x%X\n", prefix, v[14]); in d71_layer_dump()
307 get_values_from_reg(c->reg, 0xD0, 1, v); in d71_layer_dump()
308 seq_printf(sf, "%sCONTROL:\t\t0x%X\n", prefix, v[0]); in d71_layer_dump()
[all …]
|
| /linux-5.10/sound/pci/emu10k1/ |
| D | emu10k1_patch.c | 40 if (sp->v.size == 0) { in snd_emu10k1_sample_new()
42 "emu: rom font for sample %d\n", sp->v.sample); in snd_emu10k1_sample_new()
47 sp->v.end -= sp->v.start; in snd_emu10k1_sample_new()
48 sp->v.loopstart -= sp->v.start; in snd_emu10k1_sample_new()
49 sp->v.loopend -= sp->v.start; in snd_emu10k1_sample_new()
50 sp->v.start = 0; in snd_emu10k1_sample_new()
53 sampleend = sp->v.end; in snd_emu10k1_sample_new()
54 if (sampleend > sp->v.size) in snd_emu10k1_sample_new()
55 sampleend = sp->v.size; in snd_emu10k1_sample_new()
56 loopend = sp->v.loopend; in snd_emu10k1_sample_new()
[all …]
|
| /linux-5.10/arch/x86/lib/ |
| D | atomic64_386_32.S | 27 LOCK v;
32 UNLOCK v; \
39 #define v %ecx macro
41 movl (v), %eax
42 movl 4(v), %edx
44 #undef v
46 #define v %esi macro
48 movl %ebx, (v)
49 movl %ecx, 4(v)
51 #undef v
[all …]
|
| /linux-5.10/sound/soc/fsl/ |
| D | fsl_easrc.h | 24 /* ASRC Context Control Extended 2 */
70 /* ASRC Channel Status 2 */
100 #define EASRC_CC_FIFO_WTMK(v) (((v) << EASRC_CC_FIFO_WTMK_SHIFT) \ argument
106 #define EASRC_CC_SAMPLE_POS(v) (((v) << EASRC_CC_SAMPLE_POS_SHIFT) \ argument
112 #define EASRC_CC_BPS_WIDTH 2
115 #define EASRC_CC_BPS(v) (((v) << EASRC_CC_BPS_SHIFT) \ argument
127 #define EASRC_CC_CHEN(v) (((v) << EASRC_CC_CHEN_SHIFT) \ argument
141 #define EASRC_CCE1_PF_EXP(v) (((v) << EASRC_CCE1_PF_EXP_SHIFT) \ argument
161 #define EASRC_CCE1_RS_INIT_SHIFT 2
162 #define EASRC_CCE1_RS_INIT_WIDTH 2
[all …]
|
| /linux-5.10/crypto/ |
| D | blake2b_generic.c | 40 u64 t[2];
41 u64 f[2];
54 { 0, 1, 2, 3, 4, 5, 6, 7, 8, 9, 10, 11, 12, 13, 14, 15 },
55 { 14, 10, 4, 8, 9, 15, 13, 6, 1, 12, 0, 2, 11, 7, 5, 3 },
56 { 11, 8, 12, 0, 5, 2, 15, 13, 10, 14, 3, 6, 7, 1, 9, 4 },
57 { 7, 9, 3, 1, 13, 12, 11, 14, 2, 6, 5, 10, 4, 0, 15, 8 },
58 { 9, 0, 5, 7, 2, 4, 10, 15, 14, 1, 11, 12, 6, 8, 3, 13 },
59 { 2, 12, 6, 10, 0, 11, 8, 3, 4, 13, 7, 5, 15, 14, 1, 9 },
60 { 12, 5, 1, 15, 14, 13, 4, 10, 0, 7, 6, 3, 9, 2, 8, 11 },
61 { 13, 11, 7, 14, 12, 1, 3, 9, 5, 0, 15, 4, 8, 6, 2, 10 },
[all …]
|
| D | aegis128-neon-inner.c | 26 uint8x16_t v[5]; member
44 vst1q_u8(state, st.v[0]); in aegis128_save_state_neon()
45 vst1q_u8(state + 16, st.v[1]); in aegis128_save_state_neon()
46 vst1q_u8(state + 32, st.v[2]); in aegis128_save_state_neon()
47 vst1q_u8(state + 48, st.v[3]); in aegis128_save_state_neon()
48 vst1q_u8(state + 64, st.v[4]); in aegis128_save_state_neon()
66 uint8x16_t v; in aegis_aes_round() local
73 v = vqtbl4q_u8(vld1q_u8_x4(crypto_aes_sbox), w); in aegis_aes_round()
74 v = vqtbx4q_u8(v, vld1q_u8_x4(crypto_aes_sbox + 0x40), w - 0x40); in aegis_aes_round()
75 v = vqtbx4q_u8(v, vld1q_u8_x4(crypto_aes_sbox + 0x80), w - 0x80); in aegis_aes_round()
[all …]
|
| /linux-5.10/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
49 * UV_Scanlines: Height/2 aligned to 16
[all …]
|
| /linux-5.10/drivers/gpu/drm/amd/display/dc/calcs/ |
| D | dcn_calcs.c | 45 #define WM_C 2
111 .number_of_channels = 2,
132 .pte_chunk_size = 2, /*kbytes*/
133 .meta_chunk_size = 2, /*kbytes*/
134 .writeback_chunk_size = 2, /*kbytes*/
144 .max_num_writeback = 2,
146 .max_pscl_tolb_throughput = 2, /*pixels/dppclk*/
270 /* For 64bpp 2 high tiles */ in swizzle_mode_to_macro_tile_size()
368 input->src.viewport_width_c = input->src.viewport_width / 2; in pipe_ctx_to_e2e_pipe_params()
369 input->src.viewport_height_c = input->src.viewport_height / 2; in pipe_ctx_to_e2e_pipe_params()
[all …]
|
| /linux-5.10/sound/soc/qcom/ |
| D | lpass-lpaif-reg.h | 11 #define LPAIF_I2SCTL_REG_ADDR(v, addr, port) \ argument
12 (v->i2sctrl_reg_base + (addr) + v->i2sctrl_reg_stride * (port))
14 #define LPAIF_I2SCTL_REG(v, port) LPAIF_I2SCTL_REG_ADDR(v, 0x0, (port)) argument
24 #define LPAIF_I2SCTL_MODE_SD1 2
61 #define LPAIF_I2SCTL_BITWIDTH_32 2
71 #define LPAIF_IRQ_REG_ADDR(v, addr, port) \ argument
72 (v->irq_reg_base + (addr) + v->irq_reg_stride * (port))
76 #define LPAIF_IRQEN_REG(v, port) LPAIF_IRQ_REG_ADDR(v, 0x0, (port)) argument
77 #define LPAIF_IRQSTAT_REG(v, port) LPAIF_IRQ_REG_ADDR(v, 0x4, (port)) argument
78 #define LPAIF_IRQCLEAR_REG(v, port) LPAIF_IRQ_REG_ADDR(v, 0xC, (port)) argument
[all …]
|