Lines Matching refs:entry
17 struct mptcp_pm_addr_entry *entry, *tmp; in mptcp_userspace_pm_free_local_addr_list() local
25 list_for_each_entry_safe(entry, tmp, &free_list, list) { in mptcp_userspace_pm_free_local_addr_list()
26 sock_kfree_s(sk, entry, sizeof(*entry)); in mptcp_userspace_pm_free_local_addr_list()
34 struct mptcp_pm_addr_entry *entry; in mptcp_userspace_pm_lookup_addr() local
36 mptcp_for_each_userspace_pm_addr(msk, entry) { in mptcp_userspace_pm_lookup_addr()
37 if (mptcp_addresses_equal(&entry->addr, addr, false)) in mptcp_userspace_pm_lookup_addr()
38 return entry; in mptcp_userspace_pm_lookup_addr()
44 struct mptcp_pm_addr_entry *entry, in mptcp_userspace_pm_append_new_local_addr() argument
58 addr_match = mptcp_addresses_equal(&e->addr, &entry->addr, true); in mptcp_userspace_pm_append_new_local_addr()
59 if (addr_match && entry->addr.id == 0 && needs_id) in mptcp_userspace_pm_append_new_local_addr()
60 entry->addr.id = e->addr.id; in mptcp_userspace_pm_append_new_local_addr()
61 id_match = (e->addr.id == entry->addr.id); in mptcp_userspace_pm_append_new_local_addr()
71 e = sock_kmemdup(sk, entry, sizeof(*entry), GFP_ATOMIC); in mptcp_userspace_pm_append_new_local_addr()
85 ret = entry->addr.id; in mptcp_userspace_pm_append_new_local_addr()
102 struct mptcp_pm_addr_entry *entry; in mptcp_userspace_pm_delete_local_addr() local
104 entry = mptcp_userspace_pm_lookup_addr(msk, &addr->addr); in mptcp_userspace_pm_delete_local_addr()
105 if (!entry) in mptcp_userspace_pm_delete_local_addr()
111 list_del_rcu(&entry->list); in mptcp_userspace_pm_delete_local_addr()
112 sock_kfree_s(sk, entry, sizeof(*entry)); in mptcp_userspace_pm_delete_local_addr()
120 struct mptcp_pm_addr_entry *entry; in mptcp_userspace_pm_lookup_addr_by_id() local
122 mptcp_for_each_userspace_pm_addr(msk, entry) { in mptcp_userspace_pm_lookup_addr_by_id()
123 if (entry->addr.id == id) in mptcp_userspace_pm_lookup_addr_by_id()
124 return entry; in mptcp_userspace_pm_lookup_addr_by_id()
134 struct mptcp_pm_addr_entry *entry; in mptcp_userspace_pm_get_local_id() local
137 entry = mptcp_userspace_pm_lookup_addr(msk, &skc->addr); in mptcp_userspace_pm_get_local_id()
139 if (entry) in mptcp_userspace_pm_get_local_id()
140 return entry->addr.id; in mptcp_userspace_pm_get_local_id()
151 struct mptcp_pm_addr_entry *entry; in mptcp_userspace_pm_is_backup() local
155 entry = mptcp_userspace_pm_lookup_addr(msk, skc); in mptcp_userspace_pm_is_backup()
156 backup = entry && !!(entry->flags & MPTCP_PM_ADDR_FLAG_BACKUP); in mptcp_userspace_pm_is_backup()
278 struct mptcp_pm_addr_entry *entry) in mptcp_pm_remove_addr_entry() argument
284 if (mptcp_remove_anno_list_by_saddr(msk, &entry->addr)) in mptcp_pm_remove_addr_entry()
286 else if (!mptcp_lookup_subflow_by_saddr(&msk->conn_list, &entry->addr)) in mptcp_pm_remove_addr_entry()
289 alist.ids[alist.nr++] = entry->addr.id; in mptcp_pm_remove_addr_entry()
359 struct mptcp_pm_addr_entry entry = { 0 }; in mptcp_pm_nl_subflow_create_doit() local
378 err = mptcp_pm_parse_entry(laddr, info, true, &entry); in mptcp_pm_nl_subflow_create_doit()
382 if (entry.flags & MPTCP_PM_ADDR_FLAG_SIGNAL) { in mptcp_pm_nl_subflow_create_doit()
387 entry.flags |= MPTCP_PM_ADDR_FLAG_SUBFLOW; in mptcp_pm_nl_subflow_create_doit()
394 if (!mptcp_pm_addr_families_match(sk, &entry.addr, &addr_r)) { in mptcp_pm_nl_subflow_create_doit()
400 err = mptcp_userspace_pm_append_new_local_addr(msk, &entry, false); in mptcp_pm_nl_subflow_create_doit()
407 local.addr = entry.addr; in mptcp_pm_nl_subflow_create_doit()
408 local.flags = entry.flags; in mptcp_pm_nl_subflow_create_doit()
409 local.ifindex = entry.ifindex; in mptcp_pm_nl_subflow_create_doit()
420 mptcp_userspace_pm_delete_local_addr(msk, &entry); in mptcp_pm_nl_subflow_create_doit()
559 struct mptcp_pm_addr_entry *entry; in mptcp_userspace_pm_set_flags() local
599 entry = mptcp_userspace_pm_lookup_addr(msk, &local->addr); in mptcp_userspace_pm_set_flags()
600 if (entry) { in mptcp_userspace_pm_set_flags()
602 entry->flags |= MPTCP_PM_ADDR_FLAG_BACKUP; in mptcp_userspace_pm_set_flags()
604 entry->flags &= ~MPTCP_PM_ADDR_FLAG_BACKUP; in mptcp_userspace_pm_set_flags()
628 struct mptcp_pm_addr_entry *entry; in mptcp_userspace_pm_dump_addr() local
645 mptcp_for_each_userspace_pm_addr(msk, entry) { in mptcp_userspace_pm_dump_addr()
646 if (test_bit(entry->addr.id, bitmap->map)) in mptcp_userspace_pm_dump_addr()
649 if (mptcp_pm_genl_fill_addr(msg, cb, entry) < 0) in mptcp_userspace_pm_dump_addr()
652 __set_bit(entry->addr.id, bitmap->map); in mptcp_userspace_pm_dump_addr()
665 struct mptcp_pm_addr_entry *entry; in mptcp_userspace_pm_get_addr() local
678 entry = mptcp_userspace_pm_lookup_addr_by_id(msk, id); in mptcp_userspace_pm_get_addr()
679 if (entry) { in mptcp_userspace_pm_get_addr()
680 *addr = *entry; in mptcp_userspace_pm_get_addr()