| /linux-4.1.27/drivers/scsi/ |
| D | wd719x.c | 49 static inline u8 wd719x_readb(struct wd719x *wd, u8 reg) in wd719x_readb() argument
51 return ioread8(wd->base + reg); in wd719x_readb()
54 static inline u32 wd719x_readl(struct wd719x *wd, u8 reg) in wd719x_readl() argument
56 return ioread32(wd->base + reg); in wd719x_readl()
59 static inline void wd719x_writeb(struct wd719x *wd, u8 reg, u8 val) in wd719x_writeb() argument
61 iowrite8(val, wd->base + reg); in wd719x_writeb()
64 static inline void wd719x_writew(struct wd719x *wd, u8 reg, u16 val) in wd719x_writew() argument
66 iowrite16(val, wd->base + reg); in wd719x_writew()
69 static inline void wd719x_writel(struct wd719x *wd, u8 reg, u32 val) in wd719x_writel() argument
71 iowrite32(val, wd->base + reg); in wd719x_writel()
[all …]
|
| /linux-4.1.27/sound/soc/au1x/ |
| D | psc-i2s.c | 300 struct au1xpsc_audio_data *wd; in au1xpsc_i2s_drvprobe() local
302 wd = devm_kzalloc(&pdev->dev, sizeof(struct au1xpsc_audio_data), in au1xpsc_i2s_drvprobe()
304 if (!wd) in au1xpsc_i2s_drvprobe()
317 wd->mmio = devm_ioremap(&pdev->dev, iores->start, in au1xpsc_i2s_drvprobe()
319 if (!wd->mmio) in au1xpsc_i2s_drvprobe()
325 wd->dmaids[SNDRV_PCM_STREAM_PLAYBACK] = dmares->start; in au1xpsc_i2s_drvprobe()
330 wd->dmaids[SNDRV_PCM_STREAM_CAPTURE] = dmares->start; in au1xpsc_i2s_drvprobe()
335 sel = __raw_readl(PSC_SEL(wd)) & PSC_SEL_CLK_MASK; in au1xpsc_i2s_drvprobe()
336 __raw_writel(PSC_CTRL_DISABLE, PSC_CTRL(wd)); in au1xpsc_i2s_drvprobe()
338 __raw_writel(PSC_SEL_PS_I2SMODE | sel, PSC_SEL(wd)); in au1xpsc_i2s_drvprobe()
[all …]
|
| D | psc-ac97.c | 372 struct au1xpsc_audio_data *wd; in au1xpsc_ac97_drvprobe() local
374 wd = devm_kzalloc(&pdev->dev, sizeof(struct au1xpsc_audio_data), in au1xpsc_ac97_drvprobe()
376 if (!wd) in au1xpsc_ac97_drvprobe()
379 mutex_init(&wd->lock); in au1xpsc_ac97_drvprobe()
382 wd->mmio = devm_ioremap_resource(&pdev->dev, iores); in au1xpsc_ac97_drvprobe()
383 if (IS_ERR(wd->mmio)) in au1xpsc_ac97_drvprobe()
384 return PTR_ERR(wd->mmio); in au1xpsc_ac97_drvprobe()
389 wd->dmaids[SNDRV_PCM_STREAM_PLAYBACK] = dmares->start; in au1xpsc_ac97_drvprobe()
394 wd->dmaids[SNDRV_PCM_STREAM_CAPTURE] = dmares->start; in au1xpsc_ac97_drvprobe()
397 wd->cfg = PSC_AC97CFG_RT_FIFO8 | PSC_AC97CFG_TT_FIFO8 | in au1xpsc_ac97_drvprobe()
[all …]
|
| /linux-4.1.27/fs/hfsplus/ |
| D | wrapper.c | 92 static int hfsplus_read_mdb(void *bufptr, struct hfsplus_wd *wd) in hfsplus_read_mdb() argument
108 wd->ablk_size = in hfsplus_read_mdb()
110 if (wd->ablk_size < HFSPLUS_SECTOR_SIZE) in hfsplus_read_mdb()
112 if (wd->ablk_size % HFSPLUS_SECTOR_SIZE) in hfsplus_read_mdb()
114 wd->ablk_start = in hfsplus_read_mdb()
118 wd->embed_start = (extent >> 16) & 0xFFFF; in hfsplus_read_mdb()
119 wd->embed_count = extent & 0xFFFF; in hfsplus_read_mdb()
160 struct hfsplus_wd wd; in hfsplus_read_wrapper() local
196 if (!hfsplus_read_mdb(sbi->s_vhdr, &wd)) in hfsplus_read_wrapper()
198 wd.ablk_size >>= HFSPLUS_SECTOR_SHIFT; in hfsplus_read_wrapper()
[all …]
|
| /linux-4.1.27/drivers/hid/ |
| D | hid-logitech-hidpp.c | 714 struct wtp_data *wd = hidpp->private_data; in wtp_populate_input() local
721 input_set_abs_params(input_dev, ABS_MT_POSITION_X, 0, wd->x_size, 0, 0); in wtp_populate_input()
722 input_abs_set_res(input_dev, ABS_MT_POSITION_X, wd->resolution); in wtp_populate_input()
723 input_set_abs_params(input_dev, ABS_MT_POSITION_Y, 0, wd->y_size, 0, 0); in wtp_populate_input()
724 input_abs_set_res(input_dev, ABS_MT_POSITION_Y, wd->resolution); in wtp_populate_input()
736 input_mt_init_slots(input_dev, wd->maxcontacts, INPUT_MT_POINTER | in wtp_populate_input()
739 wd->input = input_dev; in wtp_populate_input()
742 static void wtp_touch_event(struct wtp_data *wd, in wtp_touch_event() argument
751 slot = input_mt_get_slot_by_key(wd->input, touch_report->finger_id); in wtp_touch_event()
753 input_mt_slot(wd->input, slot); in wtp_touch_event()
[all …]
|
| /linux-4.1.27/drivers/watchdog/ |
| D | intel-mid_wdt.c | 44 static int wdt_start(struct watchdog_device *wd) in wdt_start() argument
47 int timeout = wd->timeout; in wdt_start()
61 struct device *dev = watchdog_get_drvdata(wd); in wdt_start()
68 static int wdt_ping(struct watchdog_device *wd) in wdt_ping() argument
74 struct device *dev = watchdog_get_drvdata(wd); in wdt_ping()
81 static int wdt_stop(struct watchdog_device *wd) in wdt_stop() argument
87 struct device *dev = watchdog_get_drvdata(wd); in wdt_stop()
166 struct watchdog_device *wd = platform_get_drvdata(pdev); in mid_wdt_remove() local
167 watchdog_unregister_device(wd); in mid_wdt_remove()
|
| D | xen_wdt.c | 249 struct sched_watchdog wd = { .id = ~0 }; in xen_wdt_probe() local
250 int ret = HYPERVISOR_sched_op(SCHEDOP_watchdog, &wd); in xen_wdt_probe()
|
| /linux-4.1.27/fs/notify/inotify/ |
| D | inotify_user.c | 194 inotify_event.wd = event->wd; in copy_event_to_user()
357 i_mark->wd = ret; in inotify_add_to_idr()
367 int wd) in inotify_idr_find_locked() argument
375 i_mark = idr_find(idr, wd); in inotify_idr_find_locked()
388 int wd) in inotify_idr_find() argument
394 i_mark = inotify_idr_find_locked(group, wd); in inotify_idr_find()
405 int wd = i_mark->wd; in do_inotify_remove_from_idr() local
409 idr_remove(idr, wd); in do_inotify_remove_from_idr()
424 int wd; in inotify_remove_from_idr() local
427 wd = i_mark->wd; in inotify_remove_from_idr()
[all …]
|
| D | inotify.h | 7 int wd; member
15 int wd; member
|
| D | inotify_fsnotify.c | 105 event->wd = i_mark->wd; in inotify_handle_event()
159 fsn_mark->group, fsn_mark->inode, i_mark->wd); in idr_callback()
|
| /linux-4.1.27/arch/mips/include/asm/ |
| D | asmmacro.h | 230 .macro ld_d wd, off, base
234 ld.d $w\wd, \off(\base)
238 .macro st_d wd, off, base
242 st.d $w\wd, \off(\base)
262 .macro insert_w wd, n
266 insert.w $w\wd[\n], $1
270 .macro insert_d wd, n
274 insert.d $w\wd[\n], $1
321 .macro ld_d wd, off, base
326 .word LDD_MSA_INSN | (\wd << 6)
[all …]
|
| /linux-4.1.27/include/net/ |
| D | pkt_sched.h | 68 void qdisc_watchdog_init(struct qdisc_watchdog *wd, struct Qdisc *qdisc);
69 void qdisc_watchdog_schedule_ns(struct qdisc_watchdog *wd, u64 expires, bool throttle);
71 static inline void qdisc_watchdog_schedule(struct qdisc_watchdog *wd, in qdisc_watchdog_schedule() argument
74 qdisc_watchdog_schedule_ns(wd, PSCHED_TICKS2NS(expires), true); in qdisc_watchdog_schedule()
77 void qdisc_watchdog_cancel(struct qdisc_watchdog *wd);
|
| /linux-4.1.27/lib/raid6/ |
| D | int.uc | 88 unative_t wd$$, wq$$, wp$$, w1$$, w2$$;
97 wd$$ = *(unative_t *)&dptr[z][d+$$*NSIZE];
98 wp$$ ^= wd$$;
103 wq$$ = w1$$ ^ wd$$;
117 unative_t wd$$, wq$$, wp$$, w1$$, w2$$;
127 wd$$ = *(unative_t *)&dptr[z][d+$$*NSIZE];
128 wp$$ ^= wd$$;
133 wq$$ = w1$$ ^ wd$$;
|
| D | tilegx.uc | 56 u64 wd$$, wq$$, wp$$, w1$$, w2$$;
68 wd$$ = *(u64 *)&dptr[z][d+$$*NSIZE];
69 wp$$ = wp$$ ^ wd$$;
74 wq$$ = w1$$ ^ wd$$;
|
| D | neon.uc | 58 register unative_t wd$$, wq$$, wp$$, w1$$, w2$$;
68 wd$$ = vld1q_u8(&dptr[z][d+$$*NSIZE]);
69 wp$$ = veorq_u8(wp$$, wd$$);
75 wq$$ = veorq_u8(w1$$, wd$$);
|
| D | altivec.uc | 74 unative_t wd$$, wq$$, wp$$, w1$$, w2$$;
84 wd$$ = *(unative_t *)&dptr[z][d+$$*NSIZE];
85 wp$$ = vec_xor(wp$$, wd$$);
90 wq$$ = vec_xor(w1$$, wd$$);
|
| /linux-4.1.27/drivers/base/power/ |
| D | main.c | 404 #define DECLARE_DPM_WATCHDOG_ON_STACK(wd) \ argument
405 struct dpm_watchdog wd
417 struct dpm_watchdog *wd = (void *)data; in dpm_watchdog_handler() local
419 dev_emerg(wd->dev, "**** DPM device timeout ****\n"); in dpm_watchdog_handler()
420 show_stack(wd->tsk, NULL); in dpm_watchdog_handler()
422 dev_driver_string(wd->dev), dev_name(wd->dev)); in dpm_watchdog_handler()
430 static void dpm_watchdog_set(struct dpm_watchdog *wd, struct device *dev) in dpm_watchdog_set() argument
432 struct timer_list *timer = &wd->timer; in dpm_watchdog_set()
434 wd->dev = dev; in dpm_watchdog_set()
435 wd->tsk = current; in dpm_watchdog_set()
[all …]
|
| /linux-4.1.27/drivers/net/ethernet/qlogic/qlcnic/ |
| D | qlcnic_hw.c | 32 u32 wd[4]; member
1322 ms->wd[0] = QLCNIC_MS_WRTDATA_LO; in qlcnic_set_ms_controls()
1324 ms->wd[1] = QLCNIC_MS_WRTDATA_HI; in qlcnic_set_ms_controls()
1326 ms->wd[2] = QLCNIC_MS_WRTDATA_ULO; in qlcnic_set_ms_controls()
1327 ms->wd[3] = QLCNIC_MS_WRTDATA_UHI; in qlcnic_set_ms_controls()
1331 ms->wd[0] = QLCNIC_MS_WRTDATA_ULO; in qlcnic_set_ms_controls()
1333 ms->wd[1] = QLCNIC_MS_WRTDATA_UHI; in qlcnic_set_ms_controls()
1335 ms->wd[2] = QLCNIC_MS_WRTDATA_LO; in qlcnic_set_ms_controls()
1336 ms->wd[3] = QLCNIC_MS_WRTDATA_HI; in qlcnic_set_ms_controls()
1390 qlcnic_ind_wr(adapter, ms.wd[0], qlcnic_ind_rd(adapter, ms.rd[0])); in qlcnic_pci_mem_write_2M()
[all …]
|
| /linux-4.1.27/net/sched/ |
| D | sch_api.c | 582 struct qdisc_watchdog *wd = container_of(timer, struct qdisc_watchdog, in qdisc_watchdog() local
586 qdisc_unthrottled(wd->qdisc); in qdisc_watchdog()
587 __netif_schedule(qdisc_root(wd->qdisc)); in qdisc_watchdog()
593 void qdisc_watchdog_init(struct qdisc_watchdog *wd, struct Qdisc *qdisc) in qdisc_watchdog_init() argument
595 hrtimer_init(&wd->timer, CLOCK_MONOTONIC, HRTIMER_MODE_ABS_PINNED); in qdisc_watchdog_init()
596 wd->timer.function = qdisc_watchdog; in qdisc_watchdog_init()
597 wd->qdisc = qdisc; in qdisc_watchdog_init()
601 void qdisc_watchdog_schedule_ns(struct qdisc_watchdog *wd, u64 expires, bool throttle) in qdisc_watchdog_schedule_ns() argument
604 &qdisc_root_sleeping(wd->qdisc)->state)) in qdisc_watchdog_schedule_ns()
608 qdisc_throttled(wd->qdisc); in qdisc_watchdog_schedule_ns()
[all …]
|
| /linux-4.1.27/drivers/media/dvb-frontends/ |
| D | stv0367.c | 1198 int wd = 100; in stv0367ter_check_syr() local
1206 while ((!SYR_var) && (wd > 0)) { in stv0367ter_check_syr()
1208 wd -= 2; in stv0367ter_check_syr()
1229 int wd = 0; in stv0367ter_check_cpamp() local
1236 wd = 10; in stv0367ter_check_cpamp()
1240 wd = 55; in stv0367ter_check_cpamp()
1244 wd = 30; in stv0367ter_check_cpamp()
1251 dprintk("%s: CPAMPMin=%d wd=%d\n", __func__, CPAMPMin, wd); in stv0367ter_check_cpamp()
1254 while ((CPAMPvalue < CPAMPMin) && (wd > 0)) { in stv0367ter_check_cpamp()
1256 wd -= 1; in stv0367ter_check_cpamp()
[all …]
|
| /linux-4.1.27/Documentation/devicetree/bindings/watchdog/ |
| D | dw_wdt.txt | 16 watchdog0: wd@ffd02000 {
|
| /linux-4.1.27/include/uapi/linux/ |
| D | inotify.h | 21 __s32 wd; /* watch descriptor */ member
|
| /linux-4.1.27/drivers/net/ethernet/8390/ |
| D | Makefile | 17 obj-$(CONFIG_WD80x3) += wd.o 8390.o
|
| D | Kconfig | 191 will be called wd.
|
| /linux-4.1.27/drivers/misc/mei/ |
| D | Makefile | 12 mei-objs += wd.o
|
| /linux-4.1.27/drivers/net/wireless/brcm80211/brcmfmac/ |
| D | cfg80211.h | 435 static inline struct brcmf_cfg80211_info *wdev_to_cfg(struct wireless_dev *wd) in wdev_to_cfg() argument
437 return (struct brcmf_cfg80211_info *)(wdev_priv(wd)); in wdev_to_cfg()
|
| /linux-4.1.27/drivers/video/fbdev/matrox/ |
| D | matroxfb_misc.c | 193 unsigned int wd; in matroxfb_vgaHWinit() local
276 wd = minfo->fbcon.var.xres_virtual * minfo->curr.final_bppShift / 64; in matroxfb_vgaHWinit()
284 wd <<= 1; in matroxfb_vgaHWinit()
287 hw->CRTCEXT[0] |= (wd & 0x300) >> 4; in matroxfb_vgaHWinit()
328 hw->CRTC[19] = wd /* & 0xFF */; in matroxfb_vgaHWinit()
|
| /linux-4.1.27/drivers/video/fbdev/ |
| D | asiliantfb.c | 184 unsigned wd = (p->var.xres_virtual * ((p->var.bits_per_pixel+7)/8)) / 8; in asiliant_set_timing() local
210 write_cr(0x13, wd & 0xff); in asiliant_set_timing()
211 write_cr(0x41, (wd & 0xf00) >> 8); in asiliant_set_timing()
|
| D | tdfxfb.c | 572 u32 wd; in tdfxfb_set_par() local
597 wd = (hdispend >> 3) - 1; in tdfxfb_set_par()
598 hd = wd; in tdfxfb_set_par()
678 reg.crt[0x13] = wd; in tdfxfb_set_par()
|
| /linux-4.1.27/fs/notify/ |
| D | fdinfo.c | 86 inode_mark->wd, inode->i_ino, inode->i_sb->s_dev, in inotify_fdinfo()
|
| /linux-4.1.27/drivers/infiniband/hw/qib/ |
| D | qib_sd7220.c | 657 u32 wd, u32 mask) in qib_sd7220_reg_mod() argument
712 wd = (wd & mask) | (transval & ~mask); in qib_sd7220_reg_mod()
713 transval = loc | (wd & EPB_DATA_MASK); in qib_sd7220_reg_mod()
|
| /linux-4.1.27/arch/s390/kernel/ |
| D | compat_wrapper.c | 180 COMPAT_SYSCALL_WRAP2(inotify_rm_watch, int, fd, __s32, wd);
|
| /linux-4.1.27/drivers/scsi/qla2xxx/ |
| D | qla_sup.c | 2323 uint16_t wd; in qla2x00_write_optrom_data() local
2336 pci_read_config_word(ha->pdev, PCI_COMMAND, &wd); in qla2x00_write_optrom_data()
|
| D | qla_dbg.c | 323 uint16_t wd; in qla24xx_soft_reset() local
343 pci_read_config_word(ha->pdev, PCI_COMMAND, &wd); in qla24xx_soft_reset()
|
| D | qla_init.c | 1136 uint16_t wd; in qla24xx_reset_risc() local
1162 pci_read_config_word(ha->pdev, PCI_COMMAND, &wd); in qla24xx_reset_risc()
|
| /linux-4.1.27/include/linux/ |
| D | syscalls.h | 747 asmlinkage long sys_inotify_rm_watch(int fd, __s32 wd);
|
| /linux-4.1.27/Documentation/filesystems/ |
| D | proc.txt | 1756 …inotify wd:3 ino:9e7e sdev:800013 mask:800afce ignored_mask:0 fhandle-bytes:8 fhandle-type:1 f_han…
1758 where 'wd' is a watch descriptor in decimal form, ie a target file
|