| /kernel/linux/linux-6.6/net/mptcp/ |
| H A D | ctrl.c | 78 static void mptcp_pernet_set_defaults(struct mptcp_pernet *pernet) in mptcp_pernet_set_defaults() argument
80 pernet->mptcp_enabled = 1; in mptcp_pernet_set_defaults()
81 pernet->add_addr_timeout = TCP_RTO_MAX; in mptcp_pernet_set_defaults()
82 pernet->checksum_enabled = 0; in mptcp_pernet_set_defaults()
83 pernet->allow_join_initial_addr_port = 1; in mptcp_pernet_set_defaults()
84 pernet->stale_loss_cnt = 4; in mptcp_pernet_set_defaults()
85 pernet->pm_type = MPTCP_PM_TYPE_KERNEL; in mptcp_pernet_set_defaults()
86 strcpy(pernet->scheduler, "default"); in mptcp_pernet_set_defaults()
147 static int mptcp_pernet_new_table(struct net *net, struct mptcp_pernet *pernet) in mptcp_pernet_new_table() argument
159 table[0].data = &pernet in mptcp_pernet_new_table()
183 mptcp_pernet_del_table(struct mptcp_pernet *pernet) mptcp_pernet_del_table() argument
194 mptcp_pernet_new_table(struct net *net, struct mptcp_pernet *pernet) mptcp_pernet_new_table() argument
199 mptcp_pernet_del_table(struct mptcp_pernet *pernet) mptcp_pernet_del_table() argument
205 struct mptcp_pernet *pernet = mptcp_get_pernet(net); mptcp_net_init() local
215 struct mptcp_pernet *pernet = mptcp_get_pernet(net); mptcp_net_exit() local
[all...] |
| H A D | pm_netlink.c | 35 /* protects pernet updates */
152 select_local_address(const struct pm_nl_pernet *pernet, in select_local_address() argument
160 list_for_each_entry_rcu(entry, &pernet->local_addr_list, list) { in select_local_address()
175 select_signal_address(struct pm_nl_pernet *pernet, const struct mptcp_sock *msk) in select_signal_address() argument
185 list_for_each_entry_rcu(entry, &pernet->local_addr_list, list) { in select_signal_address()
201 const struct pm_nl_pernet *pernet = pm_nl_get_pernet_from_msk(msk); in mptcp_pm_get_add_addr_signal_max() local
203 return READ_ONCE(pernet->add_addr_signal_max); in mptcp_pm_get_add_addr_signal_max()
209 struct pm_nl_pernet *pernet = pm_nl_get_pernet_from_msk(msk); in mptcp_pm_get_add_addr_accept_max() local
211 return READ_ONCE(pernet->add_addr_accept_max); in mptcp_pm_get_add_addr_accept_max()
217 struct pm_nl_pernet *pernet in mptcp_pm_get_subflows_max() local
225 struct pm_nl_pernet *pernet = pm_nl_get_pernet_from_msk(msk); mptcp_pm_get_local_addr_max() local
233 struct pm_nl_pernet *pernet = pm_nl_get_pernet_from_msk(msk); mptcp_pm_nl_check_work_pending() local
496 __lookup_addr_by_id(struct pm_nl_pernet *pernet, unsigned int id) __lookup_addr_by_id() argument
508 __lookup_addr(struct pm_nl_pernet *pernet, const struct mptcp_addr_info *info, bool lookup_by_id) __lookup_addr() argument
528 struct pm_nl_pernet *pernet; mptcp_pm_create_subflow_or_signal_addr() local
635 struct pm_nl_pernet *pernet; fill_local_addresses_vec() local
906 mptcp_pm_nl_append_new_local_addr(struct pm_nl_pernet *pernet, struct mptcp_pm_addr_entry *entry, bool needs_id) mptcp_pm_nl_append_new_local_addr() argument
1072 struct pm_nl_pernet *pernet; mptcp_pm_nl_get_local_id() local
1330 struct pm_nl_pernet *pernet = genl_info_pm_nl(info); mptcp_nl_cmd_add_addr() local
1512 struct pm_nl_pernet *pernet = genl_info_pm_nl(info); mptcp_nl_cmd_del_addr() local
1637 __reset_counters(struct pm_nl_pernet *pernet) __reset_counters() argument
1647 struct pm_nl_pernet *pernet = genl_info_pm_nl(info); mptcp_nl_cmd_flush_addrs() local
1704 struct pm_nl_pernet *pernet = genl_info_pm_nl(info); mptcp_nl_cmd_get_addr() local
1756 struct pm_nl_pernet *pernet; mptcp_nl_cmd_dump_addrs() local
1812 struct pm_nl_pernet *pernet = genl_info_pm_nl(info); mptcp_nl_cmd_set_limits() local
1838 struct pm_nl_pernet *pernet = genl_info_pm_nl(info); mptcp_nl_cmd_get_limits() local
1912 struct pm_nl_pernet *pernet = pm_nl_get_pernet(net); mptcp_pm_nl_set_flags() local
2382 struct pm_nl_pernet *pernet = pm_nl_get_pernet(net); pm_nl_init_net() local
2404 struct pm_nl_pernet *pernet = pm_nl_get_pernet(net); pm_nl_exit_net() local
[all...] |
| /kernel/linux/linux-5.10/net/mptcp/ |
| H A D | ctrl.c | 46 static void mptcp_pernet_set_defaults(struct mptcp_pernet *pernet) in mptcp_pernet_set_defaults() argument
48 pernet->mptcp_enabled = 1; in mptcp_pernet_set_defaults()
51 static int mptcp_pernet_new_table(struct net *net, struct mptcp_pernet *pernet) in mptcp_pernet_new_table() argument
63 table[0].data = &pernet->mptcp_enabled; in mptcp_pernet_new_table()
69 pernet->ctl_table_hdr = hdr; in mptcp_pernet_new_table()
80 static void mptcp_pernet_del_table(struct mptcp_pernet *pernet) in mptcp_pernet_del_table() argument
82 struct ctl_table *table = pernet->ctl_table_hdr->ctl_table_arg; in mptcp_pernet_del_table()
84 unregister_net_sysctl_table(pernet->ctl_table_hdr); in mptcp_pernet_del_table()
91 struct mptcp_pernet *pernet = mptcp_get_pernet(net); in mptcp_net_init() local
93 mptcp_pernet_set_defaults(pernet); in mptcp_net_init()
101 struct mptcp_pernet *pernet = mptcp_get_pernet(net); mptcp_net_exit() local
[all...] |
| H A D | pm_netlink.c | 40 /* protects pernet updates */
132 select_local_address(const struct pm_nl_pernet *pernet, in select_local_address() argument
139 list_for_each_entry_rcu(entry, &pernet->local_addr_list, list) { in select_local_address()
159 select_signal_address(struct pm_nl_pernet *pernet, unsigned int pos) in select_signal_address() argument
170 list_for_each_entry_rcu(entry, &pernet->local_addr_list, list) { in select_signal_address()
310 struct pm_nl_pernet *pernet; in mptcp_pm_create_subflow_or_signal_addr() local
312 pernet = net_generic(sock_net((struct sock *)msk), pm_nl_pernet_id); in mptcp_pm_create_subflow_or_signal_addr()
321 local = select_signal_address(pernet, in mptcp_pm_create_subflow_or_signal_addr()
342 local = select_local_address(pernet, msk); in mptcp_pm_create_subflow_or_signal_addr()
478 static int mptcp_pm_nl_append_new_local_addr(struct pm_nl_pernet *pernet, in mptcp_pm_nl_append_new_local_addr() argument
523 struct pm_nl_pernet *pernet; mptcp_pm_nl_get_local_id() local
571 struct pm_nl_pernet *pernet; mptcp_pm_nl_data_init() local
697 struct pm_nl_pernet *pernet = genl_info_pm_nl(info); mptcp_nl_cmd_add_addr() local
723 __lookup_addr_by_id(struct pm_nl_pernet *pernet, unsigned int id) __lookup_addr_by_id() argument
799 struct pm_nl_pernet *pernet = genl_info_pm_nl(info); mptcp_nl_cmd_del_addr() local
829 __flush_addrs(struct pm_nl_pernet *pernet) __flush_addrs() argument
841 __reset_counters(struct pm_nl_pernet *pernet) __reset_counters() argument
851 struct pm_nl_pernet *pernet = genl_info_pm_nl(info); mptcp_nl_cmd_flush_addrs() local
900 struct pm_nl_pernet *pernet = genl_info_pm_nl(info); mptcp_nl_cmd_get_addr() local
952 struct pm_nl_pernet *pernet; mptcp_nl_cmd_dump_addrs() local
1001 struct pm_nl_pernet *pernet = genl_info_pm_nl(info); mptcp_nl_cmd_set_limits() local
1027 struct pm_nl_pernet *pernet = genl_info_pm_nl(info); mptcp_nl_cmd_get_limits() local
1104 struct pm_nl_pernet *pernet = net_generic(net, pm_nl_pernet_id); pm_nl_init_net() local
[all...] |
| /kernel/linux/linux-6.6/net/netfilter/ |
| H A D | nfnetlink_cttimeout.c | 102 struct nfct_timeout_pernet *pernet = nfct_timeout_pernet(info->net); in cttimeout_new_timeout() local
120 list_for_each_entry(timeout, &pernet->nfct_timeout_list, head) { in cttimeout_new_timeout()
174 list_add_tail_rcu(&timeout->head, &pernet->nfct_timeout_list); in cttimeout_new_timeout()
229 struct nfct_timeout_pernet *pernet; in ctnl_timeout_dump() local
241 pernet = nfct_timeout_pernet(net); in ctnl_timeout_dump()
242 list_for_each_entry_rcu(cur, &pernet->nfct_timeout_list, head) { in ctnl_timeout_dump()
267 struct nfct_timeout_pernet *pernet = nfct_timeout_pernet(info->net); in cttimeout_get_timeout() local
283 list_for_each_entry(cur, &pernet->nfct_timeout_list, head) { in cttimeout_get_timeout()
334 struct nfct_timeout_pernet *pernet = nfct_timeout_pernet(info->net); in cttimeout_del_timeout() local
340 list_for_each_entry_safe(cur, tmp, &pernet in cttimeout_del_timeout()
515 struct nfct_timeout_pernet *pernet = nfct_timeout_pernet(net); ctnl_timeout_find_get() local
586 struct nfct_timeout_pernet *pernet = nfct_timeout_pernet(net); cttimeout_net_init() local
596 struct nfct_timeout_pernet *pernet = nfct_timeout_pernet(net); cttimeout_net_pre_exit() local
609 struct nfct_timeout_pernet *pernet = nfct_timeout_pernet(net); cttimeout_net_exit() local
[all...] |
| /kernel/linux/linux-5.10/drivers/infiniband/core/ |
| H A D | cma.c | 190 struct cma_pernet *pernet = cma_pernet(net); in cma_pernet_xa() local
194 return &pernet->tcp_ps; in cma_pernet_xa()
196 return &pernet->udp_ps; in cma_pernet_xa()
198 return &pernet->ipoib_ps; in cma_pernet_xa()
200 return &pernet->ib_ps; in cma_pernet_xa()
5061 struct cma_pernet *pernet = cma_pernet(net); in cma_init_net() local
5063 xa_init(&pernet->tcp_ps); in cma_init_net()
5064 xa_init(&pernet->udp_ps); in cma_init_net()
5065 xa_init(&pernet->ipoib_ps); in cma_init_net()
5066 xa_init(&pernet in cma_init_net()
5073 struct cma_pernet *pernet = cma_pernet(net); cma_exit_net() local
[all...] |
| /kernel/linux/linux-6.6/drivers/infiniband/core/ |
| H A D | cma.c | 194 struct cma_pernet *pernet = cma_pernet(net); in cma_pernet_xa() local
198 return &pernet->tcp_ps; in cma_pernet_xa()
200 return &pernet->udp_ps; in cma_pernet_xa()
202 return &pernet->ipoib_ps; in cma_pernet_xa()
204 return &pernet->ib_ps; in cma_pernet_xa()
5397 struct cma_pernet *pernet = cma_pernet(net); in cma_init_net() local
5399 xa_init(&pernet->tcp_ps); in cma_init_net()
5400 xa_init(&pernet->udp_ps); in cma_init_net()
5401 xa_init(&pernet->ipoib_ps); in cma_init_net()
5402 xa_init(&pernet in cma_init_net()
5409 struct cma_pernet *pernet = cma_pernet(net); cma_exit_net() local
[all...] |
| /kernel/linux/linux-6.6/include/net/ |
| H A D | inet_hashtables.h | 179 bool pernet; member
|
| /kernel/linux/linux-6.6/net/ipv4/ |
| H A D | inet_hashtables.c | 1278 new_hashinfo->pernet = true; in inet_pernet_hashinfo_alloc()
1293 if (!hashinfo->pernet) in inet_pernet_hashinfo_free()
|
| H A D | tcp_minisocks.c | 372 if (net->ipv4.tcp_death_row.hashinfo->pernet) { in tcp_twsk_purge()
|
| H A D | sysctl_net_ipv4.c | 405 if (!net_eq(net, &init_net) && !hinfo->pernet) in proc_tcp_ehash_entries()
|
| H A D | tcp.c | 4712 tcp_hashinfo.pernet = false; in tcp_init()
|
| /kernel/linux/linux-6.6/net/dccp/ |
| H A D | proto.c | 1218 dccp_hashinfo.pernet = false; in dccp_init()
|