Home
last modified time | relevance | path

Searched refs:state (Results 1051 - 1075 of 13257) sorted by relevance

1...<<41424344454647484950>>...531

/kernel/linux/linux-5.10/net/rfkill/
H A Dcore.c42 unsigned long state; member
107 "Default initial state for all radio types, 0 = radio off");
126 if (rfkill->state & RFKILL_BLOCK_ANY) in rfkill_led_trigger_event()
181 if (!(rfkill->state & RFKILL_BLOCK_ANY)) { in rfkill_global_led_trigger_worker()
265 ev->hard = !!(rfkill->state & RFKILL_BLOCK_HW); in rfkill_fill_event()
266 ev->soft = !!(rfkill->state & (RFKILL_BLOCK_SW | in rfkill_fill_event()
303 * @blocked: the new software state
319 * _hard_ kill state -- whenever something tries to change the in rfkill_set_block()
320 * current software state query the hardware state to in rfkill_set_block()
726 unsigned long state; soft_store() local
747 user_state_from_blocked(unsigned long state) user_state_from_blocked() argument
769 unsigned long state; state_store() local
814 u32 state; rfkill_dev_uevent() local
911 u32 state; rfkill_blocked() local
[all...]
/kernel/linux/linux-5.10/net/netfilter/
H A Dnf_conntrack_proto_tcp.c110 * The TCP state transition table needs a few words...
119 * try to guess the state of the current sender.
123 * NONE: initial state
152 * sES -> sIG Error: SYNs in window outside the SYN_SENT state
180 * sSS -> sIV Client migth not send FIN in this state:
189 * sLA -> sLA Retransmitted FIN. Remain in the same state.
199 * sSR -> sES Established state is reached.
204 * sTW -> sTW Retransmitted last ACK. Remain in the same state.
243 * sSS -> sIV Server might not send FIN in this state.
279 seq_printf(s, "%s ", tcp_conntrack_names[ct->proto.tcp.state]); in tcp_print_conntrack()
341 tcp_options(const struct sk_buff *skb, unsigned int dataoff, const struct tcphdr *tcph, struct ip_ct_tcp_state *state) tcp_options() argument
461 tcp_in_window(const struct nf_conn *ct, struct ip_ct_tcp *state, enum ip_conntrack_dir dir, unsigned int index, const struct sk_buff *skb, unsigned int dataoff, const struct tcphdr *tcph) tcp_in_window() argument
721 tcp_error_log(const struct sk_buff *skb, const struct nf_hook_state *state, const char *msg) tcp_error_log() argument
729 tcp_error(const struct tcphdr *th, struct sk_buff *skb, unsigned int dataoff, const struct nf_hook_state *state) tcp_error() argument
843 nf_ct_tcp_state_reset(struct ip_ct_tcp_state *state) nf_ct_tcp_state_reset() argument
854 nf_conntrack_tcp_packet(struct nf_conn *ct, struct sk_buff *skb, unsigned int dataoff, enum ip_conntrack_info ctinfo, const struct nf_hook_state *state) nf_conntrack_tcp_packet() argument
[all...]
/kernel/linux/linux-5.10/drivers/gpu/drm/rcar-du/
H A Drcar_du_crtc.c215 const struct drm_display_mode *mode = &rcrtc->crtc.state->adjusted_mode; in rcar_du_crtc_set_display_timing()
331 return plane->plane.state->normalized_zpos; in plane_zpos()
337 return to_rcar_plane_state(plane->plane.state)->format; in plane_format()
355 if (plane->plane.state->crtc != &rcrtc->crtc || in rcar_du_crtc_update_planes()
356 !plane->plane.state->visible) in rcar_du_crtc_update_planes()
372 struct drm_plane_state *state = plane->plane.state; in rcar_du_crtc_update_planes() local
373 unsigned int index = to_rcar_plane_state(state)->hwindex; in rcar_du_crtc_update_planes()
490 struct drm_crtc_state *state) in rcar_du_cmm_check()
492 struct drm_property_blob *drm_lut = state in rcar_du_cmm_check()
489 rcar_du_cmm_check(struct drm_crtc *crtc, struct drm_crtc_state *state) rcar_du_cmm_check() argument
690 rcar_du_crtc_atomic_check(struct drm_crtc *crtc, struct drm_crtc_state *state) rcar_du_crtc_atomic_check() argument
936 struct rcar_du_crtc_state *state; rcar_du_crtc_atomic_duplicate_state() local
952 rcar_du_crtc_atomic_destroy_state(struct drm_crtc *crtc, struct drm_crtc_state *state) rcar_du_crtc_atomic_destroy_state() argument
970 struct rcar_du_crtc_state *state; rcar_du_crtc_reset() local
1074 struct drm_atomic_state *state; rcar_du_crtc_set_crc_source() local
[all...]
/kernel/linux/linux-6.6/fs/quota/
H A Dquota.c121 struct qc_state state; in quota_getinfo() local
128 ret = sb->s_qcop->get_state(sb, &state); in quota_getinfo()
131 tstate = state.s_state + type; in quota_getinfo()
335 static int quota_state_to_flags(struct qc_state *state) in quota_state_to_flags() argument
339 if (state->s_state[USRQUOTA].flags & QCI_ACCT_ENABLED) in quota_state_to_flags()
341 if (state->s_state[USRQUOTA].flags & QCI_LIMITS_ENFORCED) in quota_state_to_flags()
343 if (state->s_state[GRPQUOTA].flags & QCI_ACCT_ENABLED) in quota_state_to_flags()
345 if (state->s_state[GRPQUOTA].flags & QCI_LIMITS_ENFORCED) in quota_state_to_flags()
347 if (state->s_state[PRJQUOTA].flags & QCI_ACCT_ENABLED) in quota_state_to_flags()
349 if (state in quota_state_to_flags()
357 struct qc_state state; quota_getstate() local
455 struct qc_state state; quota_getstatev() local
[all...]
/kernel/linux/linux-6.6/drivers/usb/storage/
H A Duas.c68 unsigned int state; member
118 if (!(cmdinfo->state & IS_IN_WORK_LIST)) in uas_do_work()
123 cmdinfo->state &= ~IS_IN_WORK_LIST; in uas_do_work()
148 cmdinfo->state |= IS_IN_WORK_LIST; in uas_add_work()
168 cmdinfo->state &= ~COMMAND_INFLIGHT; in uas_zap_pending()
210 (ci->state & SUBMIT_STATUS_URB) ? " s-st" : "", in uas_log_cmd_state()
211 (ci->state & ALLOC_DATA_IN_URB) ? " a-in" : "", in uas_log_cmd_state()
212 (ci->state & SUBMIT_DATA_IN_URB) ? " s-in" : "", in uas_log_cmd_state()
213 (ci->state & ALLOC_DATA_OUT_URB) ? " a-out" : "", in uas_log_cmd_state()
214 (ci->state in uas_log_cmd_state()
[all...]
/kernel/linux/linux-5.10/drivers/char/ipmi/
H A Dipmi_smic_sm.c5 * The state-machine driver for an IPMI SMIC driver
36 * SMIC_DEBUG_STATES - state machine
91 enum smic_states state; member
107 smic->state = SMIC_IDLE; in init_smic_data()
131 if ((smic->state != SMIC_IDLE) && (smic->state != SMIC_HOSED)) { in start_smic_transaction()
133 "SMIC in invalid state %d\n", smic->state); in start_smic_transaction()
149 smic->state = SMIC_START_OP; in start_smic_transaction()
221 smic->state in start_error_recovery()
[all...]
/kernel/linux/linux-5.10/arch/mips/kernel/
H A Dpm-cps.c25 * cps_nc_entry_fn - type of a generated non-coherent state entry function
33 * is non-zero and this is the entry function for the CPS_PM_NC_WAIT state,
34 * returns the number of VPEs that were in the wait state at the point this
41 * The entry point of the generated non-coherent idle state entry/exit
52 * state. Actually per-core rather than per-CPU.
65 /* Saved CPU state across the CPS_PM_POWER_GATED state */
79 bool cps_pm_support_state(enum cps_pm_state state) in cps_pm_support_state() argument
81 return test_bit(state, state_support); in cps_pm_support_state()
110 int cps_pm_enter_state(enum cps_pm_state state) in cps_pm_enter_state() argument
342 cps_gen_entry_code(unsigned cpu, enum cps_pm_state state) cps_gen_entry_code() argument
638 enum cps_pm_state state; cps_pm_online_cpu() local
[all...]
/kernel/linux/linux-6.6/arch/mips/kernel/
H A Dpm-cps.c25 * cps_nc_entry_fn - type of a generated non-coherent state entry function
33 * is non-zero and this is the entry function for the CPS_PM_NC_WAIT state,
34 * returns the number of VPEs that were in the wait state at the point this
41 * The entry point of the generated non-coherent idle state entry/exit
52 * state. Actually per-core rather than per-CPU.
65 /* Saved CPU state across the CPS_PM_POWER_GATED state */
79 bool cps_pm_support_state(enum cps_pm_state state) in cps_pm_support_state() argument
81 return test_bit(state, state_support); in cps_pm_support_state()
110 int cps_pm_enter_state(enum cps_pm_state state) in cps_pm_enter_state() argument
342 cps_gen_entry_code(unsigned cpu, enum cps_pm_state state) cps_gen_entry_code() argument
638 enum cps_pm_state state; cps_pm_online_cpu() local
[all...]
/kernel/linux/linux-5.10/drivers/media/platform/qcom/venus/
H A Dhfi.c56 if (core->state >= CORE_INIT) in hfi_core_init()
78 core->state = CORE_INIT; in hfi_core_init()
90 if (core->state == CORE_UNINIT) in hfi_core_deinit()
113 core->state = CORE_UNINIT; in hfi_core_deinit()
122 if (core->state != CORE_INIT) in hfi_core_suspend()
130 if (!force && core->state != CORE_INIT) in hfi_core_resume()
185 inst->state = INST_UNINIT; in hfi_session_create()
204 if (inst->state != INST_UNINIT) in hfi_session_init()
218 inst->state = INST_INIT; in hfi_session_init()
241 if (inst->state in hfi_session_deinit()
[all...]
/kernel/linux/linux-5.10/drivers/soc/qcom/
H A Drpmh.c30 .state = s, \
118 enum rpmh_state state, in cache_rpm_request()
144 switch (state) { in cache_rpm_request()
169 * @state: Active/Sleep request type
172 * Cache the RPMH request and send if the state is ACTIVE_ONLY.
176 static int __rpmh_write(const struct device *dev, enum rpmh_state state, in __rpmh_write() argument
184 rpm_msg->msg.state = state; in __rpmh_write()
188 req = cache_rpm_request(ctrlr, state, &rpm_msg->msg.cmds[i]); in __rpmh_write()
193 rpm_msg->msg.state in __rpmh_write()
117 cache_rpm_request(struct rpmh_ctrlr *ctrlr, enum rpmh_state state, struct tcs_cmd *cmd) cache_rpm_request() argument
207 __fill_rpmh_msg(struct rpmh_request *req, enum rpmh_state state, const struct tcs_cmd *cmd, u32 n) __fill_rpmh_msg() argument
233 rpmh_write_async(const struct device *dev, enum rpmh_state state, const struct tcs_cmd *cmd, u32 n) rpmh_write_async() argument
264 rpmh_write(const struct device *dev, enum rpmh_state state, const struct tcs_cmd *cmd, u32 n) rpmh_write() argument
335 rpmh_write_batch(const struct device *dev, enum rpmh_state state, const struct tcs_cmd *cmd, u32 *n) rpmh_write_batch() argument
419 send_single(struct rpmh_ctrlr *ctrlr, enum rpmh_state state, u32 addr, u32 data) send_single() argument
[all...]
/kernel/linux/linux-5.10/drivers/staging/vc04_services/interface/vchiq_arm/
H A Dvchiq_core.h144 #define VCHIQ_STATS_INC(state, stat) (state->stats. stat++)
149 #define VCHIQ_STATS_INC(state, stat) ((void)0)
289 struct vchiq_state *state; member
374 /* Debugging state */
532 vchiq_init_state(struct vchiq_state *state, struct vchiq_slot_zero *slot_zero);
535 vchiq_connect_internal(struct vchiq_state *state, struct vchiq_instance *instance);
538 vchiq_add_service_internal(struct vchiq_state *state,
556 vchiq_shutdown_internal(struct vchiq_state *state, struct vchiq_instance *instance);
559 remote_event_pollall(struct vchiq_state *state);
586 struct vchiq_state *state = vchiq_states[(handle / VCHIQ_MAX_SERVICES) & handle_to_service() local
[all...]
/kernel/linux/linux-5.10/drivers/gpu/drm/i2c/
H A Dch7006_drv.c57 struct ch7006_state *state = &priv->state; in ch7006_encoder_dpms() local
67 ch7006_load_reg(client, state, CH7006_POWER); in ch7006_encoder_dpms()
120 struct ch7006_state *state = &priv->state; in ch7006_encoder_mode_set() local
121 uint8_t *regs = state->regs; in ch7006_encoder_mode_set()
174 ch7006_state_load(client, state); in ch7006_encoder_mode_set()
182 struct ch7006_state *state = &priv->state; in ch7006_encoder_detect() local
187 ch7006_save_reg(client, state, CH7006_DETEC in ch7006_encoder_detect()
288 struct ch7006_state *state = &priv->state; ch7006_encoder_set_property() local
[all...]
/kernel/linux/linux-6.6/drivers/char/ipmi/
H A Dipmi_smic_sm.c5 * The state-machine driver for an IPMI SMIC driver
36 * SMIC_DEBUG_STATES - state machine
91 enum smic_states state; member
107 smic->state = SMIC_IDLE; in init_smic_data()
131 if ((smic->state != SMIC_IDLE) && (smic->state != SMIC_HOSED)) { in start_smic_transaction()
133 "SMIC in invalid state %d\n", smic->state); in start_smic_transaction()
149 smic->state = SMIC_START_OP; in start_smic_transaction()
221 smic->state in start_error_recovery()
[all...]
/kernel/linux/linux-6.6/drivers/media/platform/qcom/venus/
H A Dhfi.c56 if (core->state >= CORE_INIT) in hfi_core_init()
78 core->state = CORE_INIT; in hfi_core_init()
90 if (core->state == CORE_UNINIT) in hfi_core_deinit()
113 core->state = CORE_UNINIT; in hfi_core_deinit()
122 if (core->state != CORE_INIT) in hfi_core_suspend()
130 if (!force && core->state != CORE_INIT) in hfi_core_resume()
187 inst->state = INST_UNINIT; in hfi_session_create()
232 if (inst->state != INST_UNINIT) in hfi_session_init()
246 inst->state = INST_INIT; in hfi_session_init()
269 if (inst->state in hfi_session_deinit()
[all...]
/kernel/linux/linux-6.6/crypto/
H A Daegis128-neon-inner.c31 static struct aegis128_state aegis128_load_state_neon(const void *state) in aegis128_load_state_neon() argument
34 vld1q_u8(state), in aegis128_load_state_neon()
35 vld1q_u8(state + 16), in aegis128_load_state_neon()
36 vld1q_u8(state + 32), in aegis128_load_state_neon()
37 vld1q_u8(state + 48), in aegis128_load_state_neon()
38 vld1q_u8(state + 64) in aegis128_load_state_neon()
42 static void aegis128_save_state_neon(struct aegis128_state st, void *state) in aegis128_save_state_neon() argument
44 vst1q_u8(state, st.v[0]); in aegis128_save_state_neon()
45 vst1q_u8(state + 16, st.v[1]); in aegis128_save_state_neon()
46 vst1q_u8(state in aegis128_save_state_neon()
135 crypto_aegis128_init_neon(void *state, const void *key, const void *iv) crypto_aegis128_init_neon() argument
165 crypto_aegis128_update_neon(void *state, const void *msg) crypto_aegis128_update_neon() argument
222 crypto_aegis128_encrypt_chunk_neon(void *state, void *dst, const void *src, unsigned int size) crypto_aegis128_encrypt_chunk_neon() argument
271 crypto_aegis128_decrypt_chunk_neon(void *state, void *dst, const void *src, unsigned int size) crypto_aegis128_decrypt_chunk_neon() argument
317 crypto_aegis128_final_neon(void *state, void *tag_xor, unsigned int assoclen, unsigned int cryptlen, unsigned int authsize) crypto_aegis128_final_neon() argument
[all...]
/kernel/linux/linux-6.6/drivers/gpu/drm/i2c/
H A Dch7006_drv.c59 struct ch7006_state *state = &priv->state; in ch7006_encoder_dpms() local
69 ch7006_load_reg(client, state, CH7006_POWER); in ch7006_encoder_dpms()
122 struct ch7006_state *state = &priv->state; in ch7006_encoder_mode_set() local
123 uint8_t *regs = state->regs; in ch7006_encoder_mode_set()
176 ch7006_state_load(client, state); in ch7006_encoder_mode_set()
184 struct ch7006_state *state = &priv->state; in ch7006_encoder_detect() local
189 ch7006_save_reg(client, state, CH7006_DETEC in ch7006_encoder_detect()
290 struct ch7006_state *state = &priv->state; ch7006_encoder_set_property() local
[all...]
/kernel/linux/linux-6.6/drivers/gpu/drm/xlnx/
H A Dzynqmp_kms.c55 struct drm_atomic_state *state) in zynqmp_dpsub_plane_atomic_check()
57 struct drm_plane_state *new_plane_state = drm_atomic_get_new_plane_state(state, in zynqmp_dpsub_plane_atomic_check()
64 crtc_state = drm_atomic_get_crtc_state(state, new_plane_state->crtc); in zynqmp_dpsub_plane_atomic_check()
76 struct drm_atomic_state *state) in zynqmp_dpsub_plane_atomic_disable()
78 struct drm_plane_state *old_state = drm_atomic_get_old_plane_state(state, in zynqmp_dpsub_plane_atomic_disable()
90 plane->state->alpha >> 8); in zynqmp_dpsub_plane_atomic_disable()
94 struct drm_atomic_state *state) in zynqmp_dpsub_plane_atomic_update()
96 struct drm_plane_state *old_state = drm_atomic_get_old_plane_state(state, plane); in zynqmp_dpsub_plane_atomic_update()
97 struct drm_plane_state *new_state = drm_atomic_get_new_plane_state(state, plane); in zynqmp_dpsub_plane_atomic_update()
108 * disabled state t in zynqmp_dpsub_plane_atomic_update()
54 zynqmp_dpsub_plane_atomic_check(struct drm_plane *plane, struct drm_atomic_state *state) zynqmp_dpsub_plane_atomic_check() argument
75 zynqmp_dpsub_plane_atomic_disable(struct drm_plane *plane, struct drm_atomic_state *state) zynqmp_dpsub_plane_atomic_disable() argument
93 zynqmp_dpsub_plane_atomic_update(struct drm_plane *plane, struct drm_atomic_state *state) zynqmp_dpsub_plane_atomic_update() argument
190 zynqmp_dpsub_crtc_atomic_enable(struct drm_crtc *crtc, struct drm_atomic_state *state) zynqmp_dpsub_crtc_atomic_enable() argument
216 zynqmp_dpsub_crtc_atomic_disable(struct drm_crtc *crtc, struct drm_atomic_state *state) zynqmp_dpsub_crtc_atomic_disable() argument
246 zynqmp_dpsub_crtc_atomic_check(struct drm_crtc *crtc, struct drm_atomic_state *state) zynqmp_dpsub_crtc_atomic_check() argument
252 zynqmp_dpsub_crtc_atomic_begin(struct drm_crtc *crtc, struct drm_atomic_state *state) zynqmp_dpsub_crtc_atomic_begin() argument
258 zynqmp_dpsub_crtc_atomic_flush(struct drm_crtc *crtc, struct drm_atomic_state *state) zynqmp_dpsub_crtc_atomic_flush() argument
[all...]
/kernel/linux/linux-6.6/net/devlink/
H A Dlinecard.c92 if (nla_put_u8(msg, DEVLINK_ATTR_LINECARD_STATE, linecard->state)) in devlink_nl_linecard_fill()
204 struct devlink_nl_dump_state *state = devlink_dump_state(cb); in devlink_nl_linecard_get_dump_one() local
210 if (idx < state->idx) { in devlink_nl_linecard_get_dump_one()
222 state->idx = idx; in devlink_nl_linecard_get_dump_one()
261 if (linecard->state == DEVLINK_LINECARD_STATE_PROVISIONING) { in devlink_linecard_type_set()
266 if (linecard->state == DEVLINK_LINECARD_STATE_UNPROVISIONING) { in devlink_linecard_type_set()
279 if (linecard->state != DEVLINK_LINECARD_STATE_UNPROVISIONED && in devlink_linecard_type_set()
280 linecard->state != DEVLINK_LINECARD_STATE_PROVISIONING_FAILED) { in devlink_linecard_type_set()
295 linecard->state = DEVLINK_LINECARD_STATE_PROVISIONING; in devlink_linecard_type_set()
306 linecard->state in devlink_linecard_type_set()
[all...]
/kernel/linux/linux-5.10/drivers/hv/
H A Dhv_fcopy.c36 * Global state maintained for transaction that is being processed.
50 int state; /* hvutil_device_state */ member
66 * This state maintains the version number registered by the daemon.
72 /* Transaction is finished, reset the state here to avoid races. */ in fcopy_poll_wrapper()
73 fcopy_transaction.state = HVUTIL_READY; in fcopy_poll_wrapper()
174 fcopy_transaction.state = HVUTIL_USERSPACE_REQ; in fcopy_send_data()
180 fcopy_transaction.state = HVUTIL_READY; in fcopy_send_data()
199 * Copy the global state for completing the transaction. Note that in fcopy_respond_to_host()
202 * the "transaction active" state we maintain ensures that there can in fcopy_respond_to_host()
235 if (fcopy_transaction.state > HVUTIL_READ in hv_fcopy_onchannelcallback()
[all...]
/kernel/linux/linux-5.10/drivers/media/rc/
H A Dir-nec-decoder.c37 * This function returns -EINVAL if the pulse violates the state machine
48 data->state = STATE_INACTIVE; in ir_nec_decode()
52 dev_dbg(&dev->dev, "NEC decode started at state %d (%uus %s)\n", in ir_nec_decode()
53 data->state, ev.duration, TO_STR(ev.pulse)); in ir_nec_decode()
55 switch (data->state) { in ir_nec_decode()
70 data->state = STATE_HEADER_SPACE; in ir_nec_decode()
78 data->state = STATE_BIT_PULSE; in ir_nec_decode()
81 data->state = STATE_TRAILER_PULSE; in ir_nec_decode()
94 data->state = STATE_BIT_SPACE; in ir_nec_decode()
105 data->state in ir_nec_decode()
[all...]
/kernel/linux/linux-6.6/drivers/media/rc/
H A Dir-nec-decoder.c37 * This function returns -EINVAL if the pulse violates the state machine
48 data->state = STATE_INACTIVE; in ir_nec_decode()
52 dev_dbg(&dev->dev, "NEC decode started at state %d (%uus %s)\n", in ir_nec_decode()
53 data->state, ev.duration, TO_STR(ev.pulse)); in ir_nec_decode()
55 switch (data->state) { in ir_nec_decode()
70 data->state = STATE_HEADER_SPACE; in ir_nec_decode()
78 data->state = STATE_BIT_PULSE; in ir_nec_decode()
81 data->state = STATE_TRAILER_PULSE; in ir_nec_decode()
94 data->state = STATE_BIT_SPACE; in ir_nec_decode()
105 data->state in ir_nec_decode()
[all...]
/kernel/linux/linux-6.6/drivers/pwm/
H A Dpwm-sunplus.c57 const struct pwm_state *state) in sunplus_pwm_apply()
63 if (state->polarity != pwm->state.polarity) in sunplus_pwm_apply()
66 if (!state->enabled) { in sunplus_pwm_apply()
89 * With clk_rate limited above we have dd_freq <= state->period, in sunplus_pwm_apply()
92 dd_freq = mul_u64_u64_div_u64(clk_rate, state->period, (u64)SP7021_PWM_FREQ_SCALER in sunplus_pwm_apply()
108 if (state->duty_cycle == state->period) { in sunplus_pwm_apply()
117 duty = mul_u64_u64_div_u64(state->duty_cycle, clk_rate, in sunplus_pwm_apply()
129 struct pwm_state *state) in sunplus_pwm_get_state()
56 sunplus_pwm_apply(struct pwm_chip *chip, struct pwm_device *pwm, const struct pwm_state *state) sunplus_pwm_apply() argument
128 sunplus_pwm_get_state(struct pwm_chip *chip, struct pwm_device *pwm, struct pwm_state *state) sunplus_pwm_get_state() argument
[all...]
/kernel/linux/linux-6.6/drivers/iio/proximity/
H A Dcros_ec_mkbp_proximity.c60 int *state) in cros_ec_mkbp_proximity_query()
93 *state = cros_ec_mkbp_proximity_parse_state(switches); in cros_ec_mkbp_proximity_query()
97 static void cros_ec_mkbp_proximity_push_event(struct cros_ec_mkbp_proximity_data *data, int state) in cros_ec_mkbp_proximity_push_event() argument
106 if (state != data->last_proximity) { in cros_ec_mkbp_proximity_push_event()
112 dir = state ? IIO_EV_DIR_FALLING : IIO_EV_DIR_RISING; in cros_ec_mkbp_proximity_push_event()
117 data->last_proximity = state; in cros_ec_mkbp_proximity_push_event()
130 int state; in cros_ec_mkbp_proximity_notify() local
137 state = cros_ec_mkbp_proximity_parse_state(switches); in cros_ec_mkbp_proximity_notify()
138 cros_ec_mkbp_proximity_push_event(data, state); in cros_ec_mkbp_proximity_notify()
170 enum iio_event_direction dir, int state) in cros_ec_mkbp_proximity_write_event_config()
59 cros_ec_mkbp_proximity_query(struct cros_ec_device *ec_dev, int *state) cros_ec_mkbp_proximity_query() argument
167 cros_ec_mkbp_proximity_write_event_config(struct iio_dev *indio_dev, const struct iio_chan_spec *chan, enum iio_event_type type, enum iio_event_direction dir, int state) cros_ec_mkbp_proximity_write_event_config() argument
191 int ret, state; cros_ec_mkbp_proximity_resume() local
[all...]
/kernel/linux/linux-6.6/drivers/hv/
H A Dhv_fcopy.c36 * Global state maintained for transaction that is being processed.
50 int state; /* hvutil_device_state */ member
66 * This state maintains the version number registered by the daemon.
72 /* Transaction is finished, reset the state here to avoid races. */ in fcopy_poll_wrapper()
73 fcopy_transaction.state = HVUTIL_READY; in fcopy_poll_wrapper()
174 fcopy_transaction.state = HVUTIL_USERSPACE_REQ; in fcopy_send_data()
180 fcopy_transaction.state = HVUTIL_READY; in fcopy_send_data()
199 * Copy the global state for completing the transaction. Note that in fcopy_respond_to_host()
202 * the "transaction active" state we maintain ensures that there can in fcopy_respond_to_host()
235 if (fcopy_transaction.state > HVUTIL_READ in hv_fcopy_onchannelcallback()
[all...]
/kernel/linux/linux-5.10/net/bridge/
H A Dbr_mrp.c195 hdr->state = cpu_to_be16(mrp->ring_state); in br_mrp_alloc_test_skb()
225 hdr->state = cpu_to_be16(mrp->in_state); in br_mrp_alloc_in_test_skb()
259 /* Notify that the ring is open only if the ring state is in br_mrp_test_work_expired()
333 * interconnect ring state is closed, otherwise it would in br_mrp_in_test_work_expired()
397 u8 state; in br_mrp_del_impl() local
413 state = netif_running(br->dev) ? in br_mrp_del_impl()
415 p->state = state; in br_mrp_del_impl()
418 br_mrp_port_switchdev_set_state(p, state); in br_mrp_del_impl()
425 state in br_mrp_del_impl()
544 br_mrp_set_port_state(struct net_bridge_port *p, enum br_mrp_port_state_type state) br_mrp_set_port_state() argument
602 br_mrp_set_ring_state(struct net_bridge *br, struct br_mrp_ring_state *state) br_mrp_set_ring_state() argument
685 br_mrp_set_in_state(struct net_bridge *br, struct br_mrp_in_state *state) br_mrp_set_in_state() argument
719 u8 state; br_mrp_set_in_role() local
[all...]

Completed in 30 milliseconds

1...<<41424344454647484950>>...531