Home
last modified time | relevance | path

Searched refs:wd (Results 1 – 25 of 135) sorted by relevance

123456

/OK3568_Linux_fs/kernel/drivers/scsi/
H A Dwd719x.c50 static inline u8 wd719x_readb(struct wd719x *wd, u8 reg) in wd719x_readb() argument
52 return ioread8(wd->base + reg); in wd719x_readb()
55 static inline u32 wd719x_readl(struct wd719x *wd, u8 reg) in wd719x_readl() argument
57 return ioread32(wd->base + reg); in wd719x_readl()
60 static inline void wd719x_writeb(struct wd719x *wd, u8 reg, u8 val) in wd719x_writeb() argument
62 iowrite8(val, wd->base + reg); in wd719x_writeb()
65 static inline void wd719x_writew(struct wd719x *wd, u8 reg, u16 val) in wd719x_writew() argument
67 iowrite16(val, wd->base + reg); in wd719x_writew()
70 static inline void wd719x_writel(struct wd719x *wd, u8 reg, u32 val) in wd719x_writel() argument
72 iowrite32(val, wd->base + reg); in wd719x_writel()
[all …]
/OK3568_Linux_fs/external/rkwifibt/drivers/rtl8852bs/phl/hal_g6/mac/mac_ax/
H A Dsounding.c480 snd_info->wd[0].txpktsize = 31; in mac_set_snd_para()
481 snd_info->wd[0].stf_mode = 1; in mac_set_snd_para()
482 snd_info->wd[0].disdatafb = 1; in mac_set_snd_para()
483 snd_info->wd[0].data_txcnt_lmt_sel = 1; in mac_set_snd_para()
484 snd_info->wd[0].data_txcnt_lmt = 1; in mac_set_snd_para()
485 snd_info->wd[0].sifs_tx = 1; in mac_set_snd_para()
486 snd_info->wd[0].ndpa = 1; in mac_set_snd_para()
488 snd_info->wd[1].stf_mode = 1; in mac_set_snd_para()
489 snd_info->wd[1].disdatafb = 1; in mac_set_snd_para()
490 snd_info->wd[1].data_txcnt_lmt_sel = 1; in mac_set_snd_para()
[all …]
/OK3568_Linux_fs/external/rkwifibt/drivers/rtl8852be/phl/hal_g6/mac/mac_ax/
H A Dsounding.c480 snd_info->wd[0].txpktsize = 31; in mac_set_snd_para()
481 snd_info->wd[0].stf_mode = 1; in mac_set_snd_para()
482 snd_info->wd[0].disdatafb = 1; in mac_set_snd_para()
483 snd_info->wd[0].data_txcnt_lmt_sel = 1; in mac_set_snd_para()
484 snd_info->wd[0].data_txcnt_lmt = 1; in mac_set_snd_para()
485 snd_info->wd[0].sifs_tx = 1; in mac_set_snd_para()
486 snd_info->wd[0].ndpa = 1; in mac_set_snd_para()
488 snd_info->wd[1].stf_mode = 1; in mac_set_snd_para()
489 snd_info->wd[1].disdatafb = 1; in mac_set_snd_para()
490 snd_info->wd[1].data_txcnt_lmt_sel = 1; in mac_set_snd_para()
[all …]
/OK3568_Linux_fs/external/rkwifibt/drivers/rtl8852be/phl/hal_g6/
H A Dhal_sound.c576 cmd->wd[0].txpktsize = 21;/* 2 + 2 + 6 + 6 + 1 + 4, NO FCS */ in rtw_hal_snd_vht_fwcmd_su()
577 cmd->wd[0].ndpa_duration = 100; in rtw_hal_snd_vht_fwcmd_su()
578 cmd->wd[0].disdatafb = 1; in rtw_hal_snd_vht_fwcmd_su()
579 cmd->wd[0].datarate = snd_obj->ndpa_xpara.rate; in rtw_hal_snd_vht_fwcmd_su()
580 cmd->wd[0].data_bw = snd_obj->ndpa_xpara.bw; in rtw_hal_snd_vht_fwcmd_su()
581 cmd->wd[0].macid = psta->macid; in rtw_hal_snd_vht_fwcmd_su()
582 cmd->wd[0].gi_ltf = snd_obj->ndpa_xpara.gi_ltf; in rtw_hal_snd_vht_fwcmd_su()
583 cmd->wd[0].data_stbc = snd_obj->ndpa_xpara.stbc; in rtw_hal_snd_vht_fwcmd_su()
584 cmd->wd[0].data_ldpc = snd_obj->ndpa_xpara.ldpc; in rtw_hal_snd_vht_fwcmd_su()
585 cmd->wd[0].sifs_tx = 1; in rtw_hal_snd_vht_fwcmd_su()
[all …]
/OK3568_Linux_fs/external/rkwifibt/drivers/rtl8852bs/phl/hal_g6/
H A Dhal_sound.c576 cmd->wd[0].txpktsize = 21;/* 2 + 2 + 6 + 6 + 1 + 4, NO FCS */ in rtw_hal_snd_vht_fwcmd_su()
577 cmd->wd[0].ndpa_duration = 100; in rtw_hal_snd_vht_fwcmd_su()
578 cmd->wd[0].disdatafb = 1; in rtw_hal_snd_vht_fwcmd_su()
579 cmd->wd[0].datarate = snd_obj->ndpa_xpara.rate; in rtw_hal_snd_vht_fwcmd_su()
580 cmd->wd[0].data_bw = snd_obj->ndpa_xpara.bw; in rtw_hal_snd_vht_fwcmd_su()
581 cmd->wd[0].macid = psta->macid; in rtw_hal_snd_vht_fwcmd_su()
582 cmd->wd[0].gi_ltf = snd_obj->ndpa_xpara.gi_ltf; in rtw_hal_snd_vht_fwcmd_su()
583 cmd->wd[0].data_stbc = snd_obj->ndpa_xpara.stbc; in rtw_hal_snd_vht_fwcmd_su()
584 cmd->wd[0].data_ldpc = snd_obj->ndpa_xpara.ldpc; in rtw_hal_snd_vht_fwcmd_su()
585 cmd->wd[0].sifs_tx = 1; in rtw_hal_snd_vht_fwcmd_su()
[all …]
/OK3568_Linux_fs/kernel/sound/soc/au1x/
H A Dpsc-i2s.c296 struct au1xpsc_audio_data *wd; in au1xpsc_i2s_drvprobe() local
298 wd = devm_kzalloc(&pdev->dev, sizeof(struct au1xpsc_audio_data), in au1xpsc_i2s_drvprobe()
300 if (!wd) in au1xpsc_i2s_drvprobe()
303 wd->mmio = devm_platform_ioremap_resource(pdev, 0); in au1xpsc_i2s_drvprobe()
304 if (IS_ERR(wd->mmio)) in au1xpsc_i2s_drvprobe()
305 return PTR_ERR(wd->mmio); in au1xpsc_i2s_drvprobe()
310 wd->dmaids[SNDRV_PCM_STREAM_PLAYBACK] = dmares->start; in au1xpsc_i2s_drvprobe()
315 wd->dmaids[SNDRV_PCM_STREAM_CAPTURE] = dmares->start; in au1xpsc_i2s_drvprobe()
320 sel = __raw_readl(PSC_SEL(wd)) & PSC_SEL_CLK_MASK; in au1xpsc_i2s_drvprobe()
321 __raw_writel(PSC_CTRL_DISABLE, PSC_CTRL(wd)); in au1xpsc_i2s_drvprobe()
[all …]
H A Dpsc-ac97.c367 struct au1xpsc_audio_data *wd; in au1xpsc_ac97_drvprobe() local
369 wd = devm_kzalloc(&pdev->dev, sizeof(struct au1xpsc_audio_data), in au1xpsc_ac97_drvprobe()
371 if (!wd) in au1xpsc_ac97_drvprobe()
374 mutex_init(&wd->lock); in au1xpsc_ac97_drvprobe()
376 wd->mmio = devm_platform_ioremap_resource(pdev, 0); in au1xpsc_ac97_drvprobe()
377 if (IS_ERR(wd->mmio)) in au1xpsc_ac97_drvprobe()
378 return PTR_ERR(wd->mmio); in au1xpsc_ac97_drvprobe()
383 wd->dmaids[SNDRV_PCM_STREAM_PLAYBACK] = dmares->start; in au1xpsc_ac97_drvprobe()
388 wd->dmaids[SNDRV_PCM_STREAM_CAPTURE] = dmares->start; in au1xpsc_ac97_drvprobe()
391 wd->cfg = PSC_AC97CFG_RT_FIFO8 | PSC_AC97CFG_TT_FIFO8 | in au1xpsc_ac97_drvprobe()
[all …]
/OK3568_Linux_fs/kernel/arch/mips/include/asm/
H A Dasmmacro.h261 .macro ld_b wd, off, base
266 ld.b $w\wd, \off(\base)
270 .macro ld_h wd, off, base
275 ld.h $w\wd, \off(\base)
279 .macro ld_w wd, off, base
284 ld.w $w\wd, \off(\base)
288 .macro ld_d wd, off, base
293 ld.d $w\wd, \off(\base)
297 .macro st_b wd, off, base
302 st.b $w\wd, \off(\base)
[all …]
/OK3568_Linux_fs/u-boot/drivers/watchdog/
H A Dftwdt010_wdt.c30 struct ftwdt010_wdt *wd = (struct ftwdt010_wdt *)CONFIG_FTWDT010_BASE; in ftwdt010_wdt_settimeout() local
35 if (readl(&wd->wdcr) & ~FTWDT010_WDCR_ENABLE) { in ftwdt010_wdt_settimeout()
47 writel(reg, &wd->wdload); in ftwdt010_wdt_settimeout()
54 struct ftwdt010_wdt *wd = (struct ftwdt010_wdt *)CONFIG_FTWDT010_BASE; in ftwdt010_wdt_reset() local
57 writel(0, &wd->wdcr); in ftwdt010_wdt_reset()
60 writel(FTWDT010_WDRESTART_MAGIC, &wd->wdrestart); in ftwdt010_wdt_reset()
63 writel((FTWDT010_WDCR_RST | FTWDT010_WDCR_ENABLE), &wd->wdcr); in ftwdt010_wdt_reset()
68 struct ftwdt010_wdt *wd = (struct ftwdt010_wdt *)CONFIG_FTWDT010_BASE; in ftwdt010_wdt_disable() local
78 writel(0, &wd->wdcr); in ftwdt010_wdt_disable()
H A Dat91sam9_wdt.c46 at91_wdt_t *wd = (at91_wdt_t *) ATMEL_BASE_WDT; in at91_wdt_settimeout() local
49 if (readl(&wd->mr) & AT91_WDT_MR_WDDIS) { in at91_wdt_settimeout()
66 writel(reg, &wd->mr); in at91_wdt_settimeout()
73 at91_wdt_t *wd = (at91_wdt_t *) ATMEL_BASE_WDT; in hw_watchdog_reset() local
74 writel(AT91_WDT_CR_WDRSTT | AT91_WDT_CR_KEY, &wd->cr); in hw_watchdog_reset()
/OK3568_Linux_fs/kernel/fs/hfsplus/
H A Dwrapper.c95 static int hfsplus_read_mdb(void *bufptr, struct hfsplus_wd *wd) in hfsplus_read_mdb() argument
111 wd->ablk_size = in hfsplus_read_mdb()
113 if (wd->ablk_size < HFSPLUS_SECTOR_SIZE) in hfsplus_read_mdb()
115 if (wd->ablk_size % HFSPLUS_SECTOR_SIZE) in hfsplus_read_mdb()
117 wd->ablk_start = in hfsplus_read_mdb()
121 wd->embed_start = (extent >> 16) & 0xFFFF; in hfsplus_read_mdb()
122 wd->embed_count = extent & 0xFFFF; in hfsplus_read_mdb()
166 struct hfsplus_wd wd; in hfsplus_read_wrapper() local
202 if (!hfsplus_read_mdb(sbi->s_vhdr, &wd)) in hfsplus_read_wrapper()
204 wd.ablk_size >>= HFSPLUS_SECTOR_SHIFT; in hfsplus_read_wrapper()
[all …]
/OK3568_Linux_fs/kernel/kernel/
H A Dusermode_driver.c64 if (WARN_ON_ONCE(info->wd.dentry || info->wd.mnt)) in umd_load_blob()
71 info->wd.mnt = mnt; in umd_load_blob()
72 info->wd.dentry = mnt->mnt_root; in umd_load_blob()
84 if (WARN_ON_ONCE(!info->wd.mnt || in umd_unload_blob()
85 !info->wd.dentry || in umd_unload_blob()
86 info->wd.mnt->mnt_root != info->wd.dentry)) in umd_unload_blob()
89 kern_unmount(info->wd.mnt); in umd_unload_blob()
90 info->wd.mnt = NULL; in umd_unload_blob()
91 info->wd.dentry = NULL; in umd_unload_blob()
130 set_fs_pwd(current->fs, &umd_info->wd); in umd_setup()
/OK3568_Linux_fs/kernel/drivers/acpi/arm64/
H A Dgtdt.c64 struct acpi_gtdt_watchdog *wd = platform_timer; in is_non_secure_watchdog() local
69 return !(wd->timer_flags & ACPI_GTDT_WATCHDOG_SECURE); in is_non_secure_watchdog()
328 static int __init gtdt_import_sbsa_gwdt(struct acpi_gtdt_watchdog *wd, in gtdt_import_sbsa_gwdt() argument
339 DEFINE_RES_MEM(wd->control_frame_address, SZ_4K), in gtdt_import_sbsa_gwdt()
340 DEFINE_RES_MEM(wd->refresh_frame_address, SZ_4K), in gtdt_import_sbsa_gwdt()
346 wd->refresh_frame_address, wd->control_frame_address, in gtdt_import_sbsa_gwdt()
347 wd->timer_interrupt, wd->timer_flags); in gtdt_import_sbsa_gwdt()
349 if (!(wd->refresh_frame_address && wd->control_frame_address)) { in gtdt_import_sbsa_gwdt()
354 irq = map_gt_gsi(wd->timer_interrupt, wd->timer_flags); in gtdt_import_sbsa_gwdt()
369 acpi_unregister_gsi(wd->timer_interrupt); in gtdt_import_sbsa_gwdt()
/OK3568_Linux_fs/kernel/arch/mips/sgi-ip30/
H A Dip30-xtalk.c42 struct sgi_w1_platform_data *wd; in bridge_platform_create() local
46 wd = kzalloc(sizeof(*wd), GFP_KERNEL); in bridge_platform_create()
47 if (!wd) in bridge_platform_create()
50 snprintf(wd->dev_id, sizeof(wd->dev_id), "bridge-%012lx", in bridge_platform_create()
61 kfree(wd); in bridge_platform_create()
65 platform_device_add_data(pdev, wd, sizeof(*wd)); in bridge_platform_create()
/OK3568_Linux_fs/kernel/fs/notify/inotify/
H A Dinotify_user.c185 inotify_event.wd = event->wd; in copy_event_to_user()
370 i_mark->wd = ret; in inotify_add_to_idr()
380 int wd) in inotify_idr_find_locked() argument
388 i_mark = idr_find(idr, wd); in inotify_idr_find_locked()
401 int wd) in inotify_idr_find() argument
407 i_mark = inotify_idr_find_locked(group, wd); in inotify_idr_find()
423 int wd; in inotify_remove_from_idr() local
426 wd = i_mark->wd; in inotify_remove_from_idr()
432 if (wd == -1) { in inotify_remove_from_idr()
434 __func__, i_mark, i_mark->wd, i_mark->fsn_mark.group); in inotify_remove_from_idr()
[all …]
/OK3568_Linux_fs/kernel/drivers/watchdog/
H A Dintel-mid_wdt.c37 struct watchdog_device wd; member
51 static int wdt_start(struct watchdog_device *wd) in wdt_start() argument
53 struct mid_wdt *mid = watchdog_get_drvdata(wd); in wdt_start()
55 int timeout = wd->timeout; in wdt_start()
77 static int wdt_ping(struct watchdog_device *wd) in wdt_ping() argument
79 struct mid_wdt *mid = watchdog_get_drvdata(wd); in wdt_ping()
89 static int wdt_stop(struct watchdog_device *wd) in wdt_stop() argument
91 struct mid_wdt *mid = watchdog_get_drvdata(wd); in wdt_stop()
145 wdt_dev = &mid->wd; in mid_wdt_probe()
/OK3568_Linux_fs/kernel/arch/mips/sgi-ip27/
H A Dip27-xtalk.c29 struct sgi_w1_platform_data *wd; in bridge_platform_create() local
37 wd = kzalloc(sizeof(*wd), GFP_KERNEL); in bridge_platform_create()
38 if (!wd) { in bridge_platform_create()
43 snprintf(wd->dev_id, sizeof(wd->dev_id), "bridge-%012lx", in bridge_platform_create()
61 if (platform_device_add_data(pdev_wd, wd, sizeof(*wd))) { in bridge_platform_create()
70 kfree(wd); in bridge_platform_create()
124 kfree(wd); in bridge_platform_create()
/OK3568_Linux_fs/kernel/include/net/
H A Dpkt_sched.h73 void qdisc_watchdog_init_clockid(struct qdisc_watchdog *wd, struct Qdisc *qdisc,
75 void qdisc_watchdog_init(struct qdisc_watchdog *wd, struct Qdisc *qdisc);
77 void qdisc_watchdog_schedule_range_ns(struct qdisc_watchdog *wd, u64 expires,
80 static inline void qdisc_watchdog_schedule_ns(struct qdisc_watchdog *wd, in qdisc_watchdog_schedule_ns() argument
83 return qdisc_watchdog_schedule_range_ns(wd, expires, 0ULL); in qdisc_watchdog_schedule_ns()
86 static inline void qdisc_watchdog_schedule(struct qdisc_watchdog *wd, in qdisc_watchdog_schedule() argument
89 qdisc_watchdog_schedule_ns(wd, PSCHED_TICKS2NS(expires)); in qdisc_watchdog_schedule()
92 void qdisc_watchdog_cancel(struct qdisc_watchdog *wd);
/OK3568_Linux_fs/yocto/poky/bitbake/lib/
H A Dpyinotify.py138 def inotify_rm_watch(self, fd, wd): argument
139 return self._inotify_rm_watch(fd, wd)
164 wd = inotify_syscalls.inotify_add_watch(fd, pathname, mask)
168 return wd
170 def _inotify_rm_watch(self, fd, wd): argument
172 ret = inotify_syscalls.inotify_rm_watch(fd, wd)
233 def _inotify_rm_watch(self, fd, wd): argument
235 return self._libc.inotify_rm_watch(fd, wd)
493 def __init__(self, wd, mask, cookie, name): argument
511 d = {'wd': wd,
[all …]
/OK3568_Linux_fs/kernel/drivers/net/wireless/mediatek/mt76/mt7615/
H A Dusb_sdio.c66 struct mt7615_wtbl_desc *wd) in mt7663_usb_sdio_set_rates() argument
68 struct mt7615_rate_desc *rate = &wd->rate; in mt7663_usb_sdio_set_rates()
69 struct mt7615_sta *sta = wd->sta; in mt7663_usb_sdio_set_rates()
137 struct mt7615_wtbl_desc *wd) in mt7663_usb_sdio_set_key() argument
139 struct mt7615_key_desc *key = &wd->key; in mt7663_usb_sdio_set_key()
140 struct mt7615_sta *sta = wd->sta; in mt7663_usb_sdio_set_key()
158 wcid = &wd->sta->wcid; in mt7663_usb_sdio_set_key()
183 struct mt7615_wtbl_desc *wd, *wd_next; in mt7663_usb_sdio_wtbl_work() local
195 list_for_each_entry_safe(wd, wd_next, &wd_list, node) { in mt7663_usb_sdio_wtbl_work()
196 list_del(&wd->node); in mt7663_usb_sdio_wtbl_work()
[all …]
/OK3568_Linux_fs/u-boot/doc/
H A DREADME.scrapyard55 imx27lite arm arm926ejs bc0840bc 2015-08-30 Wolfgang Denk <wd@denx.de>
75 qong arm arm1136 daf77086 2015-08-30 Wolfgang Denk <wd@denx.de>
123 P3G4 powerpc 74xx_7xx d928664f 2015-01-16 Wolfgang Denk <wd@denx.de>
150 CU824 powerpc mpc824x d622ac39 2015-01-05 Wolfgang Denk <wd@denx.de>
154 Sandpoint8240 powerpc mpc824x d622ac39 2015-01-05 Wolfgang Denk <wd@denx.de>
157 atc powerpc mpc8260 9067b300 2015-01-05 Wolfgang Denk <wd@denx.de>
158 CPU86 powerpc mpc8260 f7e1af86 2015-01-05 Wolfgang Denk <wd@denx.de>
164 PM825 powerpc mpc8260 dc0b2fb4 2015-01-05 Wolfgang Denk <wd@denx.de>
165 PM826 powerpc mpc8260 dc0b2fb4 2015-01-05 Wolfgang Denk <wd@denx.de>
175 IP860 powerpc mpc8xx 5ec71100 2015-01-05 Wolfgang Denk <wd@denx.de>
[all …]
/OK3568_Linux_fs/kernel/drivers/hid/
H A Dhid-logitech-hidpp.c1937 struct hidpp_ff_work_data *wd = container_of(w, struct hidpp_ff_work_data, work); in hidpp_ff_work_handler() local
1938 struct hidpp_ff_private_data *data = wd->data; in hidpp_ff_work_handler()
1944 switch (wd->effect_id) { in hidpp_ff_work_handler()
1946 wd->params[0] = data->slot_autocenter; in hidpp_ff_work_handler()
1953 wd->params[0] = hidpp_ff_find_effect(data, wd->effect_id); in hidpp_ff_work_handler()
1959 wd->command, wd->params, wd->size, &response); in hidpp_ff_work_handler()
1967 switch (wd->command) { in hidpp_ff_work_handler()
1971 if (wd->effect_id >= 0) in hidpp_ff_work_handler()
1973 data->effect_ids[slot-1] = wd->effect_id; in hidpp_ff_work_handler()
1974 else if (wd->effect_id >= HIDPP_FF_EFFECTID_AUTOCENTER) in hidpp_ff_work_handler()
[all …]
/OK3568_Linux_fs/kernel/lib/raid6/
H A Dneon.uc62 register unative_t wd$$, wq$$, wp$$, w1$$, w2$$;
72 wd$$ = vld1q_u8(&dptr[z][d+$$*NSIZE]);
73 wp$$ = veorq_u8(wp$$, wd$$);
79 wq$$ = veorq_u8(w1$$, wd$$);
93 register unative_t wd$$, wq$$, wp$$, w1$$, w2$$;
106 wd$$ = vld1q_u8(&dptr[z][d+$$*NSIZE]);
107 wp$$ = veorq_u8(wp$$, wd$$);
113 wq$$ = veorq_u8(w1$$, wd$$);
H A Dint.uc88 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$$;
/OK3568_Linux_fs/yocto/poky/bitbake/lib/bb/fetch2/
H A Dgitannex.py27 def uses_annex(self, ud, d, wd): argument
30 runfetchcmd("%s rev-list git-annex" % (ud.basecmd), d, quiet=True, workdir=wd)
37 def update_annex(self, ud, d, wd): argument
39 runfetchcmd("%s annex get --all" % (ud.basecmd), d, quiet=True, workdir=wd)
42 runfetchcmd("chmod u+w -R %s/annex" % (ud.clonedir), d, quiet=True, workdir=wd)

123456