Home
last modified time | relevance | path

Searched refs:reg0 (Results 51 - 75 of 175) sorted by relevance

1234567

/kernel/linux/linux-6.6/drivers/media/dvb-frontends/
H A Dm88rs2000.c241 u8 reg0, reg1; in m88rs2000_send_diseqc_burst() local
245 reg0 = m88rs2000_readreg(state, 0xb1); in m88rs2000_send_diseqc_burst()
249 m88rs2000_writereg(state, 0xb1, reg0); in m88rs2000_send_diseqc_burst()
259 u8 reg0, reg1; in m88rs2000_set_tone() local
261 reg0 = m88rs2000_readreg(state, 0xb1); in m88rs2000_set_tone()
268 reg0 |= 0x4; in m88rs2000_set_tone()
269 reg0 &= 0xbc; in m88rs2000_set_tone()
278 m88rs2000_writereg(state, 0xb1, reg0); in m88rs2000_set_tone()
/kernel/linux/linux-5.10/drivers/media/cec/platform/meson/
H A Dao-cec-g12a.c229 u32 reg0, reg1; in meson_ao_cec_g12a_dualdiv_clk_recalc_rate() local
231 regmap_read(dualdiv_clk->regmap, CECB_CLK_CNTL_REG0, &reg0); in meson_ao_cec_g12a_dualdiv_clk_recalc_rate()
237 if (reg0 & CECB_CLK_CNTL_DUAL_EN) { in meson_ao_cec_g12a_dualdiv_clk_recalc_rate()
240 n1 = FIELD_GET(CECB_CLK_CNTL_N1, reg0) + 1; in meson_ao_cec_g12a_dualdiv_clk_recalc_rate()
241 n2 = FIELD_GET(CECB_CLK_CNTL_N2, reg0) + 1; in meson_ao_cec_g12a_dualdiv_clk_recalc_rate()
255 n1 = FIELD_GET(CECB_CLK_CNTL_N1, reg0) + 1; in meson_ao_cec_g12a_dualdiv_clk_recalc_rate()
/kernel/linux/linux-6.6/drivers/media/cec/platform/meson/
H A Dao-cec-g12a.c229 u32 reg0, reg1; in meson_ao_cec_g12a_dualdiv_clk_recalc_rate() local
231 regmap_read(dualdiv_clk->regmap, CECB_CLK_CNTL_REG0, &reg0); in meson_ao_cec_g12a_dualdiv_clk_recalc_rate()
237 if (reg0 & CECB_CLK_CNTL_DUAL_EN) { in meson_ao_cec_g12a_dualdiv_clk_recalc_rate()
240 n1 = FIELD_GET(CECB_CLK_CNTL_N1, reg0) + 1; in meson_ao_cec_g12a_dualdiv_clk_recalc_rate()
241 n2 = FIELD_GET(CECB_CLK_CNTL_N2, reg0) + 1; in meson_ao_cec_g12a_dualdiv_clk_recalc_rate()
255 n1 = FIELD_GET(CECB_CLK_CNTL_N1, reg0) + 1; in meson_ao_cec_g12a_dualdiv_clk_recalc_rate()
/kernel/linux/linux-5.10/drivers/gpu/drm/i915/display/
H A Dintel_gmbus.c598 intel_de_write_fw(dev_priv, GMBUS0, gmbus0_source | bus->reg0); in do_gmbus_xfer()
604 gmbus0_source | bus->reg0); in do_gmbus_xfer()
608 gmbus0_source | bus->reg0, 0); in do_gmbus_xfer()
694 bus->adapter.name, bus->reg0 & 0xff); in do_gmbus_xfer()
878 bus->reg0 = pin | GMBUS_RATE_100KHZ; in intel_gmbus_setup()
920 bus->reg0 = (bus->reg0 & ~(0x3 << 8)) | speed; in intel_gmbus_set_speed()
/kernel/linux/linux-5.10/drivers/net/ethernet/netronome/nfp/bpf/
H A Dverifier.c314 const struct bpf_reg_state *reg0 = cur_regs(env) + BPF_REG_0; in nfp_bpf_check_exit() local
320 if (!(reg0->type == SCALAR_VALUE && tnum_is_const(reg0->var_off))) { in nfp_bpf_check_exit()
323 tnum_strn(tn_buf, sizeof(tn_buf), reg0->var_off); in nfp_bpf_check_exit()
325 reg0->type, tn_buf); in nfp_bpf_check_exit()
329 imm = reg0->var_off.value; in nfp_bpf_check_exit()
335 reg0->type, imm); in nfp_bpf_check_exit()
/kernel/linux/linux-6.6/drivers/media/platform/ti/cal/
H A Dcal-camerarx.c135 unsigned int reg0, reg1; in cal_camerarx_config() local
148 reg0 = camerarx_read(phy, CAL_CSI2_PHY_REG0); in cal_camerarx_config()
149 cal_set_field(&reg0, CAL_CSI2_PHY_REG0_HSCLOCKCONFIG_DISABLE, in cal_camerarx_config()
151 cal_set_field(&reg0, ths_term, CAL_CSI2_PHY_REG0_THS_TERM_MASK); in cal_camerarx_config()
152 cal_set_field(&reg0, ths_settle, CAL_CSI2_PHY_REG0_THS_SETTLE_MASK); in cal_camerarx_config()
154 phy_dbg(1, phy, "CSI2_%d_REG0 = 0x%08x\n", phy->instance, reg0); in cal_camerarx_config()
155 camerarx_write(phy, CAL_CSI2_PHY_REG0, reg0); in cal_camerarx_config()
/kernel/linux/linux-6.6/drivers/net/ethernet/netronome/nfp/bpf/
H A Dverifier.c314 const struct bpf_reg_state *reg0 = cur_regs(env) + BPF_REG_0; in nfp_bpf_check_exit() local
320 if (!(reg0->type == SCALAR_VALUE && tnum_is_const(reg0->var_off))) { in nfp_bpf_check_exit()
323 tnum_strn(tn_buf, sizeof(tn_buf), reg0->var_off); in nfp_bpf_check_exit()
325 reg0->type, tn_buf); in nfp_bpf_check_exit()
329 imm = reg0->var_off.value; in nfp_bpf_check_exit()
335 reg0->type, imm); in nfp_bpf_check_exit()
/kernel/linux/linux-6.6/drivers/net/ethernet/marvell/octeon_ep/
H A Doctep_cn9k_pf.c382 u64 reg0; in octep_poll_non_ioq_interrupts_cn93_pf() local
385 reg0 = octep_read_csr64(oct, CN93_SDP_EPF_OEI_RINT); in octep_poll_non_ioq_interrupts_cn93_pf()
386 if (reg0) { in octep_poll_non_ioq_interrupts_cn93_pf()
389 reg0); in octep_poll_non_ioq_interrupts_cn93_pf()
390 octep_write_csr64(oct, CN93_SDP_EPF_OEI_RINT, reg0); in octep_poll_non_ioq_interrupts_cn93_pf()
391 if (reg0 & CN93_SDP_EPF_OEI_RINT_DATA_BIT_MBOX) in octep_poll_non_ioq_interrupts_cn93_pf()
393 else if (reg0 & CN93_SDP_EPF_OEI_RINT_DATA_BIT_HBEAT) in octep_poll_non_ioq_interrupts_cn93_pf()
/third_party/mesa3d/src/freedreno/decode/
H A Dcrashdec-mempool.c56 uint32_t reg0 : 18; in dump_mem_pool_chunk() member
68 dump_mem_pool_reg_write(fields.reg0, fields.data0, fields.reg0_context, in dump_mem_pool_chunk()
/third_party/ffmpeg/libavcodec/loongarch/
H A Dhevc_mc_bi_lsx.c64 __m128i reg0, reg1, reg2, reg3; in hevc_bi_copy_4w_lsx() local
68 reg0 = __lsx_vldrepl_w(src0_ptr, 0); in hevc_bi_copy_4w_lsx()
73 DUP2_ARG2(__lsx_vilvl_w, reg1, reg0, reg3, reg2, tmp0, tmp1); in hevc_bi_copy_4w_lsx()
75 reg0 = __lsx_vldrepl_w(src0_ptr, 0); in hevc_bi_copy_4w_lsx()
79 DUP2_ARG2(__lsx_vilvl_w, reg1, reg0, reg3, reg2, tmp0, tmp1); in hevc_bi_copy_4w_lsx()
112 reg0 = __lsx_vldrepl_w(src0_ptr, 0); in hevc_bi_copy_4w_lsx()
116 src0 = __lsx_vilvl_w(reg1, reg0); in hevc_bi_copy_4w_lsx()
150 __m128i reg0, reg1, reg2, reg3; in hevc_bi_copy_6w_lsx() local
153 reg0 = __lsx_vldrepl_d(src0_ptr, 0); in hevc_bi_copy_6w_lsx()
157 DUP2_ARG2(__lsx_vilvl_d, reg1, reg0, reg in hevc_bi_copy_6w_lsx()
246 __m128i reg0, reg1, reg2, reg3; hevc_bi_copy_8w_lsx() local
1507 __m128i reg0, reg1, reg2, reg3; hevc_hv_4t_6w_lsx() local
[all...]
H A Dvp9_mc_lsx.c457 __m128i reg0, reg1, reg2, reg3, reg4; in common_vt_8t_4w_lsx() local
474 DUP2_ARG2(__lsx_vilvl_d, tmp3, tmp0, tmp4, tmp1, reg0, reg1); in common_vt_8t_4w_lsx()
476 DUP2_ARG2(__lsx_vxori_b, reg0, 128, reg1, 128, reg0, reg1); in common_vt_8t_4w_lsx()
488 out0 = FILT_8TAP_DPADD_S_H(reg0, reg1, reg2, reg3, filter0, filter1, in common_vt_8t_4w_lsx()
503 reg0 = reg2; in common_vt_8t_4w_lsx()
517 __m128i reg0, reg1, reg2, reg3, reg4, reg5; in common_vt_8t_8w_lsx() local
541 reg0, reg1, reg2, reg3); in common_vt_8t_8w_lsx()
553 out0 = FILT_8TAP_DPADD_S_H(reg0, reg1, reg2, tmp0, filter0, filter1, in common_vt_8t_8w_lsx()
572 reg0 in common_vt_8t_8w_lsx()
589 __m128i reg0, reg1, reg2, reg3, reg4, reg5; common_vt_8t_16w_lsx() local
683 __m128i reg0, reg1, reg2, reg3, reg4, reg5; common_vt_8t_16w_mult_lsx() local
1543 __m128i reg0, reg1, reg2, reg3, reg4; common_vt_8t_and_aver_dst_4w_lsx() local
1619 __m128i reg0, reg1, reg2, reg3, reg4, reg5; common_vt_8t_and_aver_dst_8w_lsx() local
1705 __m128i reg0, reg1, reg2, reg3, reg4, reg5; common_vt_8t_and_aver_dst_16w_mult_lsx() local
[all...]
H A Dvc1dsp_lasx.c144 __m256i reg0, reg1, reg2, reg3; in ff_vc1_inv_trans_8x8_dc_lasx() local
161 const_dc, temp3, const_dc, reg0, reg1, reg2, reg3); in ff_vc1_inv_trans_8x8_dc_lasx()
162 DUP2_ARG3(__lasx_xvssrarni_bu_h, reg1, reg0, 0, reg3, reg2, 0, in ff_vc1_inv_trans_8x8_dc_lasx()
272 __m256i const_dc, temp0, temp1, reg0, reg1; in ff_vc1_inv_trans_8x4_dc_lasx() local
282 DUP2_ARG2(__lasx_xvadd_h, temp0, const_dc, temp1, const_dc, reg0, reg1); in ff_vc1_inv_trans_8x4_dc_lasx()
283 temp0 = __lasx_xvssrarni_bu_h(reg1, reg0, 0); in ff_vc1_inv_trans_8x4_dc_lasx()
298 __m256i const_dc, temp0, temp1, temp2, temp3, reg0, reg1; in ff_vc1_inv_trans_4x8_dc_lasx() local
311 DUP2_ARG2(__lasx_xvilvl_d, temp1, temp0, temp3, temp2, reg0, reg1); in ff_vc1_inv_trans_4x8_dc_lasx()
312 DUP2_ARG1(__lasx_vext2xv_hu_bu, reg0, reg1, temp0, temp1); in ff_vc1_inv_trans_4x8_dc_lasx()
313 DUP2_ARG2(__lasx_xvadd_h, temp0, const_dc, temp1, const_dc, reg0, reg in ff_vc1_inv_trans_4x8_dc_lasx()
[all...]
/kernel/linux/linux-5.10/drivers/net/ethernet/8390/
H A Dne2k-pci.c99 #define ne2k_flags reg0
232 int irq, reg0, chip_idx = ent->driver_data; in ne2k_pci_init_one() local
258 reg0 = inb(ioaddr); in ne2k_pci_init_one()
259 if (reg0 == 0xFF) in ne2k_pci_init_one()
273 outb(reg0, ioaddr); in ne2k_pci_init_one()
/kernel/linux/linux-6.6/drivers/net/ethernet/8390/
H A Dne2k-pci.c100 #define ne2k_flags reg0
233 int irq, reg0, chip_idx = ent->driver_data; in ne2k_pci_init_one() local
259 reg0 = inb(ioaddr); in ne2k_pci_init_one()
260 if (reg0 == 0xFF) in ne2k_pci_init_one()
274 outb(reg0, ioaddr); in ne2k_pci_init_one()
/third_party/mesa3d/src/panfrost/bifrost/
H A Ddisassemble.c59 return regs.reg0 | ((regs.reg1 & 0x1) << 5); in get_reg0()
61 return regs.reg0 <= regs.reg1 ? regs.reg0 : 63 - regs.reg0; in get_reg0()
66 return regs.reg0 <= regs.reg1 ? regs.reg1 : 63 - regs.reg1; in get_reg1()
/kernel/linux/linux-6.6/drivers/gpu/drm/i915/display/
H A Dintel_gmbus.c48 u32 reg0; member
636 intel_de_write_fw(i915, GMBUS0(i915), gmbus0_source | bus->reg0); in do_gmbus_xfer()
642 gmbus0_source | bus->reg0); in do_gmbus_xfer()
646 gmbus0_source | bus->reg0, 0); in do_gmbus_xfer()
732 bus->adapter.name, bus->reg0 & 0xff); in do_gmbus_xfer()
917 bus->reg0 = pin | GMBUS_RATE_100KHZ; in intel_gmbus_setup()
/kernel/linux/linux-5.10/drivers/net/ethernet/adaptec/
H A Dstarfire.c1063 u16 reg0; in check_duplex() local
1076 reg0 = mdio_read(dev, np->phys[0], MII_BMCR); in check_duplex()
1079 reg0 |= BMCR_ANENABLE | BMCR_ANRESTART; in check_duplex()
1081 reg0 &= ~(BMCR_ANENABLE | BMCR_ANRESTART); in check_duplex()
1083 reg0 |= BMCR_SPEED100; in check_duplex()
1085 reg0 |= BMCR_FULLDPLX; in check_duplex()
1091 mdio_write(dev, np->phys[0], MII_BMCR, reg0); in check_duplex()
1618 u16 reg0, reg1, reg4, reg5; in netdev_media_change() local
1626 reg0 = mdio_read(dev, np->phys[0], MII_BMCR); in netdev_media_change()
1631 if (reg0 in netdev_media_change()
[all...]
/kernel/linux/linux-6.6/drivers/net/ethernet/adaptec/
H A Dstarfire.c1065 u16 reg0; in check_duplex() local
1078 reg0 = mdio_read(dev, np->phys[0], MII_BMCR); in check_duplex()
1081 reg0 |= BMCR_ANENABLE | BMCR_ANRESTART; in check_duplex()
1083 reg0 &= ~(BMCR_ANENABLE | BMCR_ANRESTART); in check_duplex()
1085 reg0 |= BMCR_SPEED100; in check_duplex()
1087 reg0 |= BMCR_FULLDPLX; in check_duplex()
1093 mdio_write(dev, np->phys[0], MII_BMCR, reg0); in check_duplex()
1620 u16 reg0, reg1, reg4, reg5; in netdev_media_change() local
1628 reg0 = mdio_read(dev, np->phys[0], MII_BMCR); in netdev_media_change()
1633 if (reg0 in netdev_media_change()
[all...]
/third_party/backends/backend/
H A Dp5_device.c723 uint8_t reg0=0; in start_scan() local
779 reg0 = 0x00; in start_scan()
784 reg0 = 0x20; in start_scan()
788 reg0 = 0x40; in start_scan()
795 write_reg (dev->fd, REG0, reg0); in start_scan()
831 write_reg (dev->fd, REG0, reg0); in start_scan()
843 write_reg (dev->fd, REG0, reg0 | 0x0C); in start_scan()
/third_party/mesa3d/src/util/
H A Dregister_allocate.h66 unsigned int base_reg, unsigned int reg0, unsigned int reg1);
/kernel/linux/linux-6.6/drivers/net/ethernet/qlogic/qed/
H A Dqed_hsi.h653 __le32 reg0; member
777 __le32 reg0; member
1635 __le32 reg0; member
1673 __le32 reg0; member
3489 __le32 reg0; member
3662 __le32 reg0; member
3744 __le32 reg0; member
4611 __le32 reg0; member
4651 __le32 reg0; member
5559 __le32 reg0; member
5677 __le32 reg0; global() member
5752 __le32 reg0; global() member
6080 __le32 reg0; global() member
6442 __le32 reg0; global() member
6741 __le32 reg0; global() member
6833 __le32 reg0; global() member
7670 __le32 reg0; global() member
7710 __le32 reg0; global() member
7747 __le32 reg0; global() member
7784 __le32 reg0; global() member
8057 __le32 reg0; global() member
8126 __le32 reg0; global() member
8628 __le32 reg0; global() member
8672 __le32 reg0; global() member
8716 __le32 reg0; global() member
8971 __le32 reg0; global() member
9089 __le32 reg0; global() member
9459 __le32 reg0; global() member
9566 __le32 reg0; global() member
10082 __le32 reg0; global() member
10147 __le32 reg0; global() member
10216 __le32 reg0; global() member
10358 __le32 reg0; global() member
10607 __le32 reg0; global() member
10725 __le32 reg0; global() member
10800 __le32 reg0; global() member
10846 __le32 reg0; global() member
10922 __le32 reg0; global() member
[all...]
/kernel/linux/linux-5.10/arch/mips/include/asm/octeon/
H A Dcvmx-pko.h181 * The size of the reg0 operation - could be 8, 16,
197 /* The register, subtract will be done if reg0 is non-zero */
198 uint64_t reg0:11; member
255 uint64_t reg0:11;
/kernel/linux/linux-5.10/drivers/gpu/drm/amd/amdgpu/
H A Damdgpu_ring.c314 * @reg0: register to write
323 uint32_t reg0, uint32_t reg1, in amdgpu_ring_emit_reg_write_reg_wait_helper()
326 amdgpu_ring_emit_wreg(ring, reg0, ref); in amdgpu_ring_emit_reg_write_reg_wait_helper()
322 amdgpu_ring_emit_reg_write_reg_wait_helper(struct amdgpu_ring *ring, uint32_t reg0, uint32_t reg1, uint32_t ref, uint32_t mask) amdgpu_ring_emit_reg_write_reg_wait_helper() argument
/kernel/linux/linux-6.6/arch/mips/include/asm/octeon/
H A Dcvmx-pko.h181 * The size of the reg0 operation - could be 8, 16,
197 /* The register, subtract will be done if reg0 is non-zero */
198 uint64_t reg0:11; member
255 uint64_t reg0:11;
/kernel/linux/linux-6.6/drivers/gpu/drm/amd/amdgpu/
H A Damdgpu_mes.h286 uint32_t reg0; member
365 uint32_t reg0, uint32_t reg1,

Completed in 64 milliseconds

1234567