| /kernel/linux/linux-6.6/net/mptcp/ |
| 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
62 void __mptcp_fastopen_gen_msk_ackseq(struct mptcp_sock *msk, struct mptcp_subflow_context *subflow, in __mptcp_fastopen_gen_msk_ackseq() argument
|
| H A D | sched.c | 118 void mptcp_subflow_set_scheduled(struct mptcp_subflow_context *subflow, in mptcp_subflow_set_scheduled() argument
126 struct mptcp_subflow_context *subflow; in mptcp_sched_get_send() local
155 struct mptcp_subflow_context *subflow; in 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
[all...] |
| H A D | pm_userspace.c | 227 struct mptcp_subflow_context *subflow; in mptcp_userspace_pm_remove_id_zero_address() local
404 struct mptcp_subflow_context *subflow; in mptcp_nl_find_ssk() local
516 struct mptcp_subflow_context *subflow in mptcp_nl_cmd_sf_destroy() local
[all...] |
| H A D | pm.c | 222 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(ssk); in mptcp_pm_add_addr_received() local
296 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(ssk); in mptcp_pm_mp_prio_received() local
187 mptcp_pm_subflow_check_next(struct mptcp_sock *msk, const struct sock *ssk, const struct mptcp_subflow_context *subflow) mptcp_pm_subflow_check_next() argument
310 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); mptcp_pm_mp_fail_received() local
455 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(ssk); mptcp_pm_subflow_chk_stale() local
[all...] |
| H A D | sockopt.c | 72 struct mptcp_subflow_context *subflow; in mptcp_sol_socket_sync_intval() local
150 struct mptcp_subflow_context *subflow; in mptcp_setsockopt_sol_socket_tstamp() local
212 struct mptcp_subflow_context *subflow; in mptcp_setsockopt_sol_socket_timestamping() local
254 struct mptcp_subflow_context *subflow; mptcp_setsockopt_sol_socket_linger() local
586 struct mptcp_subflow_context *subflow; mptcp_setsockopt_sol_tcp_congestion() local
629 struct mptcp_subflow_context *subflow; mptcp_setsockopt_sol_tcp_cork() local
659 struct mptcp_subflow_context *subflow; mptcp_setsockopt_sol_tcp_nodelay() local
727 struct mptcp_subflow_context *subflow; mptcp_setsockopt_v4_set_tos() local
1028 struct mptcp_subflow_context *subflow; mptcp_getsockopt_tcpinfo() local
1120 struct mptcp_subflow_context *subflow; mptcp_getsockopt_subflow_addrs() local
1219 struct mptcp_subflow_context *subflow; mptcp_getsockopt_full_info() local
1464 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(ssk); mptcp_sockopt_sync() local
1477 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(ssk); mptcp_sockopt_sync_locked() local
[all...] |
| H A D | options.c | 407 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); in mptcp_syn_options() local
448 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); mptcp_established_options_mp() local
528 mptcp_write_data_fin(struct mptcp_subflow_context *subflow, struct sk_buff *skb, struct mptcp_ext *ext) mptcp_write_data_fin() argument
561 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); mptcp_established_options_dss() local
654 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); mptcp_established_options_add_addr() local
709 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); mptcp_established_options_rm_addr() local
739 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); mptcp_established_options_mp_prio() local
765 const struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); mptcp_established_options_rst() local
784 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); mptcp_established_options_fastclose() local
807 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); mptcp_established_options_mp_fail() local
829 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); mptcp_established_options() local
925 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
1116 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); mptcp_incoming_options() local
1253 struct mptcp_subflow_context *subflow; mptcp_set_rwin() local
1348 struct mptcp_subflow_context *subflow; mptcp_write_options() local
[all...] |
| H A D | subflow.c | 314 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); in subflow_prep_synack() local
379 static bool subflow_thmac_valid(struct mptcp_subflow_context *subflow) in subflow_thmac_valid() argument
397 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(ssk); mptcp_subflow_reset() local
424 struct mptcp_subflow_context *subflow; __mptcp_sync_state() local
444 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
465 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
492 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); subflow_finish_connect() local
578 subflow_set_local_id(struct mptcp_subflow_context *subflow, int local_id) subflow_set_local_id() argument
586 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); subflow_chk_local_id() local
628 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); subflow_v4_conn_request() local
659 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); subflow_v6_conn_request() local
754 __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
924 dbg_bad_map(struct mptcp_subflow_context *subflow, u32 ssn) dbg_bad_map() argument
932 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(ssk); skb_is_fully_mapped() local
945 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(ssk); validate_mapping() local
967 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(ssk); validate_data_csum() local
1046 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(ssk); get_mapping_status() local
1191 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(ssk); mptcp_subflow_discard_data() local
1218 subflow_can_fallback(struct mptcp_subflow_context *subflow) subflow_can_fallback() argument
1232 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(ssk); mptcp_subflow_fail() local
1259 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(ssk); subflow_check_data_avail() local
1356 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); mptcp_subflow_data_available() local
1383 const struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(ssk); mptcp_space() local
1411 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); subflow_data_ready() local
1460 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); mptcpv6_handle_mapped() local
1512 struct mptcp_subflow_context *subflow; __mptcp_subflow_connect() local
1646 struct mptcp_subflow_context *subflow; mptcp_subflow_create_socket() local
1749 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); subflow_state_change() local
1786 struct mptcp_subflow_context *subflow; mptcp_subflow_queue_clean() local
1982 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(ssk); tcp_release_cb_override() local
[all...] |
| H A D | pm_netlink.c | 118 struct mptcp_subflow_context *subflow; in lookup_subflow_by_saddr() local
136 struct mptcp_subflow_context *subflow; in lookup_subflow_by_daddr() local
409 struct mptcp_subflow_context *subflow; in fill_remote_addresses_vec() local
467 __mptcp_pm_send_ack(struct mptcp_sock *msk, struct mptcp_subflow_context *subflow, bool prio, bool backup) __mptcp_pm_send_ack() argument
487 mptcp_pm_send_ack(struct mptcp_sock *msk, struct mptcp_subflow_context *subflow, bool prio, bool backup) mptcp_pm_send_ack() argument
539 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(msk->first); mptcp_pm_create_subflow_or_signal_addr() local
728 struct mptcp_subflow_context *subflow; mptcp_pm_nl_addr_send_ack() local
747 struct mptcp_subflow_context *subflow; mptcp_pm_nl_mp_prio_send_ack() local
781 struct mptcp_subflow_context *subflow, *tmp; mptcp_pm_nl_rm_addr_or_subflow() local
1141 struct mptcp_subflow_context *iter, *subflow = mptcp_subflow_ctx(ssk); mptcp_pm_nl_subflow_chk_stale() local
2145 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(ssk); mptcp_event_addr_announced() local
[all...] |
| H A D | protocol.c | 84 struct mptcp_subflow_context *subflow; in __mptcp_socket_create() local
358 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(ssk); in __mptcp_move_skb() local
496 mptcp_timeout_from_subflow(const struct mptcp_subflow_context *subflow) mptcp_timeout_from_subflow() argument
506 struct mptcp_subflow_context *subflow; mptcp_set_timeout() local
537 struct mptcp_subflow_context *subflow; mptcp_send_ack() local
569 struct mptcp_subflow_context *subflow; mptcp_cleanup_rbuf() local
639 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(ssk); __mptcp_move_skbs_from_subflow() local
805 struct mptcp_subflow_context *subflow; __mptcp_error_report() local
842 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(ssk); mptcp_data_ready() local
902 struct mptcp_subflow_context *tmp, *subflow; __mptcp_flush_join_list() local
949 struct mptcp_subflow_context *subflow; mptcp_subflow_recv_lookup() local
1079 struct mptcp_subflow_context *subflow; mptcp_enter_memory_pressure() local
1387 mptcp_subflow_set_active(struct mptcp_subflow_context *subflow) mptcp_subflow_set_active() argument
1396 mptcp_subflow_active(struct mptcp_subflow_context *subflow) mptcp_subflow_active() argument
1420 struct mptcp_subflow_context *subflow; mptcp_subflow_get_send() local
1586 struct mptcp_subflow_context *subflow; __mptcp_push_pending() local
1652 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(ssk); __mptcp_subflow_push_pending() local
1960 struct mptcp_subflow_context *subflow; mptcp_rcv_space_adjust() local
2287 struct mptcp_subflow_context *subflow; mptcp_subflow_get_retrans() local
2365 __mptcp_subflow_disconnect(struct sock *ssk, struct mptcp_subflow_context *subflow, unsigned int flags) __mptcp_subflow_disconnect() argument
2389 __mptcp_close_ssk(struct sock *sk, struct sock *ssk, struct mptcp_subflow_context *subflow, unsigned int flags) __mptcp_close_ssk() argument
2482 mptcp_close_ssk(struct sock *sk, struct sock *ssk, struct mptcp_subflow_context *subflow) mptcp_close_ssk() argument
2491 mptcp_pm_subflow_check_next(mptcp_sk(sk), ssk, subflow); mptcp_close_ssk() local
2503 struct mptcp_subflow_context *subflow, *tmp; __mptcp_close_subflow() local
2535 struct mptcp_subflow_context *subflow, *tmp; mptcp_check_fastclose() local
2585 struct mptcp_subflow_context *subflow; __mptcp_retrans() local
2701 struct mptcp_subflow_context *subflow, *tmp; mptcp_do_fastclose() local
2928 struct mptcp_subflow_context *subflow; mptcp_check_send_data_fin() local
3030 struct mptcp_subflow_context *subflow; __mptcp_close() local
3241 struct mptcp_subflow_context *subflow; mptcp_sk_clone_init() local
3343 struct mptcp_subflow_context *subflow; mptcp_accept() local
3371 struct mptcp_subflow_context *subflow, *tmp; mptcp_destroy_common() local
3516 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(ssk); mptcp_subflow_process_delegated() local
3566 struct mptcp_subflow_context *subflow; mptcp_finish_connect() local
3598 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(ssk); mptcp_finish_join() local
3722 mptcp_subflow_early_fallback(struct mptcp_sock *msk, struct mptcp_subflow_context *subflow) mptcp_subflow_early_fallback() argument
3731 struct mptcp_subflow_context *subflow; mptcp_connect() local
3924 struct mptcp_subflow_context *subflow; mptcp_stream_accept() local
4050 struct mptcp_subflow_context *subflow; mptcp_napi_poll() local
[all...] |
| H A D | protocol.h | 550 mptcp_subflow_tcp_sock(const struct mptcp_subflow_context *subflow) in mptcp_subflow_tcp_sock() argument
556 mptcp_subflow_ctx_reset(struct mptcp_subflow_context *subflow) in mptcp_subflow_ctx_reset() argument
564 mptcp_subflow_get_map_offset(const struct mptcp_subflow_context *subflow) mptcp_subflow_get_map_offset() argument
572 mptcp_subflow_get_mapped_dsn(const struct mptcp_subflow_context *subflow) mptcp_subflow_get_mapped_dsn() argument
579 mptcp_subflow_delegate(struct mptcp_subflow_context *subflow, int action) mptcp_subflow_delegate() argument
680 __mptcp_subflow_active(struct mptcp_subflow_context *subflow) __mptcp_subflow_active() argument
787 struct mptcp_subflow_context *subflow; __mptcp_sync_sndbuf() local
811 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(ssk); __mptcp_propagate_sndbuf() local
824 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(ssk); mptcp_propagate_sndbuf() local
1012 subflow_get_local_id(const struct mptcp_subflow_context *subflow) subflow_get_local_id() argument
1061 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); mptcp_check_fallback() local
1078 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(ssk); mptcp_do_fallback() local
1110 is_active_ssk(struct mptcp_subflow_context *subflow) is_active_ssk() argument
1117 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); subflow_simultaneous_connect() local
[all...] |
| /kernel/linux/linux-5.10/net/mptcp/ |
| H A D | pm.c | 120 mptcp_pm_subflow_established(struct mptcp_sock *msk, struct mptcp_subflow_context *subflow) mptcp_pm_subflow_established() argument
|
| H A D | token.c | 154 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); in mptcp_token_new_connect() local
[all...] |
| H A D | options.c | 336 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); in mptcp_syn_options() local
398 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); mptcp_established_options_mp() local
456 mptcp_write_data_fin(struct mptcp_subflow_context *subflow, struct sk_buff *skb, struct mptcp_ext *ext) mptcp_write_data_fin() argument
489 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); mptcp_established_options_dss() local
584 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); mptcp_established_options_add_addr() local
632 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); mptcp_established_options_rm_addr() local
724 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
887 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); mptcp_incoming_options() local
[all...] |
| H A D | pm_netlink.c | 116 struct mptcp_subflow_context *subflow; in lookup_subflow_by_saddr() local
402 struct mptcp_subflow_context *subflow, *tmp; in mptcp_pm_nl_rm_addr_received() local
438 struct mptcp_subflow_context *subflow, *tm in mptcp_pm_nl_rm_subflow_received() local
[all...] |
| H A D | subflow.c | 255 static bool subflow_thmac_valid(struct mptcp_subflow_context *subflow) in subflow_thmac_valid() argument
275 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(ssk); mptcp_subflow_reset() local
287 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); subflow_finish_connect() local
365 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); subflow_v4_conn_request() local
395 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); subflow_v6_conn_request() local
514 mptcp_subflow_fully_established(struct mptcp_subflow_context *subflow, struct mptcp_options_received *mp_opt) mptcp_subflow_fully_established() argument
683 dbg_bad_map(struct mptcp_subflow_context *subflow, u32 ssn) dbg_bad_map() argument
691 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(ssk); skb_is_fully_mapped() local
704 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(ssk); validate_mapping() local
726 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(ssk); get_mapping_status() local
861 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(ssk); mptcp_subflow_discard_data() local
881 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(ssk); subflow_check_data_avail() local
968 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); mptcp_subflow_data_available() local
995 const struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(ssk); mptcp_space() local
1004 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); subflow_data_ready() local
1031 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); subflow_write_space() local
1058 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); mptcpv6_handle_mapped() local
1100 struct mptcp_subflow_context *subflow; __mptcp_subflow_connect() local
1173 struct mptcp_subflow_context *subflow; mptcp_subflow_create_socket() local
1265 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); subflow_state_change() local
[all...] |
| H A D | protocol.c | 92 struct mptcp_subflow_context *subflow; in __mptcp_socket_create() local
268 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(ssk); __mptcp_move_skb() local
415 struct mptcp_subflow_context *subflow; mptcp_check_data_fin() local
464 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(ssk); __mptcp_move_skbs_from_subflow() local
625 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(ssk); mptcp_data_ready() local
708 struct mptcp_subflow_context *subflow; mptcp_check_for_eof() local
739 struct mptcp_subflow_context *subflow; mptcp_subflow_recv_lookup() local
794 struct mptcp_subflow_context *subflow; mptcp_is_writeable() local
1049 struct mptcp_subflow_context *subflow; mptcp_nospace() local
1064 mptcp_subflow_active(struct mptcp_subflow_context *subflow) mptcp_subflow_active() argument
1091 struct mptcp_subflow_context *subflow; mptcp_subflow_get_send() local
1383 struct mptcp_subflow_context *subflow; mptcp_rcv_space_adjust() local
1644 struct mptcp_subflow_context *subflow; mptcp_subflow_get_retrans() local
1685 __mptcp_close_ssk(struct sock *sk, struct sock *ssk, struct mptcp_subflow_context *subflow, long timeout) __mptcp_close_ssk() argument
1736 struct mptcp_subflow_context *subflow, *tmp; __mptcp_close_subflow() local
1957 struct mptcp_subflow_context *subflow, *tmp; mptcp_close() local
2140 struct mptcp_subflow_context *subflow; mptcp_accept() local
2418 struct mptcp_subflow_context *subflow; mptcp_finish_connect() local
2460 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); mptcp_finish_join() local
2559 mptcp_subflow_early_fallback(struct mptcp_sock *msk, struct mptcp_subflow_context *subflow) mptcp_subflow_early_fallback() argument
2570 struct mptcp_subflow_context *subflow; mptcp_stream_connect() local
2672 struct mptcp_subflow_context *subflow; mptcp_stream_accept() local
2732 struct mptcp_subflow_context *subflow; mptcp_shutdown() local
[all...] |
| H A D | protocol.h | 224 struct socket *subflow; /* outgoing connect/listener/!mp_capable */ member
345 mptcp_subflow_tcp_sock(const struct mptcp_subflow_context *subflow) in mptcp_subflow_tcp_sock() argument
351 mptcp_subflow_get_map_offset(const struct mptcp_subflow_context *subflow) in mptcp_subflow_get_map_offset() argument
359 mptcp_subflow_get_mapped_dsn(const struct mptcp_subflow_context *subflow) in mptcp_subflow_get_mapped_dsn() argument
513 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); mptcp_check_fallback() local
530 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); mptcp_do_fallback() local
540 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); subflow_simultaneous_connect() local
[all...] |