| /openbmc/linux/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()
183 static int mptcp_pernet_new_table(struct net *net, struct mptcp_pernet *pernet) in mptcp_pernet_new_table() argument
195 table[0].data = &pernet->mptcp_enabled; in mptcp_pernet_new_table()
[all …]
|
| H A D | pm_netlink.c | 35 /* protects pernet updates */
155 select_local_address(const struct pm_nl_pernet *pernet, in select_local_address() argument
165 list_for_each_entry_rcu(entry, &pernet->local_addr_list, list) { in select_local_address()
182 select_signal_address(struct pm_nl_pernet *pernet, const struct mptcp_sock *msk, in select_signal_address() argument
194 list_for_each_entry_rcu(entry, &pernet->local_addr_list, list) { in select_signal_address()
212 const struct pm_nl_pernet *pernet = pm_nl_get_pernet_from_msk(msk); in mptcp_pm_get_add_addr_signal_max() local
214 return READ_ONCE(pernet->add_addr_signal_max); in mptcp_pm_get_add_addr_signal_max()
220 struct pm_nl_pernet *pernet = pm_nl_get_pernet_from_msk(msk); in mptcp_pm_get_add_addr_accept_max() local
222 return READ_ONCE(pernet->add_addr_accept_max); in mptcp_pm_get_add_addr_accept_max()
228 struct pm_nl_pernet *pernet in mptcp_pm_get_subflows_max() local
236 struct pm_nl_pernet *pernet = pm_nl_get_pernet_from_msk(msk); mptcp_pm_get_local_addr_max() local
244 struct pm_nl_pernet *pernet = pm_nl_get_pernet_from_msk(msk); mptcp_pm_nl_check_work_pending() local
512 __lookup_addr_by_id(struct pm_nl_pernet * pernet,unsigned int id) __lookup_addr_by_id() argument
524 __lookup_addr(struct pm_nl_pernet * pernet,const struct mptcp_addr_info * info) __lookup_addr() argument
543 struct pm_nl_pernet *pernet; mptcp_pm_create_subflow_or_signal_addr() local
670 struct pm_nl_pernet *pernet; fill_local_addresses_vec() local
970 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
1137 struct pm_nl_pernet *pernet; mptcp_pm_nl_get_local_id() local
1173 struct pm_nl_pernet *pernet = pm_nl_get_pernet_from_msk(msk); mptcp_pm_nl_is_backup() local
1420 struct pm_nl_pernet *pernet = genl_info_pm_nl(info); mptcp_nl_cmd_add_addr() local
1636 struct pm_nl_pernet *pernet = genl_info_pm_nl(info); mptcp_nl_cmd_del_addr() local
1776 __reset_counters(struct pm_nl_pernet * pernet) __reset_counters() argument
1786 struct pm_nl_pernet *pernet = genl_info_pm_nl(info); mptcp_nl_cmd_flush_addrs() local
1843 struct pm_nl_pernet *pernet = genl_info_pm_nl(info); mptcp_nl_cmd_get_addr() local
1895 struct pm_nl_pernet *pernet; mptcp_nl_cmd_dump_addrs() local
1951 struct pm_nl_pernet *pernet = genl_info_pm_nl(info); mptcp_nl_cmd_set_limits() local
1977 struct pm_nl_pernet *pernet = genl_info_pm_nl(info); mptcp_nl_cmd_get_limits() local
2052 struct pm_nl_pernet *pernet = pm_nl_get_pernet(net); mptcp_pm_nl_set_flags() local
2524 struct pm_nl_pernet *pernet = pm_nl_get_pernet(net); pm_nl_init_net() local
2546 struct pm_nl_pernet *pernet = pm_nl_get_pernet(net); pm_nl_exit_net() local
[all...] |
| /openbmc/linux/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->nfct_timeout_list, in cttimeout_del_timeout()
[all …]
|
| /openbmc/linux/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()
5399 struct cma_pernet *pernet = cma_pernet(net); in cma_init_net() local
5401 xa_init(&pernet->tcp_ps); in cma_init_net()
5402 xa_init(&pernet->udp_ps); in cma_init_net()
5403 xa_init(&pernet->ipoib_ps); in cma_init_net()
5404 xa_init(&pernet->ib_ps); in cma_init_net()
[all …]
|
| /openbmc/linux/include/net/ |
| H A D | inet_hashtables.h | 179 bool pernet; member
|
| /openbmc/linux/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 | 4749 tcp_hashinfo.pernet = false; in tcp_init()
|
| /openbmc/linux/net/dccp/ |
| H A D | proto.c | 1218 dccp_hashinfo.pernet = false; in dccp_init()
|