Lines Matching refs:pm
13 &((__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()
138 spin_unlock_bh(&msk->pm.lock); in mptcp_userspace_pm_get_local_id()
154 spin_lock_bh(&msk->pm.lock); in mptcp_userspace_pm_is_backup()
157 spin_unlock_bh(&msk->pm.lock); in mptcp_userspace_pm_is_backup()
229 spin_lock_bh(&msk->pm.lock); in mptcp_pm_nl_announce_doit()
232 msk->pm.add_addr_signaled++; in mptcp_pm_nl_announce_doit()
237 spin_unlock_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()
268 spin_unlock_bh(&msk->pm.lock); in mptcp_userspace_pm_remove_id_zero_address()
291 spin_lock_bh(&msk->pm.lock); in mptcp_pm_remove_addr_entry()
292 msk->pm.add_addr_signaled -= anno_nr; in mptcp_pm_remove_addr_entry()
294 spin_unlock_bh(&msk->pm.lock); in mptcp_pm_remove_addr_entry()
325 spin_lock_bh(&msk->pm.lock); in mptcp_pm_nl_remove_doit()
328 spin_unlock_bh(&msk->pm.lock); in mptcp_pm_nl_remove_doit()
334 spin_unlock_bh(&msk->pm.lock); in mptcp_pm_nl_remove_doit()
418 spin_lock_bh(&msk->pm.lock); in mptcp_pm_nl_subflow_create_doit()
422 msk->pm.subflows++; in mptcp_pm_nl_subflow_create_doit()
423 spin_unlock_bh(&msk->pm.lock); in mptcp_pm_nl_subflow_create_doit()
541 spin_lock_bh(&msk->pm.lock); in mptcp_pm_nl_subflow_destroy_doit()
543 spin_unlock_bh(&msk->pm.lock); in mptcp_pm_nl_subflow_destroy_doit()
598 spin_lock_bh(&msk->pm.lock); in mptcp_userspace_pm_set_flags()
606 spin_unlock_bh(&msk->pm.lock); in mptcp_userspace_pm_set_flags()
644 spin_lock_bh(&msk->pm.lock); in mptcp_userspace_pm_dump_addr()
654 spin_unlock_bh(&msk->pm.lock); in mptcp_userspace_pm_dump_addr()
677 spin_lock_bh(&msk->pm.lock); in mptcp_userspace_pm_get_addr()
683 spin_unlock_bh(&msk->pm.lock); in mptcp_userspace_pm_get_addr()