Home
last modified time | relevance | path

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

/linux-4.4.14/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.c76 struct hdmi_wp_data *wp = data; in hdmi_irq_handler() local
79 irqstatus = hdmi_wp_get_irqstatus(wp); in hdmi_irq_handler()
80 hdmi_wp_set_irqstatus(wp, irqstatus); in hdmi_irq_handler()
92 hdmi_wp_set_phy_pwr(wp, HDMI_PHYPWRCMD_OFF); in hdmi_irq_handler()
104 hdmi_wp_set_irqstatus(wp, HDMI_IRQ_LINK_CONNECT | in hdmi_irq_handler()
107 hdmi_wp_set_phy_pwr(wp, HDMI_PHYPWRCMD_LDOON); in hdmi_irq_handler()
112 hdmi_wp_set_phy_pwr(wp, HDMI_PHYPWRCMD_TXON); in hdmi_irq_handler()
114 hdmi_wp_set_phy_pwr(wp, HDMI_PHYPWRCMD_LDOON); in hdmi_irq_handler()
199 hdmi_wp_clear_irqenable(&hdmi.wp, 0xffffffff); in hdmi_power_on_full()
200 hdmi_wp_set_irqstatus(&hdmi.wp, in hdmi_power_on_full()
[all …]
Dhdmi4.c72 struct hdmi_wp_data *wp = data; in hdmi_irq_handler() local
75 irqstatus = hdmi_wp_get_irqstatus(wp); in hdmi_irq_handler()
76 hdmi_wp_set_irqstatus(wp, irqstatus); in hdmi_irq_handler()
86 hdmi_wp_set_phy_pwr(wp, HDMI_PHYPWRCMD_OFF); in hdmi_irq_handler()
88 hdmi_wp_set_irqstatus(wp, HDMI_IRQ_LINK_CONNECT | in hdmi_irq_handler()
91 hdmi_wp_set_phy_pwr(wp, HDMI_PHYPWRCMD_LDOON); in hdmi_irq_handler()
93 hdmi_wp_set_phy_pwr(wp, HDMI_PHYPWRCMD_TXON); in hdmi_irq_handler()
95 hdmi_wp_set_phy_pwr(wp, HDMI_PHYPWRCMD_LDOON); in hdmi_irq_handler()
169 struct hdmi_wp_data *wp = &hdmi.wp; in hdmi_power_on_full() local
177 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()
687 int hdmi4_audio_config(struct hdmi_core_data *core, struct hdmi_wp_data *wp, in hdmi4_audio_config() argument
857 hdmi_wp_audio_config_dma(wp, &audio_dma); in hdmi4_audio_config()
858 hdmi_wp_audio_config_format(wp, &audio_format); in hdmi4_audio_config()
869 int hdmi4_audio_start(struct hdmi_core_data *core, struct hdmi_wp_data *wp) in hdmi4_audio_start() argument
874 hdmi_wp_audio_core_req_enable(wp, true); in hdmi4_audio_start()
879 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()
798 int hdmi5_audio_config(struct hdmi_core_data *core, struct hdmi_wp_data *wp, in hdmi5_audio_config() argument
887 hdmi_wp_audio_config_dma(wp, &audio_dma); in hdmi5_audio_config()
888 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.4.14/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.4.14/sound/hda/
Dhdac_controller.c66 bus->rirb.wp = bus->rirb.rp = 0; in snd_hdac_bus_init_cmd_io()
118 unsigned int wp, rp; in snd_hdac_bus_send_cmd() local
125 wp = snd_hdac_chip_readw(bus, CORBWP); in snd_hdac_bus_send_cmd()
126 if (wp == 0xffff) { in snd_hdac_bus_send_cmd()
131 wp++; in snd_hdac_bus_send_cmd()
132 wp %= AZX_MAX_CORB_ENTRIES; in snd_hdac_bus_send_cmd()
135 if (wp == rp) { in snd_hdac_bus_send_cmd()
142 bus->corb.buf[wp] = cpu_to_le32(val); in snd_hdac_bus_send_cmd()
143 snd_hdac_chip_writew(bus, CORBWP, wp); in snd_hdac_bus_send_cmd()
161 unsigned int rp, wp; in snd_hdac_bus_update_rirb() local
[all …]
Dhdac_bus.c131 unsigned int wp; in snd_hdac_bus_queue_event() local
137 wp = (bus->unsol_wp + 1) % HDA_UNSOL_QUEUE_SIZE; in snd_hdac_bus_queue_event()
138 bus->unsol_wp = wp; in snd_hdac_bus_queue_event()
140 wp <<= 1; in snd_hdac_bus_queue_event()
141 bus->unsol_queue[wp] = res; in snd_hdac_bus_queue_event()
142 bus->unsol_queue[wp + 1] = res_ex; in snd_hdac_bus_queue_event()
/linux-4.4.14/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.4.14/arch/ia64/kernel/
Dpatch.c146 u64 *wp; in ia64_patch_mckinley_e9() local
159 wp = (u64 *) ia64_imva((char *) offp + *offp); in ia64_patch_mckinley_e9()
160 wp[0] = 0x0000000100000011UL; /* nop.m 0; nop.i 0; br.ret.sptk.many b6 */ in ia64_patch_mckinley_e9()
161 wp[1] = 0x0084006880000200UL; in ia64_patch_mckinley_e9()
162 wp[2] = 0x0000000100000000UL; /* nop.m 0; nop.i 0; nop.i 0 */ in ia64_patch_mckinley_e9()
163 wp[3] = 0x0004000000000200UL; in ia64_patch_mckinley_e9()
164 ia64_fc(wp); ia64_fc(wp + 2); in ia64_patch_mckinley_e9()
/linux-4.4.14/lib/raid6/
Dneon.uc59 register unative_t wd$$, wq$$, wp$$, w1$$, w2$$;
67 wq$$ = wp$$ = vld1q_u8(&dptr[z0][d+$$*NSIZE]);
70 wp$$ = veorq_u8(wp$$, wd$$);
78 vst1q_u8(&p[d+NSIZE*$$], wp$$);
90 register unative_t wd$$, wq$$, wp$$, w1$$, w2$$;
99 wp$$ = veorq_u8(vld1q_u8(&p[d+$$*NSIZE]), wq$$);
104 wp$$ = veorq_u8(wp$$, wd$$);
123 vst1q_u8(&p[d+NSIZE*$$], wp$$);
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$$;
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.4.14/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.4.14/arch/arm/kernel/
Dhw_breakpoint.c696 struct perf_event *wp, **slots; in watchpoint_handler() local
705 wp = slots[i]; in watchpoint_handler()
707 if (wp == NULL) in watchpoint_handler()
710 info = counter_arch_bp(wp); in watchpoint_handler()
719 info->trigger = wp->attr.bp_addr; in watchpoint_handler()
741 if (!(access & hw_breakpoint_type(wp))) in watchpoint_handler()
750 perf_bp_event(wp, regs); in watchpoint_handler()
757 if (!wp->overflow_handler) in watchpoint_handler()
758 enable_single_step(wp, instruction_pointer(regs)); in watchpoint_handler()
768 struct perf_event *wp, **slots; in watchpoint_single_step_handler() local
[all …]
/linux-4.4.14/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.4.14/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.4.14/arch/arm/boot/dts/
Dzx296702-ad1.dts24 disable-wp;
37 disable-wp;
Domap5-sbc-t54.dts35 wp-inverted;
37 wp-gpios = <&gpio8 5 GPIO_ACTIVE_LOW>; /* gpio8_229 */
Dkirkwood-sheevaplug-esata.dts28 wp-gpios = <&gpio1 15 GPIO_ACTIVE_HIGH>;
Drk3288-evb.dtsi167 disable-wp;
185 disable-wp; /* wp not hooked up */
Drk3288-veyron-pinky.dts99 sdmmc_wp_gpio: sdmmc-wp-gpio {
122 wp-gpios = <&gpio7 10 GPIO_ACTIVE_HIGH>;
Dkirkwood-db.dtsi52 wp-gpios = <&gpio1 5 GPIO_ACTIVE_HIGH>;
Domap3-sbc-t3517.dts59 wp-gpios = <&gpio2 27 GPIO_ACTIVE_HIGH>; /* gpio_59 */
Dexynos5410-smdk5410.dts61 disable-wp;
Dimx23-stmp378x_devb.dts30 wp-gpios = <&gpio1 30 0>;
Dzynq-zc706.dts235 mux-wp {
240 conf-wp {
Drk3288-rock2-square.dts96 disable-wp; /* wp not hooked up */
Dkirkwood-sheevaplug-common.dtsi42 pmx_sdio_wp: pmx-sdio-wp {
Domap3-lilly-dbb056.dts88 OMAP3_CORE1_IOPAD(0x219a, PIN_INPUT_PULLUP | MUX_MODE4) /* uart3_cts_rctx.gpio_163 -> wp */
118 wp-gpios = <&gpio6 3 GPIO_ACTIVE_HIGH>; /* gpio_163 */
Dimx6qdl-rex.dtsi343 wp-gpios = <&gpio2 3 GPIO_ACTIVE_HIGH>;
352 wp-gpios = <&gpio2 1 GPIO_ACTIVE_HIGH>;
Dexynos5260-xyref5260.dts94 disable-wp;
Dzynq-zc702.dts314 mux-wp {
319 conf-wp {
Drk3066a-bqcurie2.dts191 disable-wp;
203 disable-wp;
Drk3066a-rayeager.dts176 disable-wp;
328 disable-wp;
341 disable-wp;
Dimx6q-tx6q-1020-comtft.dts134 fsl,wp-controller;
Dimx28-evk.dts38 wp-gpios = <&gpio2 12 0>;
46 wp-gpios = <&gpio0 28 0>;
Dimx6qdl-phytec-pfla02.dtsi413 wp-gpios = <&gpio1 2 GPIO_ACTIVE_HIGH>;
422 wp-gpios = <&gpio1 29 GPIO_ACTIVE_HIGH>;
Drk3288-firefly.dtsi214 disable-wp;
490 disable-wp;
505 disable-wp;
Drk3288-popmetal.dts168 disable-wp;
183 disable-wp; /* wp not hooked up */
Dimx6sx-sabreauto.dts53 wp-gpios = <&gpio3 19 GPIO_ACTIVE_HIGH>;
Dimx53-voipac-bsb.dts123 wp-gpios = <&gpio2 19 GPIO_ACTIVE_HIGH>;
Dimx23-evk.dts36 wp-gpios = <&gpio1 30 0>;
Dimx6q-tx6q-1020.dts208 fsl,wp-controller;
Dat91sam9263ek.dts69 wp-gpios = <&pioE 19 GPIO_ACTIVE_HIGH>;
Dste-nomadik-nhk15.dts172 wp-gpios = <&stmpe_gpio44 18 GPIO_ACTIVE_HIGH>;
Dphy3250.dts161 wp-gpios = <&gpio 3 0 0>;
Dimx6dl-riotboard.dts309 wp-gpios = <&gpio1 2 GPIO_ACTIVE_HIGH>;
318 wp-gpios = <&gpio7 1 GPIO_ACTIVE_HIGH>;
Dimx6sx-sdb.dtsi297 wp-gpios = <&gpio2 15 GPIO_ACTIVE_HIGH>;
308 wp-gpios = <&gpio6 20 GPIO_ACTIVE_HIGH>;
Dr8a7778-bockw.dts178 wp-gpios = <&gpio3 18 GPIO_ACTIVE_HIGH>;
Dimx53-ard.dts107 wp-gpios = <&gpio1 9 GPIO_ACTIVE_HIGH>;
Ddm8168-evm.dts159 wp-gpios = <&gpio2 8 GPIO_ACTIVE_LOW>;
Dberlin2q-marvell-dmp.dts92 sdhci,wp-inverted;
Domap3-pandora-common.dtsi497 * your board has good switches, feel free to uncomment wp-gpios below.
505 /*wp-gpios = <&gpio4 30 GPIO_ACTIVE_HIGH>;*/ /* GPIO_126 */
514 /*wp-gpios = <&gpio4 31 GPIO_ACTIVE_HIGH>;*/ /* GPIO_127 */
Dimx6qdl-sabresd.dtsi573 wp-gpios = <&gpio2 3 GPIO_ACTIVE_HIGH>;
582 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>;
Dimx6sl-evk.dts621 wp-gpios = <&gpio4 6 GPIO_ACTIVE_HIGH>;
631 wp-gpios = <&gpio4 29 GPIO_ACTIVE_HIGH>;
Dimx51-babbage.dts309 wp-gpios = <&gpio1 1 GPIO_ACTIVE_HIGH>;
317 wp-gpios = <&gpio1 5 GPIO_ACTIVE_HIGH>;
Dbcm5301x.dtsi190 brcm,nand-has-wp;
Dimx53-smd.dts45 wp-gpios = <&gpio4 11 GPIO_ACTIVE_HIGH>;
Dr8a7791-porter.dts169 wp-gpios = <&gpio6 7 GPIO_ACTIVE_HIGH>;
Darmada-388-rd.dts95 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.dts450 wp-gpios = <&gpio6 7 GPIO_ACTIVE_HIGH>;
461 wp-gpios = <&gpio6 15 GPIO_ACTIVE_HIGH>;
Dimx6qdl-tx6.dtsi685 fsl,wp-controller;
695 fsl,wp-controller;
Drk3288-veyron-speedy.dts97 disable-wp;
Darmada-388-db.dts157 wp-inverted;
Dr8a7791-henninger.dts185 wp-gpios = <&gpio6 7 GPIO_ACTIVE_HIGH>;
Dimx27-phytec-phycore-rdk.dts280 wp-gpios = <&gpio3 28 GPIO_ACTIVE_HIGH>;
Dat91sam9m10g45ek.dts109 wp-gpios = <&pioD 29 GPIO_ACTIVE_HIGH>;
Dimx53-m53evk.dts128 wp-gpios = <&gpio1 9 GPIO_ACTIVE_HIGH>;
Drk3288-veyron-jaq.dts112 disable-wp;
Darmada-375-db.dts160 wp-gpios = <&gpio1 13 GPIO_ACTIVE_HIGH>;
Drk3288-veyron.dtsi153 disable-wp;
554 fw_wp_ap: fw-wp-ap {
Drk3188.dtsi442 sd0_wp: sd0-wp {
475 sd1_wp: sd1-wp {
Drk3288-veyron-minnie.dts150 disable-wp;
Dimx25-pdk.dts119 wp-gpios = <&gpio2 0 GPIO_ACTIVE_HIGH>;
Drk3288-veyron-jerry.dts109 disable-wp;
Dimx53-qsb-common.dtsi151 wp-gpios = <&gpio3 12 GPIO_ACTIVE_HIGH>;
Drk3066a.dtsi487 sd0_wp: sd0-wp {
516 sd1_wp: sd1-wp {
Dbcm-cygnus.dtsi242 brcm,nand-has-wp;
Ddove-sbc-a510.dts175 wp-gpios = <&gpio_ext 10 GPIO_ACTIVE_LOW>;
Drk3288-rock2-som.dtsi81 disable-wp;
Dstih416-pinctrl.dtsi388 spi-fsm-wp = <&pio12 7 ALT1 OUT>;
530 wp = <&pio15 3 ALT4 IN>;
Dexynos5250-smdk5250.dts377 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.dtsi135 wp-gpios = <&v2m_mmc_gpios 1 0>;
Dtegra20-trimslice.dts371 wp-gpios = <&gpio TEGRA_GPIO(P, 2) GPIO_ACTIVE_HIGH>;
Dvexpress-v2m.dtsi134 wp-gpios = <&v2m_mmc_gpios 1 0>;
Drk3188-radxarock.dts309 disable-wp;
Drk3288-r89.dts344 disable-wp;
Dam335x-nano.dts375 wp-gpios = <&gpio3 18 0>;
Darmada-388-gp.dts225 wp-inverted;
Dimx7d-sdb.dts288 wp-gpios = <&gpio5 1 GPIO_ACTIVE_HIGH>;
Dimx6qdl-sabreauto.dtsi608 wp-gpios = <&gpio1 13 GPIO_ACTIVE_HIGH>;
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.dts551 disable-wp;
Dtegra20-paz00.dts481 wp-gpios = <&gpio TEGRA_GPIO(H, 1) GPIO_ACTIVE_HIGH>;
Dimx6qdl-sabrelite.dtsi595 wp-gpios = <&gpio7 1 GPIO_ACTIVE_HIGH>;
Dimx6qdl-aristainetos2.dtsi404 wp-gpios = <&gpio2 10 GPIO_ACTIVE_HIGH>;
Dexynos5250-snow-common.dtsi544 wp-gpios = <&gpc2 1 GPIO_ACTIVE_HIGH>;
Dtegra20-whistler.dts551 wp-gpios = <&gpio TEGRA_GPIO(V, 5) GPIO_ACTIVE_HIGH>;
Dtegra20-ventana.dts562 wp-gpios = <&gpio TEGRA_GPIO(H, 1) GPIO_ACTIVE_HIGH>;
Dtegra30-cardhu.dtsi384 wp-gpios = <&gpio TEGRA_GPIO(T, 3) GPIO_ACTIVE_HIGH>;
Dstih415-pinctrl.dtsi442 wp = <&pio15 3 ALT4 IN>;
Drk3288.dtsi1187 sdio0_wp: sdio0-wp {
1220 sdio1_wp: sdio1-wp {
Dtegra20-seaboard.dts768 wp-gpios = <&gpio TEGRA_GPIO(H, 1) GPIO_ACTIVE_HIGH>;
Domap4.dtsi1000 reg-names = "wp", "pll", "phy", "core";
Dtegra124-venice2.dts901 wp-gpios = <&gpio TEGRA_GPIO(Q, 4) GPIO_ACTIVE_LOW>;
Domap5.dtsi1068 reg-names = "wp", "pll", "phy", "core";
Dtegra114-dalmore.dts1110 wp-gpios = <&gpio TEGRA_GPIO(Q, 4) GPIO_ACTIVE_HIGH>;
Datlas7.dtsi1475 wp-inverted;
Dstih407-pinctrl.dtsi1156 spi-fsm-wp = <&pio40 4 ALT1 OUT>;
Dtegra124-nyan-big.dts19 wp-gpios = <&gpio TEGRA_GPIO(Q, 4) GPIO_ACTIVE_LOW>;
Ddra7.dtsi1599 reg-names = "wp", "pll", "phy", "core";
Dtegra124-jetson-tk1.dts1693 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.4.14/drivers/media/pci/saa7164/
Dsaa7164-core.c371 u32 wp, mcb, rp, cnt = 0; in saa7164_work_enchandler() local
398 wp = saa7164_readl(port->bufcounter); in saa7164_work_enchandler()
399 if (wp > (port->hwcfg.buffercount - 1)) { in saa7164_work_enchandler()
400 printk(KERN_ERR "%s() illegal buf count %d\n", __func__, wp); in saa7164_work_enchandler()
405 if (wp == 0) in saa7164_work_enchandler()
408 mcb = wp - 1; in saa7164_work_enchandler()
448 u32 wp, mcb, rp, cnt = 0; in saa7164_work_vbihandler() local
474 wp = saa7164_readl(port->bufcounter); in saa7164_work_vbihandler()
475 if (wp > (port->hwcfg.buffercount - 1)) { in saa7164_work_vbihandler()
476 printk(KERN_ERR "%s() illegal buf count %d\n", __func__, wp); in saa7164_work_vbihandler()
[all …]
/linux-4.4.14/drivers/net/wireless/realtek/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.4.14/Documentation/devicetree/bindings/mmc/
Dfsl-imx-esdhc.txt21 - fsl,wp-controller : Indicate to use controller internal write protection
43 fsl,wp-controller;
51 wp-gpios = <&gpio1 5 0>; /* GPIO1_5 */
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
24 - disable-wp: When set no physical WP line is present. This property should
27 logic it is sufficient to not specify wp-gpios property in the absence of a WP
57 logic applies to the "wp-inverted" property.
60 specified in cd-gpios and wp-gpios properties, or as dedicated pins. Polarity of
119 wp-gpios = <&gpio 70 0>;
Dfsl-esdhc.txt14 - sdhci,wp-inverted : specifies that eSDHC controller reports
16 "wp-inverted" property.
Dk3-dw-mshc.txt44 disable-wp;
56 disable-wp;
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;
Dnvidia,tegra20-sdhci.txt35 wp-gpios = <&gpio 57 0>; /* gpio PH1 */
Datmel-hsmci.txt45 - wp-gpios: specify GPIOs for write protection
/linux-4.4.14/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.4.14/arch/arm64/kernel/
Dhw_breakpoint.c664 struct perf_event *wp, **slots; in watchpoint_handler() local
675 wp = slots[i]; in watchpoint_handler()
677 if (wp == NULL) in watchpoint_handler()
680 info = counter_arch_bp(wp); in watchpoint_handler()
708 if (!(access & hw_breakpoint_type(wp))) in watchpoint_handler()
712 perf_bp_event(wp, regs); in watchpoint_handler()
715 if (!wp->overflow_handler) in watchpoint_handler()
/linux-4.4.14/drivers/bus/
Darm-ccn.c962 unsigned long wp = hw->config_base; in arm_ccn_pmu_xp_watchpoint_config() local
969 hw->event_base = CCN_XP_DT_CONFIG__DT_CFG__WATCHPOINT(wp); in arm_ccn_pmu_xp_watchpoint_config()
974 CCN_XP_DT_INTERFACE_SEL__DT_IO_SEL__SHIFT(wp)); in arm_ccn_pmu_xp_watchpoint_config()
976 CCN_XP_DT_INTERFACE_SEL__DT_IO_SEL__SHIFT(wp); in arm_ccn_pmu_xp_watchpoint_config()
978 CCN_XP_DT_INTERFACE_SEL__DT_DEV_SEL__SHIFT(wp)); in arm_ccn_pmu_xp_watchpoint_config()
980 CCN_XP_DT_INTERFACE_SEL__DT_DEV_SEL__SHIFT(wp); in arm_ccn_pmu_xp_watchpoint_config()
982 CCN_XP_DT_INTERFACE_SEL__DT_VC_SEL__SHIFT(wp)); in arm_ccn_pmu_xp_watchpoint_config()
984 CCN_XP_DT_INTERFACE_SEL__DT_VC_SEL__SHIFT(wp); in arm_ccn_pmu_xp_watchpoint_config()
988 writel(cmp_l & 0xffffffff, source->base + CCN_XP_DT_CMP_VAL_L(wp)); in arm_ccn_pmu_xp_watchpoint_config()
990 source->base + CCN_XP_DT_CMP_VAL_L(wp) + 4); in arm_ccn_pmu_xp_watchpoint_config()
[all …]
/linux-4.4.14/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).
338 Emulating cr0.wp
341 If tdp is not enabled, the host must keep cr0.wp=1 so page write protection
343 cr0.wp=1, this does not present a problem. However when the guest cr0.wp=0,
369 To prevent an spte that was converted into a kernel page with cr0.wp=0
[all …]
/linux-4.4.14/Documentation/devicetree/bindings/display/ti/
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.4.14/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
900 struct weak_page *wp; in parse_weakpages() local
919 wp = kzalloc(sizeof(*wp), GFP_KERNEL); in parse_weakpages()
920 if (!wp) { in parse_weakpages()
924 wp->page_no = page_no; in parse_weakpages()
925 wp->max_writes = max_writes; in parse_weakpages()
926 list_add(&wp->list, &weak_pages); in parse_weakpages()
933 struct weak_page *wp; in write_error() local
935 list_for_each_entry(wp, &weak_pages, list) in write_error()
[all …]
/linux-4.4.14/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.4.14/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.4.14/drivers/media/platform/sti/c8sectpfe/
Dc8sectpfe-core.c87 unsigned long wp, rp; in channel_swdemux_tsklet() local
94 wp = readl(channel->irec + DMA_PRDS_BUSWP_TP(0)); in channel_swdemux_tsklet()
100 if (wp < rp) in channel_swdemux_tsklet()
101 wp = channel->back_buffer_busaddr + FEI_BUFFER_SIZE; in channel_swdemux_tsklet()
103 size = wp - rp; in channel_swdemux_tsklet()
117 channel->tsin_id, channel, num_packets, buf, pos, rp, wp); in channel_swdemux_tsklet()
129 if (wp == (channel->back_buffer_busaddr + FEI_BUFFER_SIZE)) in channel_swdemux_tsklet()
133 writel(wp, channel->irec + DMA_PRDS_BUSWP_TP(0)); in channel_swdemux_tsklet()
/linux-4.4.14/arch/s390/include/asm/
Dnmi.h46 u64 wp : 1; /* 20 psw mwp validity */ member
/linux-4.4.14/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.4.14/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.4.14/arch/arm64/boot/dts/exynos/
Dexynos7-espresso.dts83 disable-wp;
/linux-4.4.14/arch/cris/include/arch-v32/arch/hwregs/
Drt_trace_defs.h92 unsigned int wp : 1; member
/linux-4.4.14/arch/powerpc/boot/dts/
Dac14xx.dts170 wp-gpios = <&gpio_pic 24 0>; /* write protect */
171 wp-inverted; /* WP active high */
Dmpc8377_wlan.dts153 sdhci,wp-inverted;
Dmpc8379_rdb.dts174 sdhci,wp-inverted;
Dmpc8377_rdb.dts176 sdhci,wp-inverted;
Dmpc8379_mds.dts160 sdhci,wp-inverted;
Dmpc8378_rdb.dts176 sdhci,wp-inverted;
Dmpc8378_mds.dts162 sdhci,wp-inverted;
Dmpc8377_mds.dts162 sdhci,wp-inverted;
/linux-4.4.14/arch/s390/kernel/
Dnmi.c226 if (!mci.wp) in s390_validate_registers()
/linux-4.4.14/drivers/acpi/
Dresource.c204 bool wp = addr->info.mem.write_protect; in acpi_decode_space() local
245 acpi_dev_memresource_flags(res, len, wp); in acpi_decode_space()
/linux-4.4.14/drivers/net/ethernet/smsc/
Dsmc91x.h156 u16 *wp = (u16 *) p; in mcf_insw() local
158 *wp++ = readw(a); in mcf_insw()
163 u16 *wp = (u16 *) p; in mcf_outsw() local
165 writew(*wp++, a); in mcf_outsw()
/linux-4.4.14/Documentation/hwmon/
Dthmc5014 Author: Krzysztof Helt <krzysztof.h1@wp.pl>
/linux-4.4.14/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.4.14/Documentation/DocBook/
Dmtdnand.xml.db38 API-nand-check-wp
/linux-4.4.14/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.4.14/arch/arm64/boot/dts/arm/
Drtsm_ve-motherboard.dtsi94 wp-gpios = <&v2m_sysreg 1 0>;
Djuno-motherboard.dtsi231 wp-gpios = <&v2m_mmc_gpios 1 0>; */
Dvexpress-v2m-rs1.dtsi135 wp-gpios = <&v2m_mmc_gpios 1 0>;
/linux-4.4.14/drivers/mtd/nand/brcmnand/
Dbrcmnand.c907 static void brcmnand_wp(struct mtd_info *mtd, int wp) in brcmnand_wp() argument
916 if (old_wp != wp) { in brcmnand_wp()
917 dev_dbg(ctrl->dev, "WP %s\n", wp ? "on" : "off"); in brcmnand_wp()
918 old_wp = wp; in brcmnand_wp()
920 brcmnand_set_wp(ctrl, wp); in brcmnand_wp()
/linux-4.4.14/Documentation/devicetree/bindings/arm/
Dl2cc.txt7 https://www.power.org/wp-content/uploads/2012/06/Power_ePAPR_APPROVED_v1.1.pdf
/linux-4.4.14/include/pcmcia/
Dcistpl.h110 u_char wp; member
/linux-4.4.14/Documentation/devicetree/bindings/mtd/
Dbrcm,brcmnand.txt48 - brcm,nand-has-wp : Some versions of this IP include a write-protect
/linux-4.4.14/arch/arm64/boot/dts/rockchip/
Drk3368-r88.dts191 disable-wp;
Drk3368.dtsi739 sdio0_wp: sdio0-wp {
/linux-4.4.14/include/sound/
Dhdaudio.h239 unsigned short rp, wp; /* RIRB read/write pointers */ member
/linux-4.4.14/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.4.14/drivers/media/dvb-core/
Ddvb_frontend.c207 int wp; in dvb_frontend_add_event() local
216 wp = (events->eventw + 1) % MAX_EVENT; in dvb_frontend_add_event()
217 if (wp == events->eventr) { in dvb_frontend_add_event()
226 events->eventw = wp; in dvb_frontend_add_event()
/linux-4.4.14/drivers/mtd/maps/
Dpcmciamtd.c382 pr_debug("Region %d, wp = %u\n", i, t->dev[i].wp); in pcmciamtd_cistpl_device()
/linux-4.4.14/drivers/staging/slicoss/
Dslicoss.c1167 u16 *wp = eeprom; in slic_eeprom_cksum() local
1171 checksum += *(wp++); in slic_eeprom_cksum()
1176 checksum += *(u8 *)wp; in slic_eeprom_cksum()
/linux-4.4.14/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.4.14/drivers/pcmcia/
Dcistpl.c675 device->dev[i].wp = (*p & 0x08) ? 1 : 0; in parse_device()
/linux-4.4.14/drivers/pinctrl/sh-pfc/
Dpfc-r8a7778.c1561 #define SDHI_PFC_WPPN(name, wp) SH_PFC_MUX1(name, wp) argument
/linux-4.4.14/
DMAINTAINERS5390 M: Stanislaw Gruszka <stf_xl@wp.pl>
6906 M: Jakub Kicinski <kubakici@wp.pl>