Home
last modified time | relevance | path

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

/net/mptcp/
A Dpm.c449 struct mptcp_pm_data *pm = &msk->pm; in mptcp_pm_new_connection() local
459 struct mptcp_pm_data *pm = &msk->pm; in mptcp_pm_allow_new_subflow() local
511 struct mptcp_pm_data *pm = &msk->pm; in mptcp_pm_fully_established() local
546 struct mptcp_pm_data *pm = &msk->pm; in mptcp_pm_subflow_established() local
564 struct mptcp_pm_data *pm = &msk->pm; in mptcp_pm_subflow_check_next() local
598 struct mptcp_pm_data *pm = &msk->pm; in mptcp_pm_add_addr_received() local
631 struct mptcp_pm_data *pm = &msk->pm; in mptcp_pm_add_addr_echoed() local
731 struct mptcp_pm_data *pm = &msk->pm; in mptcp_pm_rm_addr_received() local
960 struct mptcp_pm_data *pm = &msk->pm; in mptcp_pm_worker() local
994 struct mptcp_pm_data *pm = &msk->pm; in mptcp_pm_data_reset() local
[all …]
A Dpm_kernel.c190 msk->pm.subflows++; in fill_remote_addresses_vec()
221 msk->pm.subflows++; in fill_remote_addresses_vec()
322 msk->pm.add_addr_signaled++; in mptcp_pm_create_subflow_or_signal_addr()
356 msk->pm.local_addr_used++; in mptcp_pm_create_subflow_or_signal_addr()
416 msk->pm.subflows++; in fill_local_addresses_vec()
437 msk->pm.subflows++; in fill_local_addresses_vec()
459 msk->pm.remote.family); in mptcp_pm_nl_add_addr_received()
461 remote = msk->pm.remote; in mptcp_pm_nl_add_addr_received()
483 spin_lock_bh(&msk->pm.lock); in mptcp_pm_nl_add_addr_received()
881 msk->pm.local_addr_used--; in __mark_subflow_endp_available()
[all …]
A Dpm_userspace.c21 spin_lock_bh(&msk->pm.lock); 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()
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()
154 spin_lock_bh(&msk->pm.lock); in mptcp_userspace_pm_is_backup()
229 spin_lock_bh(&msk->pm.lock); in mptcp_pm_nl_announce_doit()
266 spin_lock_bh(&msk->pm.lock); in mptcp_userspace_pm_remove_id_zero_address()
[all …]
A Dprotocol.h341 struct mptcp_pm_data pm; member
1096 return READ_ONCE(msk->pm.addr_signal) & in mptcp_pm_should_add_signal()
1102 return READ_ONCE(msk->pm.addr_signal) & BIT(MPTCP_ADD_ADDR_SIGNAL); in mptcp_pm_should_add_signal_addr()
1107 return READ_ONCE(msk->pm.addr_signal) & BIT(MPTCP_ADD_ADDR_ECHO); in mptcp_pm_should_add_signal_echo()
1112 return READ_ONCE(msk->pm.addr_signal) & BIT(MPTCP_RM_ADDR_SIGNAL); in mptcp_pm_should_rm_signal()
1117 return READ_ONCE(msk->pm.pm_type) == MPTCP_PM_TYPE_USERSPACE; in mptcp_pm_is_userspace()
1122 return READ_ONCE(msk->pm.pm_type) == MPTCP_PM_TYPE_KERNEL; in mptcp_pm_is_kernel()
1193 if (--msk->pm.subflows < mptcp_pm_get_subflows_max(msk)) in __mptcp_pm_close_subflow()
1194 WRITE_ONCE(msk->pm.accept_subflow, true); in __mptcp_pm_close_subflow()
1199 spin_lock_bh(&msk->pm.lock); in mptcp_pm_close_subflow()
[all …]
A DMakefile4 mptcp-y := protocol.o subflow.o options.o token.o crypto.o ctrl.o pm.o diag.o \
A Dsockopt.c965 info->mptcpi_subflows = READ_ONCE(msk->pm.subflows); in mptcp_diag_fill_info()
966 info->mptcpi_add_addr_signal = READ_ONCE(msk->pm.add_addr_signaled); in mptcp_diag_fill_info()
967 info->mptcpi_add_addr_accepted = READ_ONCE(msk->pm.add_addr_accepted); in mptcp_diag_fill_info()
968 info->mptcpi_local_addr_used = READ_ONCE(msk->pm.local_addr_used); in mptcp_diag_fill_info()
A Dpm_netlink.c415 if (nla_put_u8(skb, MPTCP_ATTR_SERVER_SIDE, READ_ONCE(msk->pm.server_side))) in mptcp_event_created()
A Doptions.c989 WRITE_ONCE(msk->pm.remote_deny_join_id0, true); in check_fully_established()
991 if (unlikely(!READ_ONCE(msk->pm.server_side))) in check_fully_established()
A Dsubflow.c66 READ_ONCE(msk->pm.accept_subflow)); in mptcp_can_accept_new_subflow()
560 WRITE_ONCE(msk->pm.remote_deny_join_id0, true); in subflow_finish_connect()
A Dprotocol.c2989 msk->pm.status = 0; in __mptcp_destroy_sock()
/net/mac80211/
A Dmesh_ps.c161 if (sta->mesh->local_pm == pm) in ieee80211_mps_set_sta_local_pm()
165 pm, sta->sta.addr); in ieee80211_mps_set_sta_local_pm()
167 sta->mesh->local_pm = pm; in ieee80211_mps_set_sta_local_pm()
206 pm = sta->mesh->local_pm; in ieee80211_mps_set_frame_flags()
251 pm = sta->mesh->peer_pm; in ieee80211_mps_sta_status_update()
253 pm = sta->mesh->nonpeer_pm; in ieee80211_mps_sta_status_update()
304 if (sta->mesh->peer_pm == pm) in mps_set_sta_peer_pm()
308 sta->sta.addr, pm); in mps_set_sta_peer_pm()
310 sta->mesh->peer_pm = pm; in mps_set_sta_peer_pm()
329 sta->sta.addr, pm); in mps_set_sta_nonpeer_pm()
[all …]
A DMakefile56 mac80211-$(CONFIG_PM) += pm.o
A Dmesh.h290 enum nl80211_mesh_power_mode pm);
/net/8021q/
A Dvlan_netlink.c224 struct vlan_priority_tci_mapping *pm; in vlan_fill_info() local
263 for (pm = vlan->egress_priority_map[i]; pm; in vlan_fill_info()
264 pm = pm->next) { in vlan_fill_info()
265 if (!pm->vlan_qos) in vlan_fill_info()
268 m.from = pm->priority; in vlan_fill_info()
269 m.to = (pm->vlan_qos >> 13) & 0x7; in vlan_fill_info()
A Dvlan_dev.c602 struct vlan_priority_tci_mapping *pm; in vlan_dev_free_egress_priority() local
607 while ((pm = vlan->egress_priority_map[i]) != NULL) { in vlan_dev_free_egress_priority()
608 vlan->egress_priority_map[i] = pm->next; in vlan_dev_free_egress_priority()
609 kfree(pm); in vlan_dev_free_egress_priority()
/net/core/
A Dof_net.c29 const char *pm; in of_get_phy_mode() local
34 err = of_property_read_string(np, "phy-mode", &pm); in of_get_phy_mode()
36 err = of_property_read_string(np, "phy-connection-type", &pm); in of_get_phy_mode()
41 if (!strcasecmp(pm, phy_modes(i))) { in of_get_phy_mode()
/net/tipc/
A Dgroup.c595 struct tipc_member *m, *rm, *pm; in tipc_group_update_rcv_win() local
629 list_del_init(&pm->list); in tipc_group_update_rcv_win()
630 pm->state = MBR_JOINED; in tipc_group_update_rcv_win()
631 tipc_group_proto_xmit(grp, pm, GRP_ADV_MSG, xmitq); in tipc_group_update_rcv_win()
655 pm->state = MBR_ACTIVE; in tipc_group_update_rcv_win()
656 list_move_tail(&pm->list, &grp->active); in tipc_group_update_rcv_win()
658 tipc_group_proto_xmit(grp, pm, GRP_ADV_MSG, xmitq); in tipc_group_update_rcv_win()
747 struct tipc_member *m, *pm; in tipc_group_proto_rcv() local
842 pm->state = MBR_ACTIVE; in tipc_group_proto_rcv()
843 list_move_tail(&pm->list, &grp->active); in tipc_group_proto_rcv()
[all …]
/net/phonet/
A Daf_phonet.c287 const struct phonetmsg *pm; in can_respond() local
300 pm = pn_msg(skb); in can_respond()
301 if (pm->pn_msg_id != PN_COMMON_MESSAGE) in can_respond()
304 ? pm->pn_e_submsg_id : pm->pn_submsg_id; in can_respond()
306 pm->pn_e_submsg_id != PN_COMM_SERVICE_NOT_IDENTIFIED_RESP) in can_respond()
/net/ieee802154/
A Dsysfs.c100 .pm = WPAN_PHY_PM_OPS,
/net/qrtr/
A Dmhi.c174 .pm = &qcom_mhi_qrtr_pm_ops,
/net/wireless/
A Dsysfs.c168 .pm = WIPHY_PM_OPS,
/net/rfkill/
A Dcore.c952 .pm = RFKILL_PM_OPS,

Completed in 56 milliseconds