include/linux/btf_ids.h

249

BTF_SOCK_TYPE(BTF_SOCK_TYPE_SOCK_COMMON, sock_common) \

include/net/inet_timewait_sock.h

38

struct sock_common __tw_common;

include/net/request_sock.h

51

struct sock_common __req_common;

include/net/sock.h

370

struct sock_common __sk_common;

net/core/filter.c

10084

BUILD_BUG_ON(sizeof_field(struct sock_common, skc_family) != 2);

net/core/filter.c

10090

bpf_target_off(struct sock_common,

net/core/filter.c

10095

BUILD_BUG_ON(sizeof_field(struct sock_common, skc_daddr) != 4);

net/core/filter.c

10101

bpf_target_off(struct sock_common,

net/core/filter.c

10106

BUILD_BUG_ON(sizeof_field(struct sock_common,

net/core/filter.c

10113

bpf_target_off(struct sock_common,

net/core/filter.c

10120

BUILD_BUG_ON(sizeof_field(struct sock_common,

net/core/filter.c

10130

offsetof(struct sock_common,

net/core/filter.c

10140

BUILD_BUG_ON(sizeof_field(struct sock_common,

net/core/filter.c

10150

offsetof(struct sock_common,

net/core/filter.c

10159

BUILD_BUG_ON(sizeof_field(struct sock_common, skc_dport) != 2);

net/core/filter.c

10165

bpf_target_off(struct sock_common,

net/core/filter.c

10174

BUILD_BUG_ON(sizeof_field(struct sock_common, skc_num) != 2);

net/core/filter.c

10180

bpf_target_off(struct sock_common,

net/core/filter.c

10289

BPF_FIELD_SIZEOF(struct sock_common, skc_family),

net/core/filter.c

10291

bpf_target_off(struct sock_common,

net/core/filter.c

10293

sizeof_field(struct sock_common,

net/core/filter.c

10319

bpf_target_off(struct sock_common, skc_rcv_saddr,

net/core/filter.c

10320

sizeof_field(struct sock_common,

net/core/filter.c

10328

bpf_target_off(struct sock_common, skc_daddr,

net/core/filter.c

10329

sizeof_field(struct sock_common,

net/core/filter.c

10341

struct sock_common,

net/core/filter.c

10343

sizeof_field(struct sock_common,

net/core/filter.c

10358

bpf_target_off(struct sock_common,

net/core/filter.c

10360

sizeof_field(struct sock_common,

net/core/filter.c

10371

BPF_FIELD_SIZEOF(struct sock_common, skc_num),

net/core/filter.c

10373

bpf_target_off(struct sock_common, skc_num,

net/core/filter.c

10374

sizeof_field(struct sock_common,

net/core/filter.c

10381

BPF_FIELD_SIZEOF(struct sock_common, skc_dport),

net/core/filter.c

10383

bpf_target_off(struct sock_common, skc_dport,

net/core/filter.c

10384

sizeof_field(struct sock_common,

net/core/filter.c

10391

BPF_FIELD_SIZEOF(struct sock_common, skc_state),

net/core/filter.c

10393

bpf_target_off(struct sock_common, skc_state,

net/core/filter.c

10394

sizeof_field(struct sock_common,

net/core/filter.c

10827

BUILD_BUG_ON(sizeof_field(struct sock_common, skc_family) != 2);

net/core/filter.c

10834

offsetof(struct sock_common, skc_family));

net/core/filter.c

10838

BUILD_BUG_ON(sizeof_field(struct sock_common, skc_daddr) != 4);

net/core/filter.c

10845

offsetof(struct sock_common, skc_daddr));

net/core/filter.c

10849

BUILD_BUG_ON(sizeof_field(struct sock_common,

net/core/filter.c

10857

offsetof(struct sock_common,

net/core/filter.c

10864

BUILD_BUG_ON(sizeof_field(struct sock_common,

net/core/filter.c

10874

offsetof(struct sock_common,

net/core/filter.c

10885

BUILD_BUG_ON(sizeof_field(struct sock_common,

net/core/filter.c

10895

offsetof(struct sock_common,

net/core/filter.c

10904

BUILD_BUG_ON(sizeof_field(struct sock_common, skc_dport) != 2);

net/core/filter.c

10911

offsetof(struct sock_common, skc_dport));

net/core/filter.c

10918

BUILD_BUG_ON(sizeof_field(struct sock_common, skc_num) != 2);

net/core/filter.c

10925

offsetof(struct sock_common, skc_num));

net/core/filter.c

10938

BUILD_BUG_ON(sizeof_field(struct sock_common, skc_state) != 1);

net/core/filter.c

10945

offsetof(struct sock_common, skc_state));

net/core/filter.c

11217

BUILD_BUG_ON(sizeof_field(struct sock_common, skc_family) != 2);

net/core/filter.c

11224

offsetof(struct sock_common, skc_family));

net/core/filter.c

11228

BUILD_BUG_ON(sizeof_field(struct sock_common, skc_daddr) != 4);

net/core/filter.c

11235

offsetof(struct sock_common, skc_daddr));

net/core/filter.c

11239

BUILD_BUG_ON(sizeof_field(struct sock_common,

net/core/filter.c

11247

offsetof(struct sock_common,

net/core/filter.c

11254

BUILD_BUG_ON(sizeof_field(struct sock_common,

net/core/filter.c

11264

offsetof(struct sock_common,

net/core/filter.c

11275

BUILD_BUG_ON(sizeof_field(struct sock_common,

net/core/filter.c

11285

offsetof(struct sock_common,

net/core/filter.c

11294

BUILD_BUG_ON(sizeof_field(struct sock_common, skc_dport) != 2);

net/core/filter.c

11301

offsetof(struct sock_common, skc_dport));

net/core/filter.c

11308

BUILD_BUG_ON(sizeof_field(struct sock_common, skc_num) != 2);

net/core/filter.c

11315

offsetof(struct sock_common, skc_num));

net/core/filter.c

12669

__bpf_kfunc int bpf_sock_destroy(struct sock_common *sock)

net/ipv4/tcp_ipv4.c

2896

__bpf_md_ptr(struct sock_common *, sk_common);

net/ipv4/tcp_ipv4.c

2901

struct sock_common *sk_common, uid_t uid)

net/ipv4/tcp_ipv4.c

3574

struct sock_common *sk_common, uid_t uid)

net/mptcp/pm.c

1027

int mptcp_pm_get_local_id(struct mptcp_sock *msk, struct sock_common *skc)

net/mptcp/pm.c

1038

mptcp_local_address((struct sock_common *)msk, &msk_local);

net/mptcp/pm.c

1039

mptcp_local_address((struct sock_common *)skc, &skc_local.addr);

net/mptcp/pm.c

1051

bool mptcp_pm_is_backup(struct mptcp_sock *msk, struct sock_common *skc)

net/mptcp/pm.c

1055

mptcp_local_address((struct sock_common *)skc, &skc_local);

net/mptcp/pm.c

114

mptcp_remote_address((struct sock_common *)msk, &mpc_remote);

net/mptcp/pm.c

123

struct sock_common *skc;

net/mptcp/pm.c

126

skc = (struct sock_common *)mptcp_subflow_tcp_sock(subflow);

net/mptcp/pm.c

205

mptcp_local_address((struct sock_common *)ssk, &saddr);

net/mptcp/pm.c

325

mptcp_local_address((struct sock_common *)ssk, &local);

net/mptcp/pm.c

330

mptcp_remote_address((struct sock_common *)ssk, &remote);

net/mptcp/pm.c

83

void mptcp_local_address(const struct sock_common *skc,

net/mptcp/pm.c

96

void mptcp_remote_address(const struct sock_common *skc,

net/mptcp/pm_kernel.c

112

mptcp_remote_address((struct sock_common *)ssk, &cur);

net/mptcp/pm_kernel.c

1144

mptcp_local_address((struct sock_common *)msk, &msk_local);

net/mptcp/pm_kernel.c

191

mptcp_remote_address((struct sock_common *)sk, &remote);

net/mptcp/pm_kernel.c

225

mptcp_remote_address((struct sock_common *)ssk, &addrs[i]);

net/mptcp/pm_kernel.c

316

mptcp_local_address((struct sock_common *)msk->first, &mpc_addr);

net/mptcp/pm_kernel.c

976

mptcp_local_address((struct sock_common *)msk, &mpc_addr);

net/mptcp/protocol.h

1211

int mptcp_pm_get_local_id(struct mptcp_sock *msk, struct sock_common *skc);

net/mptcp/protocol.h

1216

bool mptcp_pm_is_backup(struct mptcp_sock *msk, struct sock_common *skc);

net/mptcp/protocol.h

831

void mptcp_local_address(const struct sock_common *skc,

net/mptcp/protocol.h

833

void mptcp_remote_address(const struct sock_common *skc,

net/mptcp/subflow.c

103

subflow_req->request_bkup = mptcp_pm_is_backup(msk, (struct sock_common *)req);

net/mptcp/subflow.c

639

err = mptcp_pm_get_local_id(msk, (struct sock_common *)sk);

net/mptcp/subflow.c

644

subflow->request_bkup = mptcp_pm_is_backup(msk, (struct sock_common *)sk);

net/mptcp/subflow.c

97

local_id = mptcp_pm_get_local_id(msk, (struct sock_common *)req);

tools/include/linux/btf_ids.h

184

BTF_SOCK_TYPE(BTF_SOCK_TYPE_SOCK_COMMON, sock_common) \

tools/testing/selftests/bpf/progs/bpf_iter_bpf_sk_storage_helpers.c

52

struct sock_common *sk_common = ctx->sk_common;

tools/testing/selftests/bpf/progs/bpf_iter_setsockopt.c

9

struct sock_common *_skc = skc; \

tools/testing/selftests/bpf/progs/bpf_iter_tcp4.c

198

struct sock_common *sk_common = ctx->sk_common;

tools/testing/selftests/bpf/progs/bpf_iter_tcp6.c

214

struct sock_common *sk_common = ctx->sk_common;

tools/testing/selftests/bpf/progs/sock_destroy_prog.c

11

int bpf_sock_destroy(struct sock_common *sk) __ksym;

tools/testing/selftests/bpf/progs/sock_destroy_prog.c

121

bpf_sock_destroy((struct sock_common *)sk);

tools/testing/selftests/bpf/progs/sock_destroy_prog.c

140

bpf_sock_destroy((struct sock_common *)sk);

tools/testing/selftests/bpf/progs/sock_destroy_prog.c

51

struct sock_common *sk_common = ctx->sk_common;

tools/testing/selftests/bpf/progs/sock_destroy_prog.c

76

struct sock_common *sk_common = ctx->sk_common;

tools/testing/selftests/bpf/progs/sock_destroy_prog_fail.c

11

int bpf_sock_destroy(struct sock_common *sk) __ksym;

tools/testing/selftests/bpf/progs/sock_destroy_prog_fail.c

18

bpf_sock_destroy((struct sock_common *)sk);

tools/testing/selftests/bpf/progs/sock_iter_batch.c

78

struct sock_common *sk_common = (struct sock_common *)ctx->sk_common;

tools/testing/selftests/bpf/progs/test_tcp_estats.c

75

struct sock_common __sk_common;

tools/testing/selftests/bpf/test_kmods/bpf_testmod.c

223

__bpf_kfunc struct sk_buff *bpf_kfunc_nested_acquire_zero_offset_test(struct sock_common *ptr)

tools/testing/selftests/bpf/test_kmods/bpf_testmod_kfunc.h

183

struct sk_buff *bpf_kfunc_nested_acquire_zero_offset_test(struct sock_common *ptr) __ksym;