| /kernel/linux/linux-6.6/net/mptcp/ |
| 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()
397 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(ssk); in mptcp_subflow_reset() local
424 struct mptcp_subflow_context *subflow; in __mptcp_sync_state() local
445 struct mptcp_subflow_context *subflow, in subflow_set_remote_key()
466 struct mptcp_subflow_context *subflow, in mptcp_propagate_state()
492 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); in subflow_finish_connect() local
578 static void subflow_set_local_id(struct mptcp_subflow_context *subflow, int local_id) in subflow_set_local_id()
586 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); in subflow_chk_local_id() local
628 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); in subflow_v4_conn_request() local
[all …]
|
| 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); in mptcp_established_options_mp() local
528 static void mptcp_write_data_fin(struct mptcp_subflow_context *subflow, in mptcp_write_data_fin()
561 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); in mptcp_established_options_dss() local
654 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); in mptcp_established_options_add_addr() local
709 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); in mptcp_established_options_rm_addr() local
739 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); in mptcp_established_options_mp_prio() local
765 const struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); in mptcp_established_options_rst() local
784 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); in mptcp_established_options_fastclose() local
807 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); in mptcp_established_options_mp_fail() local
[all …]
|
| 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 static long mptcp_timeout_from_subflow(const struct mptcp_subflow_context *subflow) in mptcp_timeout_from_subflow()
506 struct mptcp_subflow_context *subflow; in mptcp_set_timeout() local
537 struct mptcp_subflow_context *subflow; in mptcp_send_ack() local
569 struct mptcp_subflow_context *subflow; in mptcp_cleanup_rbuf() local
639 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(ssk); in __mptcp_move_skbs_from_subflow() local
805 struct mptcp_subflow_context *subflow; in __mptcp_error_report() local
842 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(ssk); in mptcp_data_ready() local
902 struct mptcp_subflow_context *tmp, *subflow; in __mptcp_flush_join_list() local
[all …]
|
| 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; in mptcp_setsockopt_sol_socket_linger() local
586 struct mptcp_subflow_context *subflow; in mptcp_setsockopt_sol_tcp_congestion() local
629 struct mptcp_subflow_context *subflow; in mptcp_setsockopt_sol_tcp_cork() local
659 struct mptcp_subflow_context *subflow; in mptcp_setsockopt_sol_tcp_nodelay() local
727 struct mptcp_subflow_context *subflow; in mptcp_setsockopt_v4_set_tos() local
1028 struct mptcp_subflow_context *subflow; in mptcp_getsockopt_tcpinfo() local
1120 struct mptcp_subflow_context *subflow; in mptcp_getsockopt_subflow_addrs() local
[all …]
|
| D | sched.c | 118 void mptcp_subflow_set_scheduled(struct mptcp_subflow_context *subflow, in mptcp_subflow_set_scheduled()
126 struct mptcp_subflow_context *subflow; in mptcp_sched_get_send() local
155 struct mptcp_subflow_context *subflow; in mptcp_sched_get_retrans() local
|
| D | fastopen.c | 9 void mptcp_fastopen_subflow_synack_set_params(struct mptcp_subflow_context *subflow, in mptcp_fastopen_subflow_synack_set_params()
62 void __mptcp_fastopen_gen_msk_ackseq(struct mptcp_sock *msk, struct mptcp_subflow_context *subflow, in __mptcp_fastopen_gen_msk_ackseq()
|
| D | pm.c | 188 const struct mptcp_subflow_context *subflow) in mptcp_pm_subflow_check_next()
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
310 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); in mptcp_pm_mp_fail_received() local
455 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(ssk); in mptcp_pm_subflow_chk_stale() local
|
| D | protocol.h | 550 mptcp_subflow_tcp_sock(const struct mptcp_subflow_context *subflow) in mptcp_subflow_tcp_sock()
556 mptcp_subflow_ctx_reset(struct mptcp_subflow_context *subflow) in mptcp_subflow_ctx_reset()
564 mptcp_subflow_get_map_offset(const struct mptcp_subflow_context *subflow) in mptcp_subflow_get_map_offset()
572 mptcp_subflow_get_mapped_dsn(const struct mptcp_subflow_context *subflow) in mptcp_subflow_get_mapped_dsn()
579 static inline void mptcp_subflow_delegate(struct mptcp_subflow_context *subflow, int action) in mptcp_subflow_delegate()
680 static inline bool __mptcp_subflow_active(struct mptcp_subflow_context *subflow) in __mptcp_subflow_active()
787 struct mptcp_subflow_context *subflow; in __mptcp_sync_sndbuf() local
811 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(ssk); in __mptcp_propagate_sndbuf() local
824 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(ssk); in mptcp_propagate_sndbuf() local
1012 static inline u8 subflow_get_local_id(const struct mptcp_subflow_context *subflow) in subflow_get_local_id()
[all …]
|
| 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 = mptcp_subflow_ctx(ssk); in mptcp_nl_cmd_sf_destroy() local
|
| 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 static void __mptcp_pm_send_ack(struct mptcp_sock *msk, struct mptcp_subflow_context *subflow, in __mptcp_pm_send_ack()
487 static void mptcp_pm_send_ack(struct mptcp_sock *msk, struct mptcp_subflow_context *subflow, in mptcp_pm_send_ack()
539 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(msk->first); in mptcp_pm_create_subflow_or_signal_addr() local
728 struct mptcp_subflow_context *subflow; in mptcp_pm_nl_addr_send_ack() local
747 struct mptcp_subflow_context *subflow; in mptcp_pm_nl_mp_prio_send_ack() local
781 struct mptcp_subflow_context *subflow, *tmp; in mptcp_pm_nl_rm_addr_or_subflow() local
1141 struct mptcp_subflow_context *iter, *subflow = mptcp_subflow_ctx(ssk); in mptcp_pm_nl_subflow_chk_stale() local
[all …]
|
| D | token.c | 153 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(ssk); in mptcp_token_new_connect() local
|
| /kernel/linux/linux-5.10/net/mptcp/ |
| D | subflow.c | 255 static bool subflow_thmac_valid(struct mptcp_subflow_context *subflow) in subflow_thmac_valid()
275 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(ssk); in mptcp_subflow_reset() local
287 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); in subflow_finish_connect() local
365 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); in subflow_v4_conn_request() local
395 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); in subflow_v6_conn_request() local
514 void mptcp_subflow_fully_established(struct mptcp_subflow_context *subflow, in mptcp_subflow_fully_established()
683 static void dbg_bad_map(struct mptcp_subflow_context *subflow, u32 ssn) in dbg_bad_map()
691 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(ssk); in skb_is_fully_mapped() local
704 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(ssk); in validate_mapping() local
726 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(ssk); in get_mapping_status() local
[all …]
|
| 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); in mptcp_established_options_mp() local
456 static void mptcp_write_data_fin(struct mptcp_subflow_context *subflow, in mptcp_write_data_fin()
489 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); in mptcp_established_options_dss() local
584 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); in mptcp_established_options_add_addr() local
632 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); in mptcp_established_options_rm_addr() local
725 struct mptcp_subflow_context *subflow, in check_fully_established()
887 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); in mptcp_incoming_options() local
|
| D | protocol.c | 92 struct mptcp_subflow_context *subflow; in __mptcp_socket_create() local
268 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(ssk); in __mptcp_move_skb() local
415 struct mptcp_subflow_context *subflow; in mptcp_check_data_fin() local
464 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(ssk); in __mptcp_move_skbs_from_subflow() local
625 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(ssk); in mptcp_data_ready() local
708 struct mptcp_subflow_context *subflow; in mptcp_check_for_eof() local
739 struct mptcp_subflow_context *subflow; in mptcp_subflow_recv_lookup() local
794 struct mptcp_subflow_context *subflow; in mptcp_is_writeable() local
1049 struct mptcp_subflow_context *subflow; in mptcp_nospace() local
1064 static bool mptcp_subflow_active(struct mptcp_subflow_context *subflow) in mptcp_subflow_active()
[all …]
|
| 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()
351 mptcp_subflow_get_map_offset(const struct mptcp_subflow_context *subflow) in mptcp_subflow_get_map_offset()
359 mptcp_subflow_get_mapped_dsn(const struct mptcp_subflow_context *subflow) in mptcp_subflow_get_mapped_dsn()
513 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); in mptcp_check_fallback() local
530 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); in mptcp_do_fallback() local
540 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); in subflow_simultaneous_connect() local
|
| 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, *tmp; in mptcp_pm_nl_rm_subflow_received() local
|
| D | pm.c | 121 struct mptcp_subflow_context *subflow) in mptcp_pm_subflow_established()
|
| D | token.c | 154 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); in mptcp_token_new_connect() local
|