Home
last modified time | relevance | path

Searched refs:pm (Results 1 – 25 of 1828) sorted by relevance

12345678910>>...74

/linux/drivers/input/touchscreen/
H A Dpenmount.c50 struct pm { struct
59 void (*parse_packet)(struct pm *); argument
66 static void pm_mtevent(struct pm *pm, struct input_dev *input) in pm_mtevent() argument
70 for (i = 0; i < pm->maxcontacts; ++i) { in pm_mtevent()
73 pm->slots[i].active); in pm_mtevent()
74 if (pm->slots[i].active) { in pm_mtevent()
75 input_event(input, EV_ABS, ABS_MT_POSITION_X, pm->slots[i].x); in pm_mtevent()
76 input_event(input, EV_ABS, ABS_MT_POSITION_Y, pm->slots[i].y); in pm_mtevent()
99 static void pm_parse_9000(struct pm *pm) in pm_parse_9000() argument
101 struct input_dev *dev = pm->dev; in pm_parse_9000()
[all …]
/linux/drivers/input/misc/
H A Dpowermate.c88 struct powermate_device *pm = urb->context; in powermate_irq() local
89 struct device *dev = &pm->intf->dev; in powermate_irq()
110 input_report_key(pm->input, BTN_0, pm->data[0] & 0x01); in powermate_irq()
111 input_report_rel(pm->input, REL_DIAL, pm->data[1]); in powermate_irq()
112 input_sync(pm->input); in powermate_irq()
122 static void powermate_sync_state(struct powermate_device *pm) in powermate_sync_state() argument
124 if (pm->requires_update == 0) in powermate_sync_state()
126 if (pm->config->status == -EINPROGRESS) in powermate_sync_state()
129 if (pm->requires_update & UPDATE_PULSE_ASLEEP){ in powermate_sync_state()
130 pm->configcr->wValue = cpu_to_le16( SET_PULSE_ASLEEP ); in powermate_sync_state()
[all …]
/linux/drivers/hid/
H A Dhid-prodikeys.c37 struct pcmidi_snd *pm; member
94 struct pcmidi_snd *pm = hid_get_drvdata(hdev); in show_channel() local
96 dbg_hid("pcmidi sysfs read channel=%u\n", pm->midi_channel); in show_channel()
98 return sprintf(buf, "%u (min:%u, max:%u)\n", pm->midi_channel, in show_channel()
107 struct pcmidi_snd *pm = hid_get_drvdata(hdev); in store_channel() local
113 pm->midi_channel = channel; in store_channel()
131 struct pcmidi_snd *pm = hid_get_drvdata(hdev); in show_sustain() local
133 dbg_hid("pcmidi sysfs read sustain=%u\n", pm->midi_sustain); in show_sustain()
135 return sprintf(buf, "%u (off:%u, max:%u (ms))\n", pm->midi_sustain, in show_sustain()
144 struct pcmidi_snd *pm = hid_get_drvdata(hdev); in store_sustain() local
[all …]
/linux/sound/drivers/
H A Dportman2x4.c77 static int portman_free(struct portman *pm) in portman_free() argument
79 kfree(pm); in portman_free()
87 struct portman *pm; in portman_create() local
91 pm = kzalloc_obj(struct portman); in portman_create()
92 if (pm == NULL) in portman_create()
96 spin_lock_init(&pm->reg_lock); in portman_create()
97 pm->card = card; in portman_create()
98 pm->pardev = pardev; in portman_create()
100 *rchip = pm; in portman_create()
180 static inline void portman_write_command(struct portman *pm, u8 value) in portman_write_command() argument
[all …]
/linux/drivers/media/platform/samsung/s5p-mfc/
H A Ds5p_mfc_pm.c19 struct s5p_mfc_pm *pm = &dev->pm; in s5p_mfc_init_pm() local
22 pm->num_clocks = dev->variant->num_clocks; in s5p_mfc_init_pm()
23 pm->clk_names = dev->variant->clk_names; in s5p_mfc_init_pm()
24 pm->device = &dev->plat_dev->dev; in s5p_mfc_init_pm()
25 pm->clock_gate = NULL; in s5p_mfc_init_pm()
28 for (i = 0; i < pm->num_clocks; i++) { in s5p_mfc_init_pm()
29 pm->clocks[i] = devm_clk_get(pm->device, pm->clk_names[i]); in s5p_mfc_init_pm()
30 if (IS_ERR(pm->clocks[i])) { in s5p_mfc_init_pm()
32 if (i && PTR_ERR(pm->clocks[i]) == -ENOENT) { in s5p_mfc_init_pm()
33 pm->clocks[i] = NULL; in s5p_mfc_init_pm()
[all …]
/linux/drivers/gpu/drm/amd/pm/legacy-dpm/
H A Dlegacy_dpm.c105 rps == adev->pm.dpm.current_ps ? " c" : "", in amdgpu_dpm_dbg_print_ps_status()
106 rps == adev->pm.dpm.requested_ps ? " r" : "", in amdgpu_dpm_dbg_print_ps_status()
107 rps == adev->pm.dpm.boot_ps ? " b" : ""); in amdgpu_dpm_dbg_print_ps_status()
117 for (i = 0; i < adev->pm.dpm.num_ps; i++) in amdgpu_pm_print_power_states()
118 amdgpu_dpm_print_power_state(adev, &adev->pm.dpm.ps[i]); in amdgpu_pm_print_power_states()
146 adev->pm.dpm.platform_caps = le32_to_cpu(power_info->pplib.ulPlatformCaps); in amdgpu_get_platform_caps()
147 adev->pm.dpm.backbias_response_time = le16_to_cpu(power_info->pplib.usBackbiasTime); in amdgpu_get_platform_caps()
148 adev->pm.dpm.voltage_response_time = le16_to_cpu(power_info->pplib.usVoltageTime); in amdgpu_get_platform_caps()
216 adev->pm.dpm.fan.t_hyst = fan_info->fan.ucTHyst; in amdgpu_parse_extended_power_table()
217 adev->pm.dpm.fan.t_min = le16_to_cpu(fan_info->fan.usTMin); in amdgpu_parse_extended_power_table()
[all …]
/linux/drivers/scsi/
H A Dscsi_pm.c22 static int do_scsi_suspend(struct device *dev, const struct dev_pm_ops *pm) in do_scsi_suspend() argument
24 return pm && pm->suspend ? pm->suspend(dev) : 0; in do_scsi_suspend()
27 static int do_scsi_freeze(struct device *dev, const struct dev_pm_ops *pm) in do_scsi_freeze() argument
29 return pm && pm->freeze ? pm->freeze(dev) : 0; in do_scsi_freeze()
32 static int do_scsi_poweroff(struct device *dev, const struct dev_pm_ops *pm) in do_scsi_poweroff() argument
34 return pm && pm->poweroff ? pm->poweroff(dev) : 0; in do_scsi_poweroff()
37 static int do_scsi_resume(struct device *dev, const struct dev_pm_ops *pm) in do_scsi_resume() argument
39 return pm && pm->resume ? pm->resume(dev) : 0; in do_scsi_resume()
42 static int do_scsi_thaw(struct device *dev, const struct dev_pm_ops *pm) in do_scsi_thaw() argument
44 return pm && pm->thaw ? pm->thaw(dev) : 0; in do_scsi_thaw()
[all …]
/linux/net/mptcp/
H A Dpm.c142 lockdep_assert_held(&msk->pm.lock); in mptcp_lookup_anno_list_by_saddr()
144 list_for_each_entry(entry, &msk->pm.anno_list, list) { in mptcp_lookup_anno_list_by_saddr()
173 spin_lock_bh(&msk->pm.lock); in mptcp_pm_sport_in_anno_list()
174 list_for_each_entry(entry, &msk->pm.anno_list, list) { in mptcp_pm_sport_in_anno_list()
182 spin_unlock_bh(&msk->pm.lock); in mptcp_pm_sport_in_anno_list()
211 spin_unlock_bh(&msk->pm.lock); in mptcp_pm_send_ack()
213 spin_lock_bh(&msk->pm.lock); in mptcp_pm_send_ack()
236 lockdep_assert_held(&msk->pm.lock); in mptcp_pm_addr_send_ack_avoid_list()
365 spin_lock_bh(&msk->pm.lock); in mptcp_pm_add_timer()
385 spin_unlock_bh(&msk->pm.lock); in mptcp_pm_add_timer()
[all …]
H A Dpm_kernel.c134 if (!test_bit(entry->addr.id, msk->pm.id_avail_bitmap)) in select_local_address()
162 if (!test_bit(entry->addr.id, msk->pm.id_avail_bitmap)) in select_signal_address()
183 bool deny_id0 = READ_ONCE(msk->pm.remote_deny_join_id0); in fill_remote_addr()
195 msk->pm.extra_subflows++; in fill_remote_addr()
207 bool deny_id0 = READ_ONCE(msk->pm.remote_deny_join_id0); in fill_remote_addresses_fullmesh()
236 msk->pm.extra_subflows++; in fill_remote_addresses_fullmesh()
239 if (msk->pm.extra_subflows >= limit_extra_subflows) in fill_remote_addresses_fullmesh()
305 if (likely(msk->pm.status & BIT(MPTCP_PM_MPC_ENDPOINT_ACCOUNTED)) || in mptcp_mpc_endpoint_setup()
316 __clear_bit(entry->addr.id, msk->pm.id_avail_bitmap); in mptcp_mpc_endpoint_setup()
326 msk->pm.status |= BIT(MPTCP_PM_MPC_ENDPOINT_ACCOUNTED); in mptcp_mpc_endpoint_setup()
[all …]
H A Dpm_userspace.c13 &((__msk)->pm.userspace_pm_local_addr_list), list)
21 spin_lock_bh(&msk->pm.lock); in mptcp_userspace_pm_free_local_addr_list()
22 list_splice_init(&msk->pm.userspace_pm_local_addr_list, &free_list); in mptcp_userspace_pm_free_local_addr_list()
23 spin_unlock_bh(&msk->pm.lock); in mptcp_userspace_pm_free_local_addr_list()
56 spin_lock_bh(&msk->pm.lock); in mptcp_userspace_pm_append_new_local_addr()
81 list_add_tail_rcu(&e->list, &msk->pm.userspace_pm_local_addr_list); in mptcp_userspace_pm_append_new_local_addr()
82 msk->pm.local_addr_used++; in mptcp_userspace_pm_append_new_local_addr()
89 spin_unlock_bh(&msk->pm.lock); in mptcp_userspace_pm_append_new_local_addr()
113 msk->pm.local_addr_used--; in mptcp_userspace_pm_delete_local_addr()
136 spin_lock_bh(&msk->pm.lock); in mptcp_userspace_pm_get_local_id()
[all …]
/linux/tools/power/pm-graph/
H A DMakefile36 $(INSTALL) -d $(DESTDIR)$(LIBDIR)/pm-graph
37 $(INSTALL) sleepgraph.py $(DESTDIR)$(LIBDIR)/pm-graph
38 $(INSTALL) bootgraph.py $(DESTDIR)$(LIBDIR)/pm-graph
39 $(INSTALL) -d $(DESTDIR)$(LIBDIR)/pm-graph/config
40 $(INSTALL_DATA) config/cgskip.txt $(DESTDIR)$(LIBDIR)/pm-graph/config
41 $(INSTALL_DATA) config/freeze-callgraph.cfg $(DESTDIR)$(LIBDIR)/pm-graph/config
42 $(INSTALL_DATA) config/freeze.cfg $(DESTDIR)$(LIBDIR)/pm-graph/config
43 $(INSTALL_DATA) config/freeze-dev.cfg $(DESTDIR)$(LIBDIR)/pm-graph/config
44 $(INSTALL_DATA) config/standby-callgraph.cfg $(DESTDIR)$(LIBDIR)/pm-graph/config
45 $(INSTALL_DATA) config/standby.cfg $(DESTDIR)$(LIBDIR)/pm-graph/config
[all …]
/linux/drivers/pci/
H A Dpci-driver.c738 pci_WARN(pci_dev, ret && drv->driver.pm, "device %04x:%04x\n", in pci_has_legacy_pm_support()
749 const struct dev_pm_ops *pm = dev->driver ? dev->driver->pm : NULL; in pci_pm_prepare() local
753 if (pm && pm->prepare) { in pci_pm_prepare()
754 int error = pm->prepare(dev); in pci_pm_prepare()
822 const struct dev_pm_ops *pm = dev->driver ? dev->driver->pm : NULL; in pci_pm_suspend() local
835 if (!pm) { in pci_pm_suspend()
860 if (pm->suspend) { in pci_pm_suspend()
864 error = pm->suspend(dev); in pci_pm_suspend()
865 suspend_report_result(dev, pm->suspend, error); in pci_pm_suspend()
873 pm->suspend); in pci_pm_suspend()
[all …]
/linux/drivers/gpu/drm/radeon/
H A Dr600.c366 rdev->pm.dynpm_can_upclock = true; in r600_pm_get_dynpm_state()
367 rdev->pm.dynpm_can_downclock = true; in r600_pm_get_dynpm_state()
373 if (rdev->pm.num_power_states > 2) in r600_pm_get_dynpm_state()
376 switch (rdev->pm.dynpm_planned_action) { in r600_pm_get_dynpm_state()
378 rdev->pm.requested_power_state_index = min_power_state_index; in r600_pm_get_dynpm_state()
379 rdev->pm.requested_clock_mode_index = 0; in r600_pm_get_dynpm_state()
380 rdev->pm.dynpm_can_downclock = false; in r600_pm_get_dynpm_state()
383 if (rdev->pm.current_power_state_index == min_power_state_index) { in r600_pm_get_dynpm_state()
384 rdev->pm.requested_power_state_index = rdev->pm.current_power_state_index; in r600_pm_get_dynpm_state()
385 rdev->pm.dynpm_can_downclock = false; in r600_pm_get_dynpm_state()
[all …]
H A Dr600_dpm.c145 if (rps == rdev->pm.dpm.current_ps) in r600_dpm_print_ps_status()
147 if (rps == rdev->pm.dpm.requested_ps) in r600_dpm_print_ps_status()
149 if (rps == rdev->pm.dpm.boot_ps) in r600_dpm_print_ps_status()
756 rdev->pm.dpm.thermal.min_temp = low_temp; in r600_set_thermal_temperature_range()
757 rdev->pm.dpm.thermal.max_temp = high_temp; in r600_set_thermal_temperature_range()
790 r600_is_internal_thermal_sensor(rdev->pm.int_thermal_type)) { in r600_dpm_late_enable()
855 rdev->pm.dpm.platform_caps = le32_to_cpu(power_info->pplib.ulPlatformCaps); in r600_get_platform_caps()
856 rdev->pm.dpm.backbias_response_time = le16_to_cpu(power_info->pplib.usBackbiasTime); in r600_get_platform_caps()
857 rdev->pm.dpm.voltage_response_time = le16_to_cpu(power_info->pplib.usVoltageTime); in r600_get_platform_caps()
892 rdev->pm.dpm.fan.t_hyst = fan_info->fan.ucTHyst; in r600_parse_extended_power_table()
[all …]
H A Dr420.c48 rdev->pm.profiles[PM_PROFILE_DEFAULT_IDX].dpms_off_ps_idx = rdev->pm.default_power_state_index; in r420_pm_init_profile()
49 rdev->pm.profiles[PM_PROFILE_DEFAULT_IDX].dpms_on_ps_idx = rdev->pm.default_power_state_index; in r420_pm_init_profile()
50 rdev->pm.profiles[PM_PROFILE_DEFAULT_IDX].dpms_off_cm_idx = 0; in r420_pm_init_profile()
51 rdev->pm.profiles[PM_PROFILE_DEFAULT_IDX].dpms_on_cm_idx = 0; in r420_pm_init_profile()
53 rdev->pm.profiles[PM_PROFILE_LOW_SH_IDX].dpms_off_ps_idx = 0; in r420_pm_init_profile()
54 rdev->pm.profiles[PM_PROFILE_LOW_SH_IDX].dpms_on_ps_idx = 0; in r420_pm_init_profile()
55 rdev->pm.profiles[PM_PROFILE_LOW_SH_IDX].dpms_off_cm_idx = 0; in r420_pm_init_profile()
56 rdev->pm.profiles[PM_PROFILE_LOW_SH_IDX].dpms_on_cm_idx = 0; in r420_pm_init_profile()
58 rdev->pm.profiles[PM_PROFILE_MID_SH_IDX].dpms_off_ps_idx = 0; in r420_pm_init_profile()
59 rdev->pm.profiles[PM_PROFILE_MID_SH_IDX].dpms_on_ps_idx = 1; in r420_pm_init_profile()
[all …]
H A Drs690.c82 rdev->pm.igp_sideport_mclk.full = dfixed_const(le32_to_cpu(info->info.ulBootUpMemoryClock)); in rs690_pm_info()
83 rdev->pm.igp_sideport_mclk.full = dfixed_div(rdev->pm.igp_sideport_mclk, tmp); in rs690_pm_info()
85 rdev->pm.igp_system_mclk.full = dfixed_const(le16_to_cpu(info->info.usK8MemoryClock)); in rs690_pm_info()
87 rdev->pm.igp_system_mclk.full = dfixed_const(rdev->clock.default_mclk); in rs690_pm_info()
88 rdev->pm.igp_system_mclk.full = dfixed_div(rdev->pm.igp_system_mclk, tmp); in rs690_pm_info()
90 rdev->pm.igp_system_mclk.full = dfixed_const(400); in rs690_pm_info()
91 rdev->pm.igp_ht_link_clk.full = dfixed_const(le16_to_cpu(info->info.usFSBClock)); in rs690_pm_info()
92 rdev->pm.igp_ht_link_width.full = dfixed_const(info->info.ucHTLinkWidth); in rs690_pm_info()
96 rdev->pm.igp_sideport_mclk.full = dfixed_const(le32_to_cpu(info->info_v2.ulBootUpSidePortClock)); in rs690_pm_info()
97 rdev->pm.igp_sideport_mclk.full = dfixed_div(rdev->pm.igp_sideport_mclk, tmp); in rs690_pm_info()
[all …]
H A Dradeon_atombios.c2045 rdev->pm.power_state[state_index].misc = misc; in radeon_atombios_parse_misc_flags_1_3()
2046 rdev->pm.power_state[state_index].misc2 = misc2; in radeon_atombios_parse_misc_flags_1_3()
2049 rdev->pm.power_state[state_index].type = in radeon_atombios_parse_misc_flags_1_3()
2052 rdev->pm.power_state[state_index].type = in radeon_atombios_parse_misc_flags_1_3()
2055 rdev->pm.power_state[state_index].type = in radeon_atombios_parse_misc_flags_1_3()
2058 rdev->pm.power_state[state_index].type = in radeon_atombios_parse_misc_flags_1_3()
2061 rdev->pm.power_state[state_index].type = in radeon_atombios_parse_misc_flags_1_3()
2063 rdev->pm.power_state[state_index].flags &= in radeon_atombios_parse_misc_flags_1_3()
2067 rdev->pm.power_state[state_index].type = in radeon_atombios_parse_misc_flags_1_3()
2070 rdev->pm.power_state[state_index].type = in radeon_atombios_parse_misc_flags_1_3()
[all …]
/linux/drivers/crypto/intel/qat/qat_common/
H A Dadf_pm_dbgfs.c14 struct adf_pm pm = accel_dev->power_management; in pm_status_read() local
16 if (pm.print_pm_status) in pm_status_read()
17 return pm.print_pm_status(accel_dev, buf, count, pos); in pm_status_read()
29 struct adf_pm *pm = &accel_dev->power_management; in adf_pm_dbgfs_add() local
31 if (!pm->present || !pm->print_pm_status) in adf_pm_dbgfs_add()
34 pm->debugfs_pm_status = debugfs_create_file("pm_status", 0400, in adf_pm_dbgfs_add()
41 struct adf_pm *pm = &accel_dev->power_management; in adf_pm_dbgfs_rm() local
43 if (!pm->present) in adf_pm_dbgfs_rm()
46 debugfs_remove(pm->debugfs_pm_status); in adf_pm_dbgfs_rm()
47 pm->debugfs_pm_status = NULL; in adf_pm_dbgfs_rm()
/linux/fs/hfs/
H A Dpart_tbl.c73 struct old_pmap *pm; in hfs_part_find() local
76 pm = (struct old_pmap *)bh->b_data; in hfs_part_find()
77 p = pm->pdEntry; in hfs_part_find()
92 struct new_pmap *pm; in hfs_part_find() local
94 pm = (struct new_pmap *)bh->b_data; in hfs_part_find()
95 size = be32_to_cpu(pm->pmMapBlkCnt); in hfs_part_find()
97 if (!memcmp(pm->pmPartType,"Apple_HFS", 9) && in hfs_part_find()
99 *part_start += be32_to_cpu(pm->pmPyPartStart); in hfs_part_find()
100 *part_size = be32_to_cpu(pm->pmPartBlkCnt); in hfs_part_find()
105 bh = sb_bread512(sb, *part_start + HFS_PMAP_BLK + ++i, pm); in hfs_part_find()
[all …]
/linux/fs/hfsplus/
H A Dpart_tbl.c70 static int hfs_parse_old_pmap(struct super_block *sb, struct old_pmap *pm, in hfs_parse_old_pmap() argument
77 struct old_pmap_entry *p = &pm->pdEntry[i]; in hfs_parse_old_pmap()
92 struct new_pmap *pm, sector_t *part_start, sector_t *part_size) in hfs_parse_new_pmap() argument
95 int size = be32_to_cpu(pm->pmMapBlkCnt); in hfs_parse_new_pmap()
101 if (!memcmp(pm->pmPartType, "Apple_HFS", 9) && in hfs_parse_new_pmap()
103 *part_start += be32_to_cpu(pm->pmPyPartStart); in hfs_parse_new_pmap()
104 *part_size = be32_to_cpu(pm->pmPartBlkCnt); in hfs_parse_new_pmap()
111 pm = (struct new_pmap *)((u8 *)pm + HFSPLUS_SECTOR_SIZE); in hfs_parse_new_pmap()
112 if ((u8 *)pm - (u8 *)buf >= buf_size) { in hfs_parse_new_pmap()
115 buf, (void **)&pm, REQ_OP_READ); in hfs_parse_new_pmap()
[all …]
/linux/tools/perf/util/
H A Dmetricgroup.c184 static bool metric__group_events(const struct pmu_metric *pm, bool metric_no_threshold) in metric__group_events() argument
186 switch (pm->event_grouping) { in metric__group_events()
192 metric__watchdog_constraint_hint(pm->metric_name, /*foot=*/false); in metric__group_events()
201 metric__watchdog_constraint_hint(pm->metric_name, /*foot=*/false); in metric__group_events()
221 static struct metric *metric__new(const struct pmu_metric *pm, in metric__new() argument
239 m->pmu = pm->pmu ?: "cpu"; in metric__new()
240 m->metric_name = pm->metric_name; in metric__new()
241 m->default_metricgroup_name = pm->default_metricgroup_name ?: ""; in metric__new()
248 m->metric_expr = pm->metric_expr; in metric__new()
249 m->metric_threshold = pm->metric_threshold; in metric__new()
[all …]
/linux/tools/testing/selftests/tc-testing/
H A Dtdc.py201 def exec_cmd(caseinfo, args, pm, stage, command): argument
211 command = pm.call_adjust_command(caseinfo, stage, command)
236 def prepare_env(caseinfo, args, pm, stage, prefix, cmdlist, output = None): argument
254 (proc, foutput) = exec_cmd(caseinfo, args, pm, stage, cmd)
271 def verify_by_json(procout, res, tidx, args, pm): argument
375 def run_one_test(pm, args, index, tidx): argument
394 pm.call_pre_case(tidx, test_skip=True)
395 pm.call_post_execute(tidx)
401 (p, procout) = exec_cmd(tidx, args, pm, 'execute', tidx['dependsOn'])
407 pm
480 prepare_run(pm, args, testlist) global() argument
499 purge_run(pm, index) global() argument
502 test_runner(pm, args, filtered_tests) global() argument
604 test_runner_mp(pm, args, alltests) global() argument
635 test_runner_serial(pm, args, alltests) global() argument
744 check_default_settings(args, remaining, pm) global() argument
915 set_operation_mode(pm, parser, args, remaining) global() argument
[all...]
/linux/drivers/greybus/
H A Dbundle.c111 const struct dev_pm_ops *pm = dev->driver->pm; in gb_bundle_suspend() local
114 if (pm && pm->runtime_suspend) { in gb_bundle_suspend()
115 ret = pm->runtime_suspend(&bundle->dev); in gb_bundle_suspend()
124 if (pm && pm->runtime_resume) in gb_bundle_suspend()
125 ret = pm->runtime_resume(dev); in gb_bundle_suspend()
138 const struct dev_pm_ops *pm = dev->driver->pm; in gb_bundle_resume() local
145 if (pm && pm->runtime_resume) { in gb_bundle_resume()
146 ret = pm->runtime_resume(dev); in gb_bundle_resume()
172 .pm = &gb_bundle_pm_ops,
/linux/arch/mips/pci/
H A Dpci-alchemy.c43 unsigned long pm[12]; member
313 ctx->pm[0] = __raw_readl(ctx->regs + PCI_REG_CMEM); in alchemy_pci_suspend()
314 ctx->pm[1] = __raw_readl(ctx->regs + PCI_REG_CONFIG) & 0x0009ffff; in alchemy_pci_suspend()
315 ctx->pm[2] = __raw_readl(ctx->regs + PCI_REG_B2BMASK_CCH); in alchemy_pci_suspend()
316 ctx->pm[3] = __raw_readl(ctx->regs + PCI_REG_B2BBASE0_VID); in alchemy_pci_suspend()
317 ctx->pm[4] = __raw_readl(ctx->regs + PCI_REG_B2BBASE1_SID); in alchemy_pci_suspend()
318 ctx->pm[5] = __raw_readl(ctx->regs + PCI_REG_MWMASK_DEV); in alchemy_pci_suspend()
319 ctx->pm[6] = __raw_readl(ctx->regs + PCI_REG_MWBASE_REV_CCL); in alchemy_pci_suspend()
320 ctx->pm[7] = __raw_readl(ctx->regs + PCI_REG_ID); in alchemy_pci_suspend()
321 ctx->pm[8] = __raw_readl(ctx->regs + PCI_REG_CLASSREV); in alchemy_pci_suspend()
[all …]
/linux/drivers/gpio/
H A Dgpio-amd8111.c70 void __iomem *pm; member
80 agp->orig[offset] = ioread8(agp->pm + AMD_REG_GPIO(offset)) & in amd_gpio_request()
94 iowrite8(agp->orig[offset], agp->pm + AMD_REG_GPIO(offset)); in amd_gpio_free()
104 temp = ioread8(agp->pm + AMD_REG_GPIO(offset)); in amd_gpio_set()
106 iowrite8(temp, agp->pm + AMD_REG_GPIO(offset)); in amd_gpio_set()
119 temp = ioread8(agp->pm + AMD_REG_GPIO(offset)); in amd_gpio_get()
133 temp = ioread8(agp->pm + AMD_REG_GPIO(offset)); in amd_gpio_dirout()
135 iowrite8(temp, agp->pm + AMD_REG_GPIO(offset)); in amd_gpio_dirout()
150 temp = ioread8(agp->pm + AMD_REG_GPIO(offset)); in amd_gpio_dirin()
152 iowrite8(temp, agp->pm + AMD_REG_GPIO(offset)); in amd_gpio_dirin()
[all …]

12345678910>>...74