Home
last modified time | relevance | path

Searched refs:wp (Results 1 – 168 of 168) sorted by relevance

/linux-4.1.27/drivers/video/fbdev/omap2/dss/
Dhdmi_wp.c22 void hdmi_wp_dump(struct hdmi_wp_data *wp, struct seq_file *s) in hdmi_wp_dump() argument
24 #define DUMPREG(r) seq_printf(s, "%-35s %08x\n", #r, hdmi_read_reg(wp->base, r)) in hdmi_wp_dump()
46 u32 hdmi_wp_get_irqstatus(struct hdmi_wp_data *wp) in hdmi_wp_get_irqstatus() argument
48 return hdmi_read_reg(wp->base, HDMI_WP_IRQSTATUS); in hdmi_wp_get_irqstatus()
51 void hdmi_wp_set_irqstatus(struct hdmi_wp_data *wp, u32 irqstatus) in hdmi_wp_set_irqstatus() argument
53 hdmi_write_reg(wp->base, HDMI_WP_IRQSTATUS, irqstatus); in hdmi_wp_set_irqstatus()
55 hdmi_read_reg(wp->base, HDMI_WP_IRQSTATUS); in hdmi_wp_set_irqstatus()
58 void hdmi_wp_set_irqenable(struct hdmi_wp_data *wp, u32 mask) in hdmi_wp_set_irqenable() argument
60 hdmi_write_reg(wp->base, HDMI_WP_IRQENABLE_SET, mask); in hdmi_wp_set_irqenable()
63 void hdmi_wp_clear_irqenable(struct hdmi_wp_data *wp, u32 mask) in hdmi_wp_clear_irqenable() argument
[all …]
Dhdmi.h243 struct hdmi_wp_data *wp; member
287 int hdmi_wp_video_start(struct hdmi_wp_data *wp);
288 void hdmi_wp_video_stop(struct hdmi_wp_data *wp);
289 void hdmi_wp_dump(struct hdmi_wp_data *wp, struct seq_file *s);
290 u32 hdmi_wp_get_irqstatus(struct hdmi_wp_data *wp);
291 void hdmi_wp_set_irqstatus(struct hdmi_wp_data *wp, u32 irqstatus);
292 void hdmi_wp_set_irqenable(struct hdmi_wp_data *wp, u32 mask);
293 void hdmi_wp_clear_irqenable(struct hdmi_wp_data *wp, u32 mask);
294 int hdmi_wp_set_phy_pwr(struct hdmi_wp_data *wp, enum hdmi_phy_pwr val);
295 int hdmi_wp_set_pll_pwr(struct hdmi_wp_data *wp, enum hdmi_pll_pwr val);
[all …]
Dhdmi5.c75 struct hdmi_wp_data *wp = data; in hdmi_irq_handler() local
78 irqstatus = hdmi_wp_get_irqstatus(wp); in hdmi_irq_handler()
79 hdmi_wp_set_irqstatus(wp, irqstatus); in hdmi_irq_handler()
91 hdmi_wp_set_phy_pwr(wp, HDMI_PHYPWRCMD_OFF); in hdmi_irq_handler()
103 hdmi_wp_set_irqstatus(wp, HDMI_IRQ_LINK_CONNECT | in hdmi_irq_handler()
106 hdmi_wp_set_phy_pwr(wp, HDMI_PHYPWRCMD_LDOON); in hdmi_irq_handler()
111 hdmi_wp_set_phy_pwr(wp, HDMI_PHYPWRCMD_TXON); in hdmi_irq_handler()
113 hdmi_wp_set_phy_pwr(wp, HDMI_PHYPWRCMD_LDOON); in hdmi_irq_handler()
198 hdmi_wp_clear_irqenable(&hdmi.wp, 0xffffffff); in hdmi_power_on_full()
199 hdmi_wp_set_irqstatus(&hdmi.wp, in hdmi_power_on_full()
[all …]
Dhdmi4.c71 struct hdmi_wp_data *wp = data; in hdmi_irq_handler() local
74 irqstatus = hdmi_wp_get_irqstatus(wp); in hdmi_irq_handler()
75 hdmi_wp_set_irqstatus(wp, irqstatus); in hdmi_irq_handler()
85 hdmi_wp_set_phy_pwr(wp, HDMI_PHYPWRCMD_OFF); in hdmi_irq_handler()
87 hdmi_wp_set_irqstatus(wp, HDMI_IRQ_LINK_CONNECT | in hdmi_irq_handler()
90 hdmi_wp_set_phy_pwr(wp, HDMI_PHYPWRCMD_LDOON); in hdmi_irq_handler()
92 hdmi_wp_set_phy_pwr(wp, HDMI_PHYPWRCMD_TXON); in hdmi_irq_handler()
94 hdmi_wp_set_phy_pwr(wp, HDMI_PHYPWRCMD_LDOON); in hdmi_irq_handler()
168 struct hdmi_wp_data *wp = &hdmi.wp; in hdmi_power_on_full() local
176 hdmi_wp_clear_irqenable(wp, 0xffffffff); in hdmi_power_on_full()
[all …]
Dhdmi_pll.c104 struct hdmi_wp_data *wp = pll->wp; in hdmi_pll_enable() local
109 r = hdmi_wp_set_pll_pwr(wp, HDMI_PLLPWRCMD_BOTHON_ALLCLKS); in hdmi_pll_enable()
119 struct hdmi_wp_data *wp = pll->wp; in hdmi_pll_disable() local
121 hdmi_wp_set_pll_pwr(wp, HDMI_PLLPWRCMD_ALLOFF); in hdmi_pll_disable()
222 struct hdmi_wp_data *wp) in hdmi_pll_init() argument
227 pll->wp = wp; in hdmi_pll_init()
Dhdmi4_core.h264 void hdmi4_configure(struct hdmi_core_data *core, struct hdmi_wp_data *wp,
269 int hdmi4_audio_start(struct hdmi_core_data *core, struct hdmi_wp_data *wp);
270 void hdmi4_audio_stop(struct hdmi_core_data *core, struct hdmi_wp_data *wp);
271 int hdmi4_audio_config(struct hdmi_core_data *core, struct hdmi_wp_data *wp,
Dhdmi4_core.c310 struct hdmi_wp_data *wp, struct hdmi_config *cfg) in hdmi4_configure() argument
323 hdmi_wp_video_config_timing(wp, &video_timing); in hdmi4_configure()
328 hdmi_wp_video_config_format(wp, &video_format); in hdmi4_configure()
330 hdmi_wp_video_config_interface(wp, &video_timing); in hdmi4_configure()
680 int hdmi4_audio_config(struct hdmi_core_data *core, struct hdmi_wp_data *wp, in hdmi4_audio_config() argument
847 hdmi_wp_audio_config_dma(wp, &audio_dma); in hdmi4_audio_config()
848 hdmi_wp_audio_config_format(wp, &audio_format); in hdmi4_audio_config()
859 int hdmi4_audio_start(struct hdmi_core_data *core, struct hdmi_wp_data *wp) in hdmi4_audio_start() argument
864 hdmi_wp_audio_core_req_enable(wp, true); in hdmi4_audio_start()
869 void hdmi4_audio_stop(struct hdmi_core_data *core, struct hdmi_wp_data *wp) in hdmi4_audio_stop() argument
[all …]
Dhdmi5_core.c600 void hdmi5_configure(struct hdmi_core_data *core, struct hdmi_wp_data *wp, in hdmi5_configure() argument
613 hdmi_wp_video_config_timing(wp, &video_timing); in hdmi5_configure()
618 hdmi_wp_video_config_format(wp, &video_format); in hdmi5_configure()
620 hdmi_wp_video_config_interface(wp, &video_timing); in hdmi5_configure()
796 int hdmi5_audio_config(struct hdmi_core_data *core, struct hdmi_wp_data *wp, in hdmi5_audio_config() argument
884 hdmi_wp_audio_config_dma(wp, &audio_dma); in hdmi5_audio_config()
885 hdmi_wp_audio_config_format(wp, &audio_format); in hdmi5_audio_config()
Dhdmi5_core.h298 void hdmi5_configure(struct hdmi_core_data *core, struct hdmi_wp_data *wp,
302 int hdmi5_audio_config(struct hdmi_core_data *core, struct hdmi_wp_data *wp,
/linux-4.1.27/arch/powerpc/math-emu/
Dmath_efp.c112 u32 wp[2]; member
203 vc.wp[0] = current->thread.evr[fc]; in do_spe_mathemu()
204 vc.wp[1] = regs->gpr[fc]; in do_spe_mathemu()
205 va.wp[0] = current->thread.evr[fa]; in do_spe_mathemu()
206 va.wp[1] = regs->gpr[fa]; in do_spe_mathemu()
207 vb.wp[0] = current->thread.evr[fb]; in do_spe_mathemu()
208 vb.wp[1] = regs->gpr[fb]; in do_spe_mathemu()
213 pr_debug("vc: %08x %08x\n", vc.wp[0], vc.wp[1]); in do_spe_mathemu()
214 pr_debug("va: %08x %08x\n", va.wp[0], va.wp[1]); in do_spe_mathemu()
215 pr_debug("vb: %08x %08x\n", vb.wp[0], vb.wp[1]); in do_spe_mathemu()
[all …]
/linux-4.1.27/lib/mpi/
Dgeneric_mpih-lshift.c41 mpihelp_lshift(mpi_ptr_t wp, mpi_ptr_t up, mpi_size_t usize, unsigned int cnt) in mpihelp_lshift() argument
49 wp += 1; in mpihelp_lshift()
57 wp[i] = (high_limb << sh_1) | (low_limb >> sh_2); in mpihelp_lshift()
60 wp[i] = high_limb << sh_1; in mpihelp_lshift()
Dgeneric_mpih-rshift.c42 mpihelp_rshift(mpi_ptr_t wp, mpi_ptr_t up, mpi_size_t usize, unsigned cnt) in mpihelp_rshift() argument
50 wp -= 1; in mpihelp_rshift()
57 wp[i] = (low_limb >> sh_1) | (high_limb << sh_2); in mpihelp_rshift()
60 wp[i] = low_limb >> sh_1; in mpihelp_rshift()
Dmpi-internal.h232 mpi_limb_t mpihelp_lshift(mpi_ptr_t wp, mpi_ptr_t up, mpi_size_t usize,
234 mpi_limb_t mpihelp_rshift(mpi_ptr_t wp, mpi_ptr_t up, mpi_size_t usize,
/linux-4.1.27/arch/ia64/kernel/
Dpatch.c147 u64 *wp; in ia64_patch_mckinley_e9() local
160 wp = (u64 *) ia64_imva((char *) offp + *offp); in ia64_patch_mckinley_e9()
161 wp[0] = 0x0000000100000011UL; /* nop.m 0; nop.i 0; br.ret.sptk.many b6 */ in ia64_patch_mckinley_e9()
162 wp[1] = 0x0084006880000200UL; in ia64_patch_mckinley_e9()
163 wp[2] = 0x0000000100000000UL; /* nop.m 0; nop.i 0; nop.i 0 */ in ia64_patch_mckinley_e9()
164 wp[3] = 0x0004000000000200UL; in ia64_patch_mckinley_e9()
165 ia64_fc(wp); ia64_fc(wp + 2); in ia64_patch_mckinley_e9()
/linux-4.1.27/sound/hda/
Dhdac_bus.c115 unsigned int wp; in snd_hdac_bus_queue_event() local
121 wp = (bus->unsol_wp + 1) % HDA_UNSOL_QUEUE_SIZE; in snd_hdac_bus_queue_event()
122 bus->unsol_wp = wp; in snd_hdac_bus_queue_event()
124 wp <<= 1; in snd_hdac_bus_queue_event()
125 bus->unsol_queue[wp] = res; in snd_hdac_bus_queue_event()
126 bus->unsol_queue[wp + 1] = res_ex; in snd_hdac_bus_queue_event()
/linux-4.1.27/lib/raid6/
Dint.uc88 unative_t wd$$, wq$$, wp$$, w1$$, w2$$;
95 wq$$ = wp$$ = *(unative_t *)&dptr[z0][d+$$*NSIZE];
98 wp$$ ^= wd$$;
105 *(unative_t *)&p[d+NSIZE*$$] = wp$$;
117 unative_t wd$$, wq$$, wp$$, w1$$, w2$$;
125 wq$$ = wp$$ = *(unative_t *)&dptr[z0][d+$$*NSIZE];
128 wp$$ ^= wd$$;
142 *(unative_t *)&p[d+NSIZE*$$] ^= wp$$;
Dtilegx.uc56 u64 wd$$, wq$$, wp$$, w1$$, w2$$;
66 wq$$ = wp$$ = *z0ptr++;
69 wp$$ = wp$$ ^ wd$$;
76 *p++ = wp$$;
Dneon.uc58 register unative_t wd$$, wq$$, wp$$, w1$$, w2$$;
66 wq$$ = wp$$ = vld1q_u8(&dptr[z0][d+$$*NSIZE]);
69 wp$$ = veorq_u8(wp$$, wd$$);
77 vst1q_u8(&p[d+NSIZE*$$], wp$$);
Daltivec.uc74 unative_t wd$$, wq$$, wp$$, w1$$, w2$$;
82 wq$$ = wp$$ = *(unative_t *)&dptr[z0][d+$$*NSIZE];
85 wp$$ = vec_xor(wp$$, wd$$);
92 *(unative_t *)&p[d+NSIZE*$$] = wp$$;
/linux-4.1.27/sound/pci/lola/
Dlola.c102 unsigned int wp = chip->corb.wp + 1; in corb_send_verb() local
103 wp %= LOLA_CORB_ENTRIES; in corb_send_verb()
104 chip->corb.wp = wp; in corb_send_verb()
105 chip->corb.buf[wp * 2] = cpu_to_le32(data); in corb_send_verb()
106 chip->corb.buf[wp * 2 + 1] = cpu_to_le32(extdata); in corb_send_verb()
107 lola_writew(chip, BAR0, CORBWP, wp); in corb_send_verb()
125 unsigned int rp, wp; in lola_update_rirb() local
128 wp = lola_readw(chip, BAR0, RIRBWP); in lola_update_rirb()
129 if (wp == chip->rirb.wp) in lola_update_rirb()
131 chip->rirb.wp = wp; in lola_update_rirb()
[all …]
Dlola.h225 unsigned short rp, wp; /* read/write pointers */ member
/linux-4.1.27/arch/arm/kernel/
Dhw_breakpoint.c697 struct perf_event *wp, **slots; in watchpoint_handler() local
706 wp = slots[i]; in watchpoint_handler()
708 if (wp == NULL) in watchpoint_handler()
711 info = counter_arch_bp(wp); in watchpoint_handler()
720 info->trigger = wp->attr.bp_addr; in watchpoint_handler()
742 if (!(access & hw_breakpoint_type(wp))) in watchpoint_handler()
751 perf_bp_event(wp, regs); in watchpoint_handler()
758 if (!wp->overflow_handler) in watchpoint_handler()
759 enable_single_step(wp, instruction_pointer(regs)); in watchpoint_handler()
769 struct perf_event *wp, **slots; in watchpoint_single_step_handler() local
[all …]
/linux-4.1.27/arch/powerpc/platforms/pseries/
Ddtl.c79 struct dtl_entry *wp = dtlr->write_ptr; in consume_dtle() local
82 if (!wp) in consume_dtle()
85 *wp = *dtle; in consume_dtle()
92 ++wp; in consume_dtle()
93 if (wp == dtlr->buf_end) in consume_dtle()
94 wp = dtlr->buf; in consume_dtle()
95 dtlr->write_ptr = wp; in consume_dtle()
/linux-4.1.27/Documentation/devicetree/bindings/pinctrl/
Dmarvell,dove-pinctrl.txt19 mpp1 1 gpio, pmu, uart2(cts), sdio0(wp), lcd1(pwm), pmu*
25 mpp5 5 gpio, pmu, uart3(cts), sdio1(wp), spi1(cs), pmu*
35 mpp13 13 gpio, pmu, uart2(cts), audio1(extclk), sdio1(wp),
40 mpp17 17 gpio, uart3(cts), sdio0(wp), ac97(sdi2), twsi(sda),
46 mpp21 21 gpio, sdio0(wp), sdio1(wp), spi1(cs), lcd-spi(cs0),
/linux-4.1.27/Documentation/devicetree/bindings/mmc/
Dfsl-imx-esdhc.txt14 - fsl,wp-controller : Indicate to use controller internal write protection
32 fsl,wp-controller;
40 wp-gpios = <&gpio1 5 0>; /* GPIO1_5 */
Dfsl-esdhc.txt14 - sdhci,wp-inverted : specifies that eSDHC controller reports
16 "wp-inverted" property.
Dmmc.txt19 - wp-gpios: Specify GPIOs for write protection, see gpio binding
22 - wp-inverted: when present, polarity on the WP line is inverted. See the note
51 logic applies to the "wp-inverted" property.
54 specified in cd-gpios and wp-gpios properties, or as dedicated pins. Polarity of
112 wp-gpios = <&gpio 70 0>;
Dsynopsys-dw-mshc.txt28 * wp-gpios: specifies the write protect gpio line. The format of the
32 * disable-wp: If the wp-gpios property isn't present then (by default)
36 want write protect. In that case specify 'disable-wp'.
Dpxa-mmc.txt23 wp-gpios = <&gpio 24 0>;
Dimg-dw-mshc.txt28 disable-wp;
Dk3-dw-mshc.txt40 disable-wp;
Dnvidia,tegra20-sdhci.txt35 wp-gpios = <&gpio 57 0>; /* gpio PH1 */
Datmel-hsmci.txt45 - wp-gpios: specify GPIOs for write protection
/linux-4.1.27/drivers/media/pci/saa7164/
Dsaa7164-core.c366 u32 wp, mcb, rp, cnt = 0; in saa7164_work_enchandler() local
393 wp = saa7164_readl(port->bufcounter); in saa7164_work_enchandler()
394 if (wp > (port->hwcfg.buffercount - 1)) { in saa7164_work_enchandler()
395 printk(KERN_ERR "%s() illegal buf count %d\n", __func__, wp); in saa7164_work_enchandler()
400 if (wp == 0) in saa7164_work_enchandler()
403 mcb = wp - 1; in saa7164_work_enchandler()
443 u32 wp, mcb, rp, cnt = 0; in saa7164_work_vbihandler() local
469 wp = saa7164_readl(port->bufcounter); in saa7164_work_vbihandler()
470 if (wp > (port->hwcfg.buffercount - 1)) { in saa7164_work_vbihandler()
471 printk(KERN_ERR "%s() illegal buf count %d\n", __func__, wp); in saa7164_work_vbihandler()
[all …]
/linux-4.1.27/drivers/net/wireless/rtlwifi/
Dpci.h330 static inline u16 calc_fifo_space(u16 rp, u16 wp) in calc_fifo_space() argument
332 if (rp <= wp) in calc_fifo_space()
333 return RTL_PCI_MAX_RX_COUNT - 1 + rp - wp; in calc_fifo_space()
334 return rp - wp - 1; in calc_fifo_space()
/linux-4.1.27/arch/arm/boot/dts/
Domap5-sbc-t54.dts35 wp-inverted;
37 wp-gpios = <&gpio8 5 GPIO_ACTIVE_LOW>; /* gpio8_229 */
Drk3288-evb.dtsi121 disable-wp;
139 disable-wp; /* wp not hooked up */
Dkirkwood-sheevaplug-esata.dts28 wp-gpios = <&gpio1 15 GPIO_ACTIVE_HIGH>;
Drk3066a-bqcurie2.dts160 disable-wp;
172 disable-wp;
Dexynos5410-smdk5410.dts61 disable-wp;
Dimx23-stmp378x_devb.dts30 wp-gpios = <&gpio1 30 0>;
Dkirkwood-db.dtsi52 wp-gpios = <&gpio1 5 GPIO_ACTIVE_HIGH>;
Domap3-sbc-t3517.dts59 wp-gpios = <&gpio2 27 GPIO_ACTIVE_HIGH>; /* gpio_59 */
Dzynq-zc706.dts234 mux-wp {
239 conf-wp {
Dkirkwood-sheevaplug-common.dtsi42 pmx_sdio_wp: pmx-sdio-wp {
Dimx6qdl-rex.dtsi343 wp-gpios = <&gpio2 3 GPIO_ACTIVE_HIGH>;
352 wp-gpios = <&gpio2 1 GPIO_ACTIVE_HIGH>;
Domap3-lilly-dbb056.dts88 OMAP3_CORE1_IOPAD(0x219a, PIN_INPUT_PULLUP | MUX_MODE4) /* uart3_cts_rctx.gpio_163 -> wp */
118 wp-gpios = <&gpio6 3 0>; /* gpio_163 */
Dzynq-zc702.dts285 mux-wp {
290 conf-wp {
Dberlin2q-marvell-dmp.dts63 sdhci,wp-inverted;
Drk3288-popmetal.dts106 disable-wp;
119 disable-wp; /* wp not hooked up */
Dexynos5260-xyref5260.dts94 disable-wp;
Drk3066a-rayeager.dts175 disable-wp;
327 disable-wp;
338 disable-wp;
Drk3288-firefly.dtsi172 disable-wp;
432 disable-wp;
446 disable-wp;
Dimx6q-tx6q-1020-comtft.dts134 fsl,wp-controller;
Dimx6qdl-phytec-pfla02.dtsi413 wp-gpios = <&gpio1 2 GPIO_ACTIVE_HIGH>;
422 wp-gpios = <&gpio1 29 GPIO_ACTIVE_HIGH>;
Dimx28-evk.dts38 wp-gpios = <&gpio2 12 0>;
46 wp-gpios = <&gpio0 28 0>;
Dimx6sx-sabreauto.dts53 wp-gpios = <&gpio3 19 GPIO_ACTIVE_HIGH>;
Dr8a7778-bockw-reference.dts111 wp-gpios = <&gpio3 18 GPIO_ACTIVE_HIGH>;
Dimx53-voipac-bsb.dts123 wp-gpios = <&gpio2 19 GPIO_ACTIVE_HIGH>;
Dimx23-evk.dts36 wp-gpios = <&gpio1 30 0>;
Dste-nomadik-nhk15.dts140 wp-gpios = <&stmpe_gpio44 18 GPIO_ACTIVE_HIGH>;
Dimx6q-tx6q-1020.dts208 fsl,wp-controller;
Dat91sam9263ek.dts77 wp-gpios = <&pioE 19 GPIO_ACTIVE_HIGH>;
Dphy3250.dts161 wp-gpios = <&gpio 3 0 0>;
Dimx6sx-sdb.dtsi297 wp-gpios = <&gpio2 15 GPIO_ACTIVE_HIGH>;
308 wp-gpios = <&gpio6 20 GPIO_ACTIVE_HIGH>;
Dimx6dl-riotboard.dts309 wp-gpios = <&gpio1 2 GPIO_ACTIVE_HIGH>;
318 wp-gpios = <&gpio7 1 GPIO_ACTIVE_HIGH>;
Ddm8168-evm.dts159 wp-gpios = <&gpio2 8 GPIO_ACTIVE_LOW>;
Dr8a7778-bockw.dts178 wp-gpios = <&gpio3 18 GPIO_ACTIVE_HIGH>;
Dimx53-ard.dts107 wp-gpios = <&gpio1 9 GPIO_ACTIVE_HIGH>;
Dimx6qdl-sabresd.dtsi566 wp-gpios = <&gpio2 3 GPIO_ACTIVE_HIGH>;
575 wp-gpios = <&gpio2 1 GPIO_ACTIVE_HIGH>;
Dimx53-tx53.dtsi187 fsl,wp-controller;
195 fsl,wp-controller;
Dimx6q-arm2.dts201 wp-gpios = <&gpio6 14 GPIO_ACTIVE_HIGH>;
Dimx51-babbage.dts309 wp-gpios = <&gpio1 1 GPIO_ACTIVE_HIGH>;
317 wp-gpios = <&gpio1 5 GPIO_ACTIVE_HIGH>;
Drk3188.dtsi378 sd0_wp: sd0-wp {
411 sd1_wp: sd1-wp {
Dimx6sl-evk.dts621 wp-gpios = <&gpio4 6 GPIO_ACTIVE_HIGH>;
631 wp-gpios = <&gpio4 29 GPIO_ACTIVE_HIGH>;
Dimx53-smd.dts45 wp-gpios = <&gpio4 11 GPIO_ACTIVE_HIGH>;
Darmada-388-rd.dts93 wp-inverted;
Dimx53-tqma53.dtsi44 wp-gpios = <&gpio1 2 GPIO_ACTIVE_HIGH>;
Dea3250.dts143 wp-gpios = <&pca9532 5 0>;
Dimx28-m28evk.dts28 wp-gpios = <&gpio3 10 0>;
Dr8a7791-koelsch.dts443 wp-gpios = <&gpio6 7 GPIO_ACTIVE_HIGH>;
454 wp-gpios = <&gpio6 15 GPIO_ACTIVE_HIGH>;
Dimx6qdl-tx6.dtsi684 fsl,wp-controller;
694 fsl,wp-controller;
Drk3066a.dtsi437 sd0_wp: sd0-wp {
466 sd1_wp: sd1-wp {
Darmada-388-db.dts155 wp-inverted;
Dr8a7791-henninger.dts185 wp-gpios = <&gpio6 7 GPIO_ACTIVE_HIGH>;
Dat91sam9m10g45ek.dts98 wp-gpios = <&pioD 29 GPIO_ACTIVE_HIGH>;
Dimx27-phytec-phycore-rdk.dts280 wp-gpios = <&gpio3 28 GPIO_ACTIVE_HIGH>;
Dimx53-m53evk.dts128 wp-gpios = <&gpio1 9 GPIO_ACTIVE_HIGH>;
Darmada-375-db.dts158 wp-gpios = <&gpio1 13 GPIO_ACTIVE_HIGH>;
Domap3-pandora-common.dtsi468 wp-gpios = <&gpio4 30 GPIO_ACTIVE_LOW>; /* GPIO_126 */
477 wp-gpios = <&gpio4 31 GPIO_ACTIVE_LOW>; /* GPIO_127 */
Dimx53-qsb-common.dtsi151 wp-gpios = <&gpio3 12 GPIO_ACTIVE_HIGH>;
Dimx25-pdk.dts119 wp-gpios = <&gpio2 0 GPIO_ACTIVE_HIGH>;
Drk3188-radxarock.dts262 disable-wp;
Dstih416-pinctrl.dtsi357 spi-fsm-wp = <&pio12 7 ALT1 OUT>;
499 wp = <&pio15 3 ALT4 IN>;
Dimx6qdl-sabrelite.dtsi448 wp-gpios = <&gpio7 1 GPIO_ACTIVE_HIGH>;
Dimx6qdl-sabreauto.dtsi471 wp-gpios = <&gpio1 13 GPIO_ACTIVE_HIGH>;
Dexynos5250-smdk5250.dts369 disable-wp;
Dtegra20-harmony.dts614 wp-gpios = <&gpio TEGRA_GPIO(H, 1) GPIO_ACTIVE_HIGH>;
622 wp-gpios = <&gpio TEGRA_GPIO(H, 3) GPIO_ACTIVE_HIGH>;
Dimx6q-tbs2910.dts264 wp-gpios = <&gpio2 1 GPIO_ACTIVE_HIGH>;
Dvexpress-v2m-rs1.dtsi133 wp-gpios = <&v2m_mmc_gpios 1 0>;
Dtegra20-trimslice.dts371 wp-gpios = <&gpio TEGRA_GPIO(P, 2) GPIO_ACTIVE_HIGH>;
Dvexpress-v2m.dtsi132 wp-gpios = <&v2m_mmc_gpios 1 0>;
Darmada-388-gp.dts210 wp-inverted;
Dam335x-nano.dts375 wp-gpios = <&gpio3 18 0>;
Dtegra20-tamonten.dtsi495 wp-gpios = <&gpio TEGRA_GPIO(H, 3) GPIO_ACTIVE_HIGH>;
Darm-realview-pb1176.dts324 wp-gpios = <&fpga_gpio1 1 GPIO_ACTIVE_HIGH>;
Dexynos5250-arndale.dts547 disable-wp;
Dtegra20-paz00.dts481 wp-gpios = <&gpio TEGRA_GPIO(H, 1) GPIO_ACTIVE_HIGH>;
Drk3288.dtsi998 sdio0_wp: sdio0-wp {
1031 sdio1_wp: sdio1-wp {
Dtegra30-cardhu.dtsi383 wp-gpios = <&gpio TEGRA_GPIO(T, 3) GPIO_ACTIVE_HIGH>;
Dtegra20-whistler.dts551 wp-gpios = <&gpio TEGRA_GPIO(V, 5) GPIO_ACTIVE_HIGH>;
Dstih415-pinctrl.dtsi442 wp = <&pio15 3 ALT4 IN>;
Dtegra20-ventana.dts562 wp-gpios = <&gpio TEGRA_GPIO(H, 1) GPIO_ACTIVE_HIGH>;
Dexynos5250-snow.dts557 wp-gpios = <&gpc2 1 GPIO_ACTIVE_HIGH>;
Datlas7.dtsi361 wp-inverted;
Dtegra20-seaboard.dts767 wp-gpios = <&gpio TEGRA_GPIO(H, 1) GPIO_ACTIVE_HIGH>;
Domap4.dtsi997 reg-names = "wp", "pll", "phy", "core";
Dtegra124-venice2.dts893 wp-gpios = <&gpio TEGRA_GPIO(Q, 4) GPIO_ACTIVE_LOW>;
Dtegra114-dalmore.dts1110 wp-gpios = <&gpio TEGRA_GPIO(Q, 4) GPIO_ACTIVE_HIGH>;
Domap5.dtsi1060 reg-names = "wp", "pll", "phy", "core";
Dtegra124-nyan-big.dts19 wp-gpios = <&gpio TEGRA_GPIO(Q, 4) GPIO_ACTIVE_LOW>;
Dtegra124-jetson-tk1.dts1681 wp-gpios = <&gpio TEGRA_GPIO(Q, 4) GPIO_ACTIVE_HIGH>;
Dtegra30-beaver.dts1914 wp-gpios = <&gpio TEGRA_GPIO(T, 3) GPIO_ACTIVE_HIGH>;
/linux-4.1.27/lib/
Dinflate.c169 #define wp outcnt macro
170 #define flush_output(w) (wp=(w),flush_window())
609 w = wp; /* initialize window position */ in inflate_codes()
690 wp = w; /* restore global window pointer */ in inflate_codes()
716 w = wp; /* initialize window position */ in inflate_stored()
749 wp = w; /* restore global window pointer */ in inflate_stored()
1092 wp = 0; in inflate()
1120 flush_output(wp); in inflate()
/linux-4.1.27/drivers/bus/
Darm-ccn.c877 unsigned long wp = hw->config_base; in arm_ccn_pmu_xp_watchpoint_config() local
884 hw->event_base = CCN_XP_DT_CONFIG__DT_CFG__WATCHPOINT(wp); in arm_ccn_pmu_xp_watchpoint_config()
889 CCN_XP_DT_INTERFACE_SEL__DT_IO_SEL__SHIFT(wp)); in arm_ccn_pmu_xp_watchpoint_config()
891 CCN_XP_DT_INTERFACE_SEL__DT_IO_SEL__SHIFT(wp); in arm_ccn_pmu_xp_watchpoint_config()
893 CCN_XP_DT_INTERFACE_SEL__DT_DEV_SEL__SHIFT(wp)); in arm_ccn_pmu_xp_watchpoint_config()
895 CCN_XP_DT_INTERFACE_SEL__DT_DEV_SEL__SHIFT(wp); in arm_ccn_pmu_xp_watchpoint_config()
897 CCN_XP_DT_INTERFACE_SEL__DT_VC_SEL__SHIFT(wp)); in arm_ccn_pmu_xp_watchpoint_config()
899 CCN_XP_DT_INTERFACE_SEL__DT_VC_SEL__SHIFT(wp); in arm_ccn_pmu_xp_watchpoint_config()
903 writel(cmp_l & 0xffffffff, source->base + CCN_XP_DT_CMP_VAL_L(wp)); in arm_ccn_pmu_xp_watchpoint_config()
905 source->base + CCN_XP_DT_CMP_VAL_L(wp) + 4); in arm_ccn_pmu_xp_watchpoint_config()
[all …]
/linux-4.1.27/arch/arm64/kernel/
Dhw_breakpoint.c662 struct perf_event *wp, **slots; in watchpoint_handler() local
673 wp = slots[i]; in watchpoint_handler()
675 if (wp == NULL) in watchpoint_handler()
678 info = counter_arch_bp(wp); in watchpoint_handler()
706 if (!(access & hw_breakpoint_type(wp))) in watchpoint_handler()
710 perf_bp_event(wp, regs); in watchpoint_handler()
713 if (!wp->overflow_handler) in watchpoint_handler()
/linux-4.1.27/sound/pci/hda/
Dhda_controller.c1037 chip->rirb.wp = chip->rirb.rp = 0; in azx_init_cmd_io()
1082 unsigned int wp, rp; in azx_corb_send_cmd() local
1087 wp = azx_readw(chip, CORBWP); in azx_corb_send_cmd()
1088 if (wp == 0xffff) { in azx_corb_send_cmd()
1093 wp++; in azx_corb_send_cmd()
1094 wp %= AZX_MAX_CORB_ENTRIES; in azx_corb_send_cmd()
1097 if (wp == rp) { in azx_corb_send_cmd()
1104 chip->corb.buf[wp] = cpu_to_le32(val); in azx_corb_send_cmd()
1105 azx_writew(chip, CORBWP, wp); in azx_corb_send_cmd()
1117 unsigned int rp, wp; in azx_update_rirb() local
[all …]
Dhda_controller.h247 unsigned short rp, wp; /* read/write pointers */ member
/linux-4.1.27/Documentation/virtual/kvm/
Dmmu.txt52 pages, pae, pse, pse36, cr0.wp, and 1GB pages. Work is in progress to support
167 Contains the value of cr0.wp for which the page is valid.
169 Contains the value of cr4.smep && !cr0.wp for which the page is valid
171 treatment of cr0.wp=0 below).
173 Contains the value of cr4.smap && !cr0.wp for which the page is valid
175 treatment of cr0.wp=0 below).
332 Emulating cr0.wp
335 If tdp is not enabled, the host must keep cr0.wp=1 so page write protection
337 cr0.wp=1, this does not present a problem. However when the guest cr0.wp=0,
363 To prevent an spte that was converted into a kernel page with cr0.wp=0
[all …]
/linux-4.1.27/Documentation/devicetree/bindings/video/
Dti,dra7-dss.txt55 - reg: addresses and lengths of the register spaces for 'wp', 'pll', 'phy',
57 - reg-names: "wp", "pll", "phy", "core"
Dti,omap5-dss.txt82 - reg: addresses and lengths of the register spaces for 'wp', 'pll', 'phy',
84 - reg-names: "wp", "pll", "phy", "core"
Dti,omap4-dss.txt101 - reg: addresses and lengths of the register spaces for 'wp', 'pll', 'phy',
103 - reg-names: "wp", "pll", "phy", "core"
Dti,omap-dss.txt74 reg-names = "wp", "pll", "phy", "core";
/linux-4.1.27/drivers/mtd/nand/
Dnandsim.c206 #define NS_STATUS_OK(ns) (NAND_STATUS_READY | (NAND_STATUS_WP * ((ns)->lines.wp == 0)))
363 int wp; /* write Protect */ member
901 struct weak_page *wp; in parse_weakpages() local
920 wp = kzalloc(sizeof(*wp), GFP_KERNEL); in parse_weakpages()
921 if (!wp) { in parse_weakpages()
925 wp->page_no = page_no; in parse_weakpages()
926 wp->max_writes = max_writes; in parse_weakpages()
927 list_add(&wp->list, &weak_pages); in parse_weakpages()
934 struct weak_page *wp; in write_error() local
936 list_for_each_entry(wp, &weak_pages, list) in write_error()
[all …]
/linux-4.1.27/drivers/block/
Dpktcdvd.c1685 write_param_page *wp; in pkt_set_write_settings() local
1694 init_cdrom_command(&cgc, buffer, sizeof(*wp), CGC_DATA_READ); in pkt_set_write_settings()
1719 wp = (write_param_page *) &buffer[sizeof(struct mode_page_header) + pd->mode_offset]; in pkt_set_write_settings()
1721 wp->fp = pd->settings.fp; in pkt_set_write_settings()
1722 wp->track_mode = pd->settings.track_mode; in pkt_set_write_settings()
1723 wp->write_type = pd->settings.write_type; in pkt_set_write_settings()
1724 wp->data_block_type = pd->settings.block_mode; in pkt_set_write_settings()
1726 wp->multi_session = 0; in pkt_set_write_settings()
1729 wp->link_size = 7; in pkt_set_write_settings()
1730 wp->ls_v = 1; in pkt_set_write_settings()
[all …]
/linux-4.1.27/drivers/block/drbd/
Ddrbd_proc.c245 char wp; in drbd_seq_show() local
294 wp = nc ? nc->wire_protocol - DRBD_PROT_A + 'A' : ' '; in drbd_seq_show()
304 wp, in drbd_seq_show()
/linux-4.1.27/arch/s390/include/asm/
Dnmi.h36 __u32 wp : 1; /* 20 psw mwp validity */ member
/linux-4.1.27/drivers/atm/
Dfirestream.c596 u32 wp; in submit_qentry() local
602 while ((wp = read_fs (dev, Q_WP (q->offset))) & Q_FULL) { in submit_qentry()
608 wp &= ~0xf; in submit_qentry()
609 cqe = bus_to_virt (wp); in submit_qentry()
620 int rp, wp; in submit_qentry() local
622 wp = read_fs (dev, Q_WP(q->offset)); in submit_qentry()
624 q->offset, rp, wp, wp-rp); in submit_qentry()
/linux-4.1.27/drivers/net/hamradio/
Dbaycom_epp.c372 unsigned char *wp, *bp; in encode_hdlc() local
385 wp = bc->hdlctx.buf; in encode_hdlc()
390 *wp++ = 0x7e; in encode_hdlc()
411 *wp++ = bitbuf; in encode_hdlc()
419 *wp++ = bitbuf; in encode_hdlc()
424 bc->hdlctx.bufcnt = wp - bc->hdlctx.buf; in encode_hdlc()
/linux-4.1.27/arch/arm64/boot/dts/exynos/
Dexynos7-espresso.dts83 disable-wp;
/linux-4.1.27/arch/cris/include/arch-v32/arch/hwregs/
Drt_trace_defs.h92 unsigned int wp : 1; member
/linux-4.1.27/drivers/acpi/
Dresource.c194 bool wp = addr->info.mem.write_protect; in acpi_decode_space() local
235 acpi_dev_memresource_flags(res, len, wp); in acpi_decode_space()
/linux-4.1.27/arch/powerpc/boot/dts/
Dac14xx.dts170 wp-gpios = <&gpio_pic 24 0>; /* write protect */
171 wp-inverted; /* WP active high */
Dmpc8379_rdb.dts174 sdhci,wp-inverted;
Dmpc8377_wlan.dts153 sdhci,wp-inverted;
Dmpc8379_mds.dts160 sdhci,wp-inverted;
Dmpc8378_mds.dts162 sdhci,wp-inverted;
Dmpc8377_rdb.dts176 sdhci,wp-inverted;
Dmpc8378_rdb.dts176 sdhci,wp-inverted;
Dmpc8377_mds.dts162 sdhci,wp-inverted;
/linux-4.1.27/drivers/net/ethernet/smsc/
Dsmc91x.h155 u16 *wp = (u16 *) p; in mcf_insw() local
157 *wp++ = readw(a); in mcf_insw()
162 u16 *wp = (u16 *) p; in mcf_outsw() local
164 writew(*wp++, a); in mcf_outsw()
/linux-4.1.27/arch/s390/kernel/
Dnmi.c216 if (!mci->wp) in s390_revalidate_registers()
/linux-4.1.27/arch/arm64/boot/dts/arm/
Djuno-motherboard.dtsi97 wp-gpios = <&v2m_mmc_gpios 1 0>; */
Drtsm_ve-motherboard.dtsi92 wp-gpios = <&v2m_sysreg 1 0>;
/linux-4.1.27/Documentation/hwmon/
Dthmc5014 Author: Krzysztof Helt <krzysztof.h1@wp.pl>
/linux-4.1.27/drivers/usb/gadget/udc/
Domap_udc.c335 u16 *wp; in write_packet() local
342 wp = (u16 *)buf; in write_packet()
344 omap_writew(*wp++, UDC_DATA); in write_packet()
347 buf = (u8 *)wp; in write_packet()
400 u16 *wp; in read_packet() local
407 wp = (u16 *)buf; in read_packet()
409 *wp++ = omap_readw(UDC_DATA); in read_packet()
412 buf = (u8 *)wp; in read_packet()
/linux-4.1.27/drivers/media/pci/ttpci/
Dav7110_av.c885 int wp; in dvb_video_add_event() local
889 wp = (events->eventw + 1) % MAX_VIDEO_EVENT; in dvb_video_add_event()
890 if (wp == events->eventr) { in dvb_video_add_event()
897 events->eventw = wp; in dvb_video_add_event()
/linux-4.1.27/Documentation/devicetree/bindings/arm/
Dl2cc.txt7 https://www.power.org/wp-content/uploads/2012/06/Power_ePAPR_APPROVED_v1.1.pdf
/linux-4.1.27/include/pcmcia/
Dcistpl.h110 u_char wp; member
/linux-4.1.27/net/mac80211/
Dmlme.c4680 const u8 *wp, *start, *end; in ieee80211_mgd_assoc() local
4688 wp = cfg80211_find_vendor_ie( in ieee80211_mgd_assoc()
4692 if (!wp) in ieee80211_mgd_assoc()
4694 start = wp + wp[1] + 2; in ieee80211_mgd_assoc()
4696 if (wp[1] <= 4) in ieee80211_mgd_assoc()
4699 if (wp[6] == 1) in ieee80211_mgd_assoc()
4703 if (!wp || !ieee80211_usable_wmm_params(sdata, wp + 2, in ieee80211_mgd_assoc()
4704 wp[1] - 2)) { in ieee80211_mgd_assoc()
/linux-4.1.27/drivers/scsi/fcoe/
Dfcoe_ctlr.c1319 struct fip_wwn_desc *wp; in fcoe_ctlr_recv_clr_vlink() local
1387 wp = (struct fip_wwn_desc *)desc; in fcoe_ctlr_recv_clr_vlink()
1388 if (dlen < sizeof(*wp)) in fcoe_ctlr_recv_clr_vlink()
1390 if (get_unaligned_be64(&wp->fd_wwn) != fcf->switch_name) in fcoe_ctlr_recv_clr_vlink()
/linux-4.1.27/drivers/media/dvb-core/
Ddvb_frontend.c206 int wp; in dvb_frontend_add_event() local
215 wp = (events->eventw + 1) % MAX_EVENT; in dvb_frontend_add_event()
216 if (wp == events->eventr) { in dvb_frontend_add_event()
225 events->eventw = wp; in dvb_frontend_add_event()
/linux-4.1.27/drivers/mtd/maps/
Dpcmciamtd.c382 pr_debug("Region %d, wp = %u\n", i, t->dev[i].wp); in pcmciamtd_cistpl_device()
/linux-4.1.27/drivers/net/ethernet/chelsio/cxgb3/
Dsge.c1078 struct work_request_hdr *wp = wrp; in write_wr_hdr_sgl() local
1118 wp->wr_lo = htonl(V_WR_LEN(WR_FLITS) | V_WR_GEN(ogen)) | wr_lo; in write_wr_hdr_sgl()
1119 wr_gen2((struct tx_desc *)wp, ogen); in write_wr_hdr_sgl()
/linux-4.1.27/drivers/staging/slicoss/
Dslicoss.c1145 u16 *wp = eeprom; in slic_eeprom_cksum() local
1149 checksum += *(wp++); in slic_eeprom_cksum()
1154 checksum += *(u8 *) wp; in slic_eeprom_cksum()
/linux-4.1.27/drivers/pcmcia/
Dcistpl.c677 device->dev[i].wp = (*p & 0x08) ? 1 : 0; in parse_device()
/linux-4.1.27/drivers/pinctrl/sh-pfc/
Dpfc-r8a7778.c1555 #define SDHI_PFC_WPPN(name, wp) SH_PFC_MUX1(name, wp) argument
/linux-4.1.27/
DMAINTAINERS5005 M: Stanislaw Gruszka <stf_xl@wp.pl>