| /linux/net/mptcp/ |
| H A D | subflow.c | 347 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); in subflow_prep_synack() local
355 mptcp_fastopen_subflow_synack_set_params(subflow, req); in subflow_prep_synack()
414 static bool subflow_thmac_valid(struct mptcp_subflow_context *subflow) in subflow_thmac_valid() argument
419 subflow_generate_hmac(subflow->remote_key, subflow->local_key, in subflow_thmac_valid()
420 subflow->remote_nonce, subflow->local_nonce, in subflow_thmac_valid()
425 subflow, subflow->token, thmac, subflow->thmac); in subflow_thmac_valid()
427 return thmac == subflow->thmac; in subflow_thmac_valid()
432 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(ssk); in mptcp_subflow_reset() local
433 struct sock *sk = subflow->conn; in mptcp_subflow_reset()
459 struct mptcp_subflow_context *subflow; in __mptcp_sync_state() local
[all …]
|
| H A D | options.c | 404 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); in mptcp_syn_options() local
409 subflow->snd_isn = TCP_SKB_CB(skb)->end_seq; in mptcp_syn_options()
410 if (subflow->request_mptcp) { in mptcp_syn_options()
416 } else if (subflow->request_join) { in mptcp_syn_options()
417 pr_debug("remote_token=%u, nonce=%u\n", subflow->remote_token, in mptcp_syn_options()
418 subflow->local_nonce); in mptcp_syn_options()
420 opts->join_id = subflow->local_id; in mptcp_syn_options()
421 opts->token = subflow->remote_token; in mptcp_syn_options()
422 opts->nonce = subflow->local_nonce; in mptcp_syn_options()
423 opts->backup = subflow->request_bkup; in mptcp_syn_options()
[all …]
|
| H A D | pm.c | 119 struct mptcp_subflow_context *subflow; in mptcp_lookup_subflow_by_saddr() local
123 list_for_each_entry(subflow, list, node) { in mptcp_lookup_subflow_by_saddr()
124 skc = (struct sock_common *)mptcp_subflow_tcp_sock(subflow); in mptcp_lookup_subflow_by_saddr()
185 struct mptcp_subflow_context *subflow, in __mptcp_pm_send_ack() argument
188 struct sock *ssk = mptcp_subflow_tcp_sock(subflow); in __mptcp_pm_send_ack()
197 subflow->send_mp_prio = 1; in __mptcp_pm_send_ack()
198 subflow->request_bkup = backup; in __mptcp_pm_send_ack()
206 struct mptcp_subflow_context *subflow, in mptcp_pm_send_ack() argument
210 __mptcp_pm_send_ack(msk, subflow, prio, backup); in mptcp_pm_send_ack()
216 struct mptcp_subflow_context *subflow, *alt = NULL; in mptcp_pm_addr_send_ack() local
[all …]
|
| H A D | protocol.c | 72 struct mptcp_subflow_context *subflow; in __mptcp_socket_create() local
83 subflow = mptcp_subflow_ctx(ssock->sk); in __mptcp_socket_create()
84 list_add(&subflow->node, &msk->conn_list); in __mptcp_socket_create()
86 subflow->request_mptcp = 1; in __mptcp_socket_create()
87 subflow->subflow_id = msk->subflow_id++; in __mptcp_socket_create()
90 WRITE_ONCE(subflow->local_id, 0); in __mptcp_socket_create()
279 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(ssk); in __mptcp_move_skb() local
301 MPTCP_SKB_CB(skb)->map_seq = mptcp_subflow_get_mapped_dsn(subflow); in __mptcp_move_skb()
422 static long mptcp_timeout_from_subflow(const struct mptcp_subflow_context *subflow) in mptcp_timeout_from_subflow() argument
424 const struct sock *ssk = mptcp_subflow_tcp_sock(subflow); in mptcp_timeout_from_subflow()
[all …]
|
| H A D | protocol.h | 276 u64 local_key; /* protected by the first subflow socket lock
305 bool recovery; /* closing subflow write queue reinjected */
314 u8 pending_state; /* A subflow asked to set this sk_state,
337 * ONCE annotation, the subflow outside the socket
494 /* MPTCP subflow context */
533 is_mptfo : 1, /* subflow is doing TFO */
546 u8 hmac[MPTCPOPT_HMAC_LEN]; /* MPJ subflow only */
590 mptcp_subflow_tcp_sock(const struct mptcp_subflow_context *subflow) in mptcp_subflow_tcp_sock()
592 return subflow->tcp_sock; in mptcp_subflow_tcp_sock()
596 mptcp_subflow_ctx_reset(struct mptcp_subflow_context *subflow) in mptcp_subflow_ctx_reset()
589 mptcp_subflow_tcp_sock(const struct mptcp_subflow_context * subflow) mptcp_subflow_tcp_sock() argument
595 mptcp_subflow_ctx_reset(struct mptcp_subflow_context * subflow) mptcp_subflow_ctx_reset() argument
632 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); mptcp_send_active_reset_reason() local
640 mptcp_subflow_get_map_offset(const struct mptcp_subflow_context * subflow) mptcp_subflow_get_map_offset() argument
648 mptcp_subflow_get_mapped_dsn(const struct mptcp_subflow_context * subflow) mptcp_subflow_get_mapped_dsn() argument
655 mptcp_subflow_delegate(struct mptcp_subflow_context * subflow,int action) mptcp_subflow_delegate() argument
789 __mptcp_subflow_active(struct mptcp_subflow_context * subflow) __mptcp_subflow_active() argument
919 struct mptcp_subflow_context *subflow; __mptcp_sync_sndbuf() local
943 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(ssk); __mptcp_propagate_sndbuf() local
956 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(ssk); mptcp_propagate_sndbuf() local
1156 subflow_get_local_id(const struct mptcp_subflow_context * subflow) subflow_get_local_id() argument
1205 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); mptcp_check_fallback() local
1233 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(ssk); mptcp_do_fallback() local
1255 mptcp_subflow_early_fallback(struct mptcp_sock * msk,struct mptcp_subflow_context * subflow) mptcp_subflow_early_fallback() argument
1273 is_active_ssk(struct mptcp_subflow_context * subflow) is_active_ssk() argument
1280 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); subflow_simultaneous_connect() local
[all...] |
| H A D | fastopen.c | 9 void mptcp_fastopen_subflow_synack_set_params(struct mptcp_subflow_context *subflow, in mptcp_fastopen_subflow_synack_set_params() argument
19 if (!subflow) in mptcp_fastopen_subflow_synack_set_params()
22 ssk = subflow->tcp_sock; in mptcp_fastopen_subflow_synack_set_params()
23 sk = subflow->conn; in mptcp_fastopen_subflow_synack_set_params()
26 subflow->is_mptfo = 1; in mptcp_fastopen_subflow_synack_set_params()
41 subflow->ssn_offset += skb->len; in mptcp_fastopen_subflow_synack_set_params()
|
| H A D | sockopt.c | 72 struct mptcp_subflow_context *subflow; in mptcp_sol_socket_sync_intval() local
78 mptcp_for_each_subflow(msk, subflow) { in mptcp_sol_socket_sync_intval()
79 struct sock *ssk = mptcp_subflow_tcp_sock(subflow); in mptcp_sol_socket_sync_intval()
116 subflow->setsockopt_seq = msk->setsockopt_seq; in mptcp_sol_socket_sync_intval()
150 struct mptcp_subflow_context *subflow; in mptcp_setsockopt_sol_socket_tstamp() local
160 mptcp_for_each_subflow(msk, subflow) { in mptcp_setsockopt_sol_socket_tstamp()
161 struct sock *ssk = mptcp_subflow_tcp_sock(subflow); in mptcp_setsockopt_sol_socket_tstamp()
210 struct mptcp_subflow_context *subflow; in mptcp_setsockopt_sol_socket_timestamping() local
236 mptcp_for_each_subflow(msk, subflow) { in mptcp_setsockopt_sol_socket_timestamping()
237 struct sock *ssk = mptcp_subflow_tcp_sock(subflow); in mptcp_setsockopt_sol_socket_timestamping()
[all …]
|
| H A D | sched.c | 162 void mptcp_subflow_set_scheduled(struct mptcp_subflow_context *subflow, in mptcp_sched_get_send()
165 WRITE_ONCE(subflow->scheduled, scheduled); in mptcp_sched_get_send()
170 struct mptcp_subflow_context *subflow; in mptcp_sched_get_send()
185 mptcp_for_each_subflow(msk, subflow) { in mptcp_sched_get_retrans()
186 if (READ_ONCE(subflow->scheduled)) in mptcp_sched_get_retrans()
197 struct mptcp_subflow_context *subflow; in mptcp_sched_get_retrans()
205 mptcp_for_each_subflow(msk, subflow) { in mptcp_sched_get_retrans()
206 if (READ_ONCE(subflow->scheduled)) in mptcp_sched_get_retrans()
151 mptcp_subflow_set_scheduled(struct mptcp_subflow_context * subflow,bool scheduled) mptcp_subflow_set_scheduled() argument
159 struct mptcp_subflow_context *subflow; mptcp_sched_get_send() local
187 struct mptcp_subflow_context *subflow; mptcp_sched_get_retrans() local
|
| H A D | token.c | 153 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(ssk); in mptcp_token_new_connect() local
154 struct mptcp_sock *msk = mptcp_sk(subflow->conn); in mptcp_token_new_connect()
156 struct sock *sk = subflow->conn; in mptcp_token_new_connect()
160 mptcp_crypto_key_gen_sha(&subflow->local_key, &subflow->token, in mptcp_token_new_connect()
161 &subflow->idsn); in mptcp_token_new_connect()
163 bucket = token_bucket(subflow->token); in mptcp_token_new_connect()
165 if (__token_bucket_busy(bucket, subflow->token)) { in mptcp_token_new_connect()
173 ssk, subflow->local_key, subflow->token, subflow->idsn); in mptcp_token_new_connect()
175 WRITE_ONCE(msk->token, subflow->token); in mptcp_token_new_connect()
|
| H A D | ctrl.c | 514 struct mptcp_subflow_context *subflow; in mptcp_active_detect_blackhole() local
522 subflow = mptcp_subflow_ctx(ssk); in mptcp_active_detect_blackhole()
525 if (!subflow->request_mptcp) { in mptcp_active_detect_blackhole()
527 subflow->mpc_drop = 0; in mptcp_active_detect_blackhole()
537 subflow->mpc_drop = 1; in mptcp_active_detect_blackhole()
538 mptcp_subflow_early_fallback(mptcp_sk(subflow->conn), subflow); in mptcp_active_detect_blackhole()
|
| H A D | pm_kernel.c | 84 struct mptcp_subflow_context *subflow; in lookup_subflow_by_daddr() local
87 list_for_each_entry(subflow, list, node) { in lookup_subflow_by_daddr()
88 struct sock *ssk = mptcp_subflow_tcp_sock(subflow); in lookup_subflow_by_daddr()
172 struct mptcp_subflow_context *subflow; in fill_remote_addresses_vec() local
199 mptcp_for_each_subflow(msk, subflow) in fill_remote_addresses_vec()
200 if (READ_ONCE(subflow->local_id) == local->id) in fill_remote_addresses_vec()
201 __set_bit(subflow->remote_id, unavail_id); in fill_remote_addresses_vec()
203 mptcp_for_each_subflow(msk, subflow) { in fill_remote_addresses_vec()
204 ssk = mptcp_subflow_tcp_sock(subflow); in fill_remote_addresses_vec()
206 addrs[i].id = READ_ONCE(subflow->remote_id); in fill_remote_addresses_vec()
[all …]
|
| H A D | pm_userspace.c | 249 struct mptcp_subflow_context *subflow; in mptcp_userspace_pm_remove_id_zero_address() local
255 mptcp_for_each_subflow(msk, subflow) { in mptcp_userspace_pm_remove_id_zero_address()
256 if (READ_ONCE(subflow->local_id) == 0) { in mptcp_userspace_pm_remove_id_zero_address()
434 struct mptcp_subflow_context *subflow; in mptcp_nl_find_ssk() local
439 mptcp_for_each_subflow(msk, subflow) { in mptcp_nl_find_ssk()
443 ssk = mptcp_subflow_tcp_sock(subflow); in mptcp_nl_find_ssk()
|
| H A D | Makefile | 4 mptcp-y := protocol.o subflow.o options.o token.o crypto.o ctrl.o pm.o diag.o \
|
| H A D | Kconfig | 10 subflows in order to utilize multiple network paths. Each subflow
|
| H A D | pm_netlink.c | 455 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(ssk); in mptcp_event_addr_announced() local
456 struct mptcp_sock *msk = mptcp_sk(subflow->conn); in mptcp_event_addr_announced()
|
| /linux/tools/testing/selftests/net/mptcp/ |
| H A D | mptcp_join.sh | 1693 local subflow="client"
1707 subflow="server"
1720 print_check "rm subflow ${subflow}"
1966 pm_nl_add_endpoint $ns2 10.0.3.2 flags subflow
1975 pm_nl_add_endpoint $ns2 10.0.3.2 flags subflow
1985 pm_nl_add_endpoint $ns2 10.0.3.2 flags subflow
1994 pm_nl_add_endpoint $ns2 10.0.3.2 flags subflow
1995 pm_nl_add_endpoint $ns2 10.0.2.2 flags subflow
2004 pm_nl_add_endpoint $ns2 10.0.3.2 flags subflow
2005 pm_nl_add_endpoint $ns2 10.0.2.2 flags subflow
[all …]
|
| H A D | pm_netlink.sh | 150 add_endpoint 10.0.1.2 flags subflow dev lo
156 "2,10.0.1.2,subflow,lo" \
242 add_endpoint 10.0.1.1 flags subflow
244 check "show_endpoints" "$(format_endpoints "1,10.0.1.1,subflow backup")" \
247 check "show_endpoints" "$(format_endpoints "1,10.0.1.1,subflow")" \
254 check "show_endpoints" "$(format_endpoints "1,10.0.1.1,subflow fullmesh")" \
257 check "show_endpoints" "$(format_endpoints "1,10.0.1.1,subflow")" \
260 check "show_endpoints" "$(format_endpoints "1,10.0.1.1,subflow backup fullmesh")" \
|
| H A D | simult_flows.sh | 90 mptcp_lib_pm_nl_add_endpoint "${ns1}" 10.0.2.1 dev ns1eth2 flags subflow
|
| /linux/include/trace/events/ |
| H A D | mptcp.h | 20 TP_PROTO(struct mptcp_subflow_context *subflow),
22 TP_ARGS(subflow),
36 __entry->active = mptcp_subflow_active(subflow);
37 __entry->backup = subflow->backup || subflow->request_bkup;
39 if (subflow->tcp_sock && sk_fullsock(subflow->tcp_sock))
40 __entry->free = sk_stream_memory_free(subflow->tcp_sock);
44 ssk = mptcp_subflow_tcp_sock(subflow);
|
| /linux/Documentation/networking/ |
| H A D | mptcp-sysctl.rst | 22 by the initial subflow if the value is 1. This controls a flag that is
63 unchanged for such time, after the last subflow removal, before
81 socket. In-kernel path management will control subflow
84 API. Userspace path management puts per-MPTCP-connection subflow
98 socket. In-kernel path management will control subflow
101 API. Userspace path management puts per-MPTCP-connection subflow
125 pending outstanding data on a given subflow required to declare it stale.
|
| H A D | mptcp.rst | 41 (Linux-specific), a *subflow* (or *path*) is created. This *subflow* consists of
45 *option* field of the underlying TCP *subflow*. This field contains, amongst
79 The Packet Scheduler is in charge of selecting which available *subflow(s)* to
127 values per subflow.
151 kernel is in charge of creating subflow sockets: they are TCP sockets where the
|