Home
last modified time | relevance | path

Searched refs:sock_common (Results 1 – 20 of 20) sorted by relevance

/linux-6.15/tools/testing/selftests/bpf/progs/
H A Dsock_destroy_prog.c11 int bpf_sock_destroy(struct sock_common *sk) __ksym;
51 struct sock_common *sk_common = ctx->sk_common; in iter_tcp6_client()
76 struct sock_common *sk_common = ctx->sk_common; in iter_tcp6_server()
121 bpf_sock_destroy((struct sock_common *)sk); in iter_udp6_client()
140 bpf_sock_destroy((struct sock_common *)sk); in iter_udp6_server()
H A Dsock_destroy_prog_fail.c11 int bpf_sock_destroy(struct sock_common *sk) __ksym;
18 bpf_sock_destroy((struct sock_common *)sk); in BPF_PROG()
H A Dtest_tcp_estats.c54 struct sock_common { struct
75 struct sock_common __sk_common; argument
H A Dbpf_iter_bpf_sk_storage_helpers.c52 struct sock_common *sk_common = ctx->sk_common; in negate_socket_local_storage()
H A Dbpf_iter_setsockopt.c9 struct sock_common *_skc = skc; \
H A Dbpf_iter_tcp4.c198 struct sock_common *sk_common = ctx->sk_common; in dump_tcp4()
H A Dbpf_iter_tcp6.c214 struct sock_common *sk_common = ctx->sk_common; in dump_tcp6()
/linux-6.15/net/mptcp/
H A Dpm.c81 void mptcp_local_address(const struct sock_common *skc, in mptcp_local_address()
94 void mptcp_remote_address(const struct sock_common *skc, in mptcp_remote_address()
112 mptcp_remote_address((struct sock_common *)msk, &mpc_remote); in mptcp_pm_is_init_remote_addr()
121 struct sock_common *skc; in mptcp_lookup_subflow_by_saddr()
124 skc = (struct sock_common *)mptcp_subflow_tcp_sock(subflow); in mptcp_lookup_subflow_by_saddr()
166 mptcp_local_address((struct sock_common *)sk, &saddr); in mptcp_pm_sport_in_anno_list()
251 mptcp_local_address((struct sock_common *)ssk, &local); in mptcp_pm_mp_prio_send_ack()
256 mptcp_remote_address((struct sock_common *)ssk, &remote); in mptcp_pm_mp_prio_send_ack()
867 mptcp_local_address((struct sock_common *)msk, &msk_local); in mptcp_pm_get_local_id()
868 mptcp_local_address((struct sock_common *)skc, &skc_local.addr); in mptcp_pm_get_local_id()
[all …]
H A Dpm_kernel.c94 mptcp_remote_address((struct sock_common *)ssk, &cur); in lookup_subflow_by_daddr()
178 mptcp_remote_address((struct sock_common *)sk, &remote); in fill_remote_addresses_vec()
205 mptcp_remote_address((struct sock_common *)ssk, &addrs[i]); in fill_remote_addresses_vec()
279 mptcp_local_address((struct sock_common *)msk->first, &mpc_addr); in mptcp_pm_create_subflow_or_signal_addr()
397 mptcp_local_address((struct sock_common *)msk, &mpc_addr); in fill_local_addresses_vec()
754 mptcp_local_address((struct sock_common *)msk, &mpc_addr); in mptcp_nl_add_subflow_or_signal_addr()
947 mptcp_local_address((struct sock_common *)msk, &msk_local); in mptcp_nl_remove_id_zero_address()
H A Dprotocol.h733 void mptcp_local_address(const struct sock_common *skc,
735 void mptcp_remote_address(const struct sock_common *skc,
1139 int mptcp_pm_get_local_id(struct mptcp_sock *msk, struct sock_common *skc);
1144 bool mptcp_pm_is_backup(struct mptcp_sock *msk, struct sock_common *skc);
H A Dsubflow.c97 local_id = mptcp_pm_get_local_id(msk, (struct sock_common *)req); in subflow_token_join_request()
103 subflow_req->request_bkup = mptcp_pm_is_backup(msk, (struct sock_common *)req); in subflow_token_join_request()
634 err = mptcp_pm_get_local_id(msk, (struct sock_common *)sk); in subflow_chk_local_id()
639 subflow->request_bkup = mptcp_pm_is_backup(msk, (struct sock_common *)sk); in subflow_chk_local_id()
/linux-6.15/net/core/
H A Dfilter.c9879 offsetof(struct sock_common, in bpf_convert_ctx_access()
9899 offsetof(struct sock_common, in bpf_convert_ctx_access()
10040 bpf_target_off(struct sock_common, in bpf_sock_convert_ctx_access()
10090 struct sock_common, in bpf_sock_convert_ctx_access()
10092 sizeof_field(struct sock_common, in bpf_sock_convert_ctx_access()
10107 bpf_target_off(struct sock_common, in bpf_sock_convert_ctx_access()
10604 offsetof(struct sock_common, in sock_ops_convert_ctx_access()
10621 offsetof(struct sock_common, in sock_ops_convert_ctx_access()
10642 offsetof(struct sock_common, in sock_ops_convert_ctx_access()
10994 offsetof(struct sock_common, in sk_msg_convert_ctx_access()
[all …]
/linux-6.15/include/net/
H A Dinet_timewait_sock.h38 struct sock_common __tw_common;
H A Drequest_sock.h56 struct sock_common __req_common;
H A Dsock.h150 struct sock_common { struct
350 struct sock_common __sk_common;
/linux-6.15/tools/include/linux/
H A Dbtf_ids.h184 BTF_SOCK_TYPE(BTF_SOCK_TYPE_SOCK_COMMON, sock_common) \
/linux-6.15/tools/testing/selftests/bpf/test_kmods/
H A Dbpf_testmod_kfunc.h148 struct sk_buff *bpf_kfunc_nested_acquire_zero_offset_test(struct sock_common *ptr) __ksym;
H A Dbpf_testmod.c192 __bpf_kfunc struct sk_buff *bpf_kfunc_nested_acquire_zero_offset_test(struct sock_common *ptr) in bpf_kfunc_nested_acquire_zero_offset_test()
/linux-6.15/include/linux/
H A Dbtf_ids.h249 BTF_SOCK_TYPE(BTF_SOCK_TYPE_SOCK_COMMON, sock_common) \
/linux-6.15/net/ipv4/
H A Dtcp_ipv4.c3027 __bpf_md_ptr(struct sock_common *, sk_common);
3032 struct sock_common *sk_common, uid_t uid)
3585 struct sock_common *sk_common, uid_t uid)