| /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()
424 pr_debug("subflow=%p, token=%u, thmac=%llu, subflow->thmac=%llu\n", in subflow_thmac_valid()
425 subflow, subflo in subflow_thmac_valid()
432 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(ssk); mptcp_subflow_reset() local
459 struct mptcp_subflow_context *subflow; __mptcp_sync_state() local
478 subflow_set_remote_key(struct mptcp_sock * msk,struct mptcp_subflow_context * subflow,const struct mptcp_options_received * mp_opt) subflow_set_remote_key() argument
502 mptcp_propagate_state(struct sock * sk,struct sock * ssk,struct mptcp_subflow_context * subflow,const struct mptcp_options_received * mp_opt) mptcp_propagate_state() argument
528 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); subflow_finish_connect() local
624 subflow_set_local_id(struct mptcp_subflow_context * subflow,int local_id) subflow_set_local_id() argument
632 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); subflow_chk_local_id() local
676 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); subflow_v4_conn_request() local
707 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); subflow_v6_conn_request() local
798 __mptcp_subflow_fully_established(struct mptcp_sock * msk,struct mptcp_subflow_context * subflow,const struct mptcp_options_received * mp_opt) __mptcp_subflow_fully_established() argument
938 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(child); subflow_syn_recv_sock() local
988 dbg_bad_map(struct mptcp_subflow_context * subflow,u32 ssn) dbg_bad_map() argument
996 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(ssk); skb_is_fully_mapped() local
1011 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(ssk); validate_mapping() local
1033 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(ssk); validate_data_csum() local
1112 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(ssk); get_mapping_status() local
1259 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(ssk); mptcp_subflow_discard_data() local
1291 const struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(ssk); subflow_sched_work_if_closed() local
1317 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(ssk); mptcp_subflow_fail() local
1354 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(ssk); subflow_check_data_avail() local
1453 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); mptcp_subflow_data_available() local
1480 const struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(ssk); mptcp_space() local
1508 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); subflow_data_ready() local
1565 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); mptcpv6_handle_mapped() local
1617 struct mptcp_subflow_context *subflow; __mptcp_subflow_connect() local
1779 struct mptcp_subflow_context *subflow; mptcp_subflow_create_socket() local
1876 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); subflow_state_change() local
1897 struct mptcp_subflow_context *subflow; mptcp_subflow_queue_clean() local
2093 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(ssk); tcp_release_cb_override() local
[all...] |
| H A D | pm.c | 121 struct mptcp_subflow_context *subflow; in mptcp_lookup_subflow_by_saddr() local
125 mptcp_for_each_subflow(msk, subflow) { in mptcp_lookup_subflow_by_saddr()
126 skc = (struct sock_common *)mptcp_subflow_tcp_sock(subflow); in mptcp_lookup_subflow_by_saddr()
221 struct mptcp_subflow_context *subflow, in subflow_in_rm_list()
224 struct sock *ssk = mptcp_subflow_tcp_sock(subflow); in subflow_in_rm_list()
233 subflow->send_mp_prio = 1; in mptcp_pm_addr_send_ack_avoid_list() local
234 subflow->request_bkup = backup; in mptcp_pm_addr_send_ack_avoid_list()
242 struct mptcp_subflow_context *subflow, in mptcp_pm_addr_send_ack_avoid_list()
246 __mptcp_pm_send_ack(msk, subflow, prio, backup); in mptcp_pm_addr_send_ack_avoid_list()
250 static bool subflow_in_rm_list(const struct mptcp_subflow_context *subflow, in mptcp_pm_addr_send_ack_avoid_list()
187 __mptcp_pm_send_ack(struct mptcp_sock * msk,struct mptcp_subflow_context * subflow,bool prio,bool backup) __mptcp_pm_send_ack() argument
208 mptcp_pm_send_ack(struct mptcp_sock * msk,struct mptcp_subflow_context * subflow,bool prio,bool backup) mptcp_pm_send_ack() argument
216 subflow_in_rm_list(const struct mptcp_subflow_context * subflow,const struct mptcp_rm_list * rm_list) subflow_in_rm_list() argument
279 struct mptcp_subflow_context *subflow; mptcp_pm_mp_prio_send_ack() local
311 struct mptcp_subflow_context *subflow; mptcp_adjust_add_addr_timeout() local
658 mptcp_pm_subflow_check_next(struct mptcp_sock * msk,const struct mptcp_subflow_context * subflow) mptcp_pm_subflow_check_next() argument
694 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(ssk); mptcp_pm_add_addr_received() local
759 struct mptcp_subflow_context *subflow, *tmp; mptcp_pm_rm_addr_or_subflow() local
850 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(ssk); mptcp_pm_mp_prio_received() local
864 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); mptcp_pm_mp_fail_received() local
1024 struct mptcp_subflow_context *iter, *subflow = mptcp_subflow_ctx(ssk); mptcp_pm_subflows_chk_stale() local
1061 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(ssk); mptcp_pm_subflow_chk_stale() local
[all...] |
| H A D | options.c | 56 * close the subflow with a RST, as it is not behaving as negotiated. in mptcp_parse_option()
58 * receiver MUST close the subflow with a RST, as it is considered in mptcp_parse_option()
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()
417 subflow->request_mptcp = 0; in mptcp_syn_options()
426 } else if (subflow->request_join) { in mptcp_syn_options()
427 pr_debug("remote_token=%u, nonce=%u\n", subflow->remote_token, in mptcp_syn_options()
428 subflow->local_nonce); in mptcp_syn_options()
430 opts->join_id = subflow in mptcp_syn_options()
454 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); mptcp_established_options_mp() local
534 mptcp_write_data_fin(struct mptcp_subflow_context * subflow,struct sk_buff * skb,struct mptcp_ext * ext) mptcp_write_data_fin() argument
567 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); mptcp_established_options_dss() local
666 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); mptcp_established_options_add_addr() local
714 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); mptcp_established_options_rm_addr() local
744 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); mptcp_established_options_mp_prio() local
770 const struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); mptcp_established_options_rst() local
789 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); mptcp_established_options_fastclose() local
812 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); mptcp_established_options_mp_fail() local
834 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); mptcp_established_options() local
934 check_fully_established(struct mptcp_sock * msk,struct sock * ssk,struct mptcp_subflow_context * subflow,struct sk_buff * skb,struct mptcp_options_received * mp_opt) check_fully_established() argument
1051 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(ssk); rwin_update() local
1156 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); mptcp_incoming_options() local
1357 struct mptcp_subflow_context *subflow; mptcp_track_rwin() local
1407 struct mptcp_subflow_context *subflow; mptcp_write_options() local
[all...] |
| H A D | protocol.c | 105 struct mptcp_subflow_context *subflow; in __mptcp_socket_create() local
116 subflow = mptcp_subflow_ctx(ssock->sk); in __mptcp_socket_create()
117 list_add(&subflow->node, &msk->conn_list); in __mptcp_socket_create()
119 subflow->request_mptcp = 1; in __mptcp_socket_create()
120 subflow->subflow_id = msk->subflow_id++; in __mptcp_socket_create()
123 WRITE_ONCE(subflow->local_id, 0); in __mptcp_socket_create()
357 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(ssk); in mptcp_init_skb() local
364 MPTCP_SKB_CB(skb)->map_seq = mptcp_subflow_get_mapped_dsn(subflow); in mptcp_init_skb()
443 struct mptcp_subflow_context *subflow; in mptcp_shutdown_subflows() local
445 mptcp_for_each_subflow(msk, subflow) { in mptcp_shutdown_subflows()
[all …]
|
| H A D | protocol.h | 272 /* Arbitrary compromise between as low as possible to react timely to subflow
274 * samples due to peer sending data on a different subflow WRT to the incoming
283 u64 local_key; /* protected by the first subflow socket lock
312 bool recovery; /* closing subflow write queue reinjected */
321 u8 pending_state; /* A subflow asked to set this sk_state,
346 * ONCE annotation, the subflow outside the socket
541 /* MPTCP subflow context */
583 is_mptfo : 1, /* subflow is doing TFO */
597 u8 hmac[MPTCPOPT_HMAC_LEN]; /* MPJ subflow only */
641 mptcp_subflow_tcp_sock(const struct mptcp_subflow_context *subflow) in mptcp_subflow_tcp_sock() argument
647 mptcp_subflow_ctx_reset(struct mptcp_subflow_context * subflow) mptcp_subflow_ctx_reset() argument
684 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); mptcp_send_active_reset_reason() local
712 __mptcp_subflow_lend_fwdmem(struct mptcp_subflow_context * subflow,int size) __mptcp_subflow_lend_fwdmem() argument
720 mptcp_subflow_lend_fwdmem(struct mptcp_subflow_context * subflow,struct sk_buff * skb) mptcp_subflow_lend_fwdmem() argument
728 mptcp_subflow_get_map_offset(const struct mptcp_subflow_context * subflow) mptcp_subflow_get_map_offset() argument
736 mptcp_subflow_get_mapped_dsn(const struct mptcp_subflow_context * subflow) mptcp_subflow_get_mapped_dsn() argument
743 mptcp_subflow_delegate(struct mptcp_subflow_context * subflow,int action) mptcp_subflow_delegate() argument
885 __mptcp_subflow_active(struct mptcp_subflow_context * subflow) __mptcp_subflow_active() argument
1020 struct mptcp_subflow_context *subflow; __mptcp_sync_sndbuf() local
1044 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(ssk); __mptcp_propagate_sndbuf() local
1057 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(ssk); mptcp_propagate_sndbuf() local
1254 subflow_get_local_id(const struct mptcp_subflow_context * subflow) subflow_get_local_id() argument
1313 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); mptcp_check_fallback() local
1332 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(ssk); mptcp_try_fallback() local
1354 mptcp_early_fallback(struct mptcp_sock * msk,struct mptcp_subflow_context * subflow,int fb_mib) mptcp_early_fallback() argument
1372 is_active_ssk(struct mptcp_subflow_context * subflow) is_active_ssk() argument
1379 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
20 if (!subflow) in mptcp_fastopen_subflow_synack_set_params()
23 ssk = subflow->tcp_sock; in mptcp_fastopen_subflow_synack_set_params()
24 sk = subflow->conn; in mptcp_fastopen_subflow_synack_set_params()
27 subflow->is_mptfo = 1; in mptcp_fastopen_subflow_synack_set_params()
37 mptcp_subflow_lend_fwdmem(subflow, skb); in mptcp_fastopen_subflow_synack_set_params()
43 subflow->ssn_offset += skb->len; in mptcp_fastopen_subflow_synack_set_params()
|
| H A D | sockopt.c | 78 struct mptcp_subflow_context *subflow; in mptcp_sol_socket_sync_intval() local
84 mptcp_for_each_subflow(msk, subflow) { in mptcp_sol_socket_sync_intval()
85 struct sock *ssk = mptcp_subflow_tcp_sock(subflow); in mptcp_sol_socket_sync_intval()
122 subflow->setsockopt_seq = msk->setsockopt_seq; in mptcp_sol_socket_sync_intval()
156 struct mptcp_subflow_context *subflow; in mptcp_setsockopt_sol_socket_tstamp() local
166 mptcp_for_each_subflow(msk, subflow) { in mptcp_setsockopt_sol_socket_tstamp()
167 struct sock *ssk = mptcp_subflow_tcp_sock(subflow); in mptcp_setsockopt_sol_socket_tstamp()
216 struct mptcp_subflow_context *subflow; in mptcp_setsockopt_sol_socket_timestamping() local
242 mptcp_for_each_subflow(msk, subflow) { in mptcp_setsockopt_sol_socket_timestamping()
243 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 | pm_kernel.c | 102 struct mptcp_subflow_context *subflow; in lookup_subflow_by_daddr()
105 mptcp_for_each_subflow(msk, subflow) { in lookup_subflow_by_daddr()
106 struct sock *ssk = mptcp_subflow_tcp_sock(subflow); in lookup_subflow_by_daddr()
212 struct mptcp_subflow_context *subflow; in fill_remote_addresses_fullmesh()
219 mptcp_for_each_subflow(msk, subflow) in fill_remote_addresses_fullmesh()
220 if (READ_ONCE(subflow->local_id) == local->id) in fill_remote_addresses_fullmesh()
221 __set_bit(subflow->remote_id, unavail_id); in fill_remote_addresses_fullmesh()
223 mptcp_for_each_subflow(msk, subflow) { in fill_remote_addresses_fullmesh()
224 ssk = mptcp_subflow_tcp_sock(subflow); in fill_remote_addresses_fullmesh()
226 addrs[i].id = READ_ONCE(subflow in fill_remote_addresses_fullmesh()
101 struct mptcp_subflow_context *subflow; lookup_subflow_by_daddr() local
210 struct mptcp_subflow_context *subflow; fill_remote_addresses_fullmesh() local
298 struct mptcp_subflow_context *subflow; mptcp_mpc_endpoint_setup() local
505 struct mptcp_subflow_context *subflow; fill_local_laminar_endp() local
[all...] |
| H A D | pm_userspace.c | 93 /* If the subflow is closed from the other peer (not via a
94 * subflow destroy command then), we want to keep the entry
96 * able to send RM_ADDR after the removal of the subflow.
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()
283 /* only delete if either announced or matching a subflow */ in mptcp_pm_remove_addr_entry()
436 struct mptcp_subflow_context *subflow; in mptcp_nl_find_ssk() local
441 mptcp_for_each_subflow(msk, subflow) { in mptcp_nl_find_ssk()
445 ssk = mptcp_subflow_tcp_sock(subflow); in mptcp_nl_find_ssk()
[all...] |
| 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 | 468 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(ssk); in mptcp_event_addr_announced() local
469 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 | 783 local flags="subflow"
789 # let the mptcp subflow be established in background before
1614 # the subflow creation
1853 local subflow="client"
1867 subflow="server"
1880 print_check "rm subflow ${subflow}"
1889 # in case of simult flush, the subflow removal count on each side is
2033 # number of all subflows, including the initial subflow.
2122 # subflow limite
[all...] |
| H A D | pm_netlink.sh | 162 add_endpoint 10.0.1.2 flags subflow dev lo
168 "2,10.0.1.2,subflow,lo" \
268 add_endpoint 10.0.1.1 flags subflow
270 check "show_endpoints" "$(format_endpoints "1,10.0.1.1,subflow backup")" \
273 check "show_endpoints" "$(format_endpoints "1,10.0.1.1,subflow")" \
280 check "show_endpoints" "$(format_endpoints "1,10.0.1.1,subflow fullmesh")" \
283 check "show_endpoints" "$(format_endpoints "1,10.0.1.1,subflow")" \
286 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/Documentation/networking/ |
| 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
|