Home
last modified time | relevance | path

Searched refs:lsk (Results 1 – 24 of 24) sorted by relevance

/linux/tools/testing/selftests/net/tcp_ao/
A Dbench-lookups.c163 measure_call(del, delete_mkt, lsk, (void *)&ao_del); in bench_delete()
166 measure_call(add, add_back_mkt, lsk, (void *)p); in bench_delete()
191 if (test_wait_fd(lsk, TEST_TIMEOUT_SEC, 0)) in bench_connect_srv()
194 sk = accept(lsk, NULL, NULL); in bench_connect_srv()
215 int lsk; in server_fn() local
226 server_apply_keys(lsk, test_ips, nr_keys[i]); in server_fn()
229 bench_connect_srv(lsk, test_ips, nr_keys[i]); in server_fn()
230 bench_connect_srv(lsk, test_ips, nr_keys[i]); in server_fn()
233 bench_delete(lsk, &bt->add_key, &bt->delete_last_key, in server_fn()
245 bench_delete(lsk, &bt->add_key, &bt->delete_async, in server_fn()
[all …]
A Drst.c89 int sk, lsk; in test_server_active_rst() local
94 if (test_get_tcp_ao_counters(lsk, &cnt1)) in test_server_active_rst()
98 if (test_wait_fd(lsk, TEST_TIMEOUT_SEC, 0)) in test_server_active_rst()
101 sk = accept(lsk, NULL, NULL); in test_server_active_rst()
106 if (test_get_tcp_ao_counters(lsk, &cnt2)) in test_server_active_rst()
110 close(lsk); in test_server_active_rst()
132 int sk, lsk; in test_server_passive_rst() local
135 lsk = test_listen_socket(this_ip_addr, port, 1); in test_server_passive_rst()
141 if (test_wait_fd(lsk, TEST_TIMEOUT_SEC, 0)) in test_server_passive_rst()
144 sk = accept(lsk, NULL, NULL); in test_server_passive_rst()
[all …]
A Dconnect.c8 int sk, lsk; in server_fn() local
11 lsk = test_listen_socket(this_ip_addr, test_server_port, 1); in server_fn()
13 if (test_add_key(lsk, DEFAULT_TEST_PASSWORD, this_ip_dest, -1, 100, 100)) in server_fn()
17 if (test_wait_fd(lsk, TEST_TIMEOUT_SEC, 0)) in server_fn()
20 sk = accept(lsk, NULL, NULL); in server_fn()
A Dconnect-deny.c39 int lsk, err, sk = 0; in try_accept() local
42 lsk = test_listen_socket(this_ip_addr, port, 1); in try_accept()
44 if (pwd && test_add_key_maclen(lsk, pwd, maclen, addr, prefix, sndid, rcvid)) in try_accept()
49 if (pwd && test_get_tcp_ao_counters(lsk, &ao_cnt1)) in try_accept()
55 err = test_wait_fd(lsk, timeout, 0); in try_accept()
65 sk = accept(lsk, NULL, NULL); in try_accept()
75 if (pwd && test_get_tcp_ao_counters(lsk, &ao_cnt2)) in try_accept()
78 close(lsk); in try_accept()
A Dseq-ext.c73 int sk, lsk; in server_fn() local
75 lsk = test_listen_socket(this_ip_addr, test_server_port, 1); in server_fn()
77 if (test_add_key(lsk, DEFAULT_TEST_PASSWORD, this_ip_dest, -1, 100, 100)) in server_fn()
82 if (test_wait_fd(lsk, TEST_TIMEOUT_SEC, 0)) in server_fn()
85 sk = accept(lsk, NULL, NULL); in server_fn()
90 close(lsk); in server_fn()
A Drestore.c22 int sk, lsk; in try_server_run() local
28 lsk = test_listen_socket(this_ip_addr, port, 1); in try_server_run()
30 if (test_add_key(lsk, DEFAULT_TEST_PASSWORD, this_ip_dest, -1, 100, 100)) in try_server_run()
34 if (test_wait_fd(lsk, TEST_TIMEOUT_SEC, 0)) in try_server_run()
37 sk = accept(lsk, NULL, NULL); in try_server_run()
42 close(lsk); in try_server_run()
A Dunsigned-md5.c46 int lsk, err, sk = 0; in try_accept() local
52 lsk = test_listen_socket(this_ip_addr, port, 1); in try_accept()
54 if (md5_addr && test_set_md5(lsk, *md5_addr, md5_prefix, -1, md5_password)) in try_accept()
57 if (ao_addr && test_add_key(lsk, ao_password, in try_accept()
61 if (set_ao_required && test_set_ao_flags(lsk, true, false)) in try_accept()
66 if (ao_addr && test_get_tcp_ao_counters(lsk, &ao_cnt1)) in try_accept()
72 err = test_wait_fd(lsk, timeout, 0); in try_accept()
83 sk = accept(lsk, NULL, NULL); in try_accept()
92 if (ao_addr && test_get_tcp_ao_counters(lsk, &ao_cnt2)) in try_accept()
94 close(lsk); in try_accept()
A Dicmps-accept.c108 int val, sk, lsk; in server_fn() local
111 lsk = test_listen_socket(this_ip_addr, test_server_port, 1); in server_fn()
117 if (test_set_ao_flags(lsk, false, accept_icmps)) in server_fn()
120 if (test_add_key(lsk, DEFAULT_TEST_PASSWORD, this_ip_dest, -1, 100, 100)) in server_fn()
124 if (test_wait_fd(lsk, TEST_TIMEOUT_SEC, 0)) in server_fn()
127 sk = accept(lsk, NULL, NULL); in server_fn()
A Dicmps-discard.c108 int val, sk, lsk; in server_fn() local
111 lsk = test_listen_socket(this_ip_addr, test_server_port, 1); in server_fn()
117 if (test_set_ao_flags(lsk, false, accept_icmps)) in server_fn()
120 if (test_add_key(lsk, DEFAULT_TEST_PASSWORD, this_ip_dest, -1, 100, 100)) in server_fn()
124 if (test_wait_fd(lsk, TEST_TIMEOUT_SEC, 0)) in server_fn()
127 sk = accept(lsk, NULL, NULL); in server_fn()
A Dkey-management.c799 int sk, lsk; in start_server() local
802 lsk = key_collection_socket(true, port); in start_server()
803 if (test_get_tcp_ao_counters(lsk, &lsk_c1)) in start_server()
806 if (test_wait_fd(lsk, TEST_TIMEOUT_SEC, 0)) in start_server()
809 sk = accept(lsk, NULL, NULL); in start_server()
816 if (test_get_tcp_ao_counters(lsk, &lsk_c2)) in start_server()
818 verify_keys(tst_name, lsk, true, true); in start_server()
819 close(lsk); in start_server()
/linux/tools/testing/selftests/net/
A Dsctp_hello.c77 int lsk, csk, ret, len; in main() local
94 lsk = socket(ss.ss_family, SOCK_STREAM, IPPROTO_SCTP); in main()
95 if (lsk < 0) { in main()
101 ret = setsockopt(lsk, SOL_SOCKET, SO_BINDTODEVICE, in main()
110 ret = bind(lsk, (struct sockaddr *)&ss, len); in main()
116 ret = listen(lsk, 5); in main()
122 csk = accept(lsk, (struct sockaddr *)NULL, (socklen_t *)NULL); in main()
134 close(lsk); in main()
/linux/drivers/net/ethernet/chelsio/inline_crypto/chtls/
A Dchtls_cm.c674 ctx->lsk = sk; in chtls_listen_start()
1153 dst = ip6_dst_lookup_flow(sock_net(lsk), lsk, &fl6, NULL); in chtls_recv_sock()
1432 struct sock *lsk; in chtls_pass_accept_req() local
1443 lsk = ctx->lsk; in chtls_pass_accept_req()
1558 lsk->sk_data_ready(lsk); in add_pass_open_to_parent()
1575 struct sock *lsk, *sk; in chtls_pass_establish() local
1606 lsk = ((struct listen_ctx *)data)->lsk; in chtls_pass_establish()
1608 bh_lock_sock(lsk); in chtls_pass_establish()
1611 bh_unlock_sock(lsk); in chtls_pass_establish()
1626 bh_unlock_sock(lsk); in chtls_pass_establish()
[all …]
A Dchtls.h191 struct sock *lsk; member
/linux/net/core/
A Drequest_sock.c91 struct sock *lsk = req->rsk_listener; in reqsk_fastopen_remove() local
94 fastopenq = &inet_csk(lsk)->icsk_accept_queue.fastopenq; in reqsk_fastopen_remove()
103 if (!reset || lsk->sk_state != TCP_LISTEN) { in reqsk_fastopen_remove()
/linux/net/mptcp/
A Dmptcp_diag.c209 struct sock *lsk = READ_ONCE(msk->first); in mptcp_diag_get_info() local
211 if (lsk) { in mptcp_diag_get_info()
215 r->idiag_rqueue = READ_ONCE(lsk->sk_ack_backlog); in mptcp_diag_get_info()
216 r->idiag_wqueue = READ_ONCE(lsk->sk_max_ack_backlog); in mptcp_diag_get_info()
A Dpm_netlink.c964 if (entry->lsk) in __mptcp_pm_release_addr_entry()
965 sock_release(entry->lsk); in __mptcp_pm_release_addr_entry()
1078 SOCK_STREAM, IPPROTO_MPTCP, &entry->lsk); in mptcp_pm_nl_create_listen_socket()
1082 newsk = entry->lsk->sk; in mptcp_pm_nl_create_listen_socket()
1162 entry->lsk = NULL; in mptcp_pm_nl_get_local_id()
A Dprotocol.h250 struct socket *lsk; member
/linux/net/nfc/
A Dllcp_sock.c411 struct nfc_llcp_sock *lsk, *n, *llcp_parent; in nfc_llcp_accept_dequeue() local
416 list_for_each_entry_safe(lsk, n, &llcp_parent->accept_queue, in nfc_llcp_accept_dequeue()
418 sk = &lsk->sk; in nfc_llcp_accept_dequeue()
428 list_del_init(&lsk->accept_queue); in nfc_llcp_accept_dequeue()
619 struct nfc_llcp_sock *lsk, *n; in llcp_sock_release() local
622 list_for_each_entry_safe(lsk, n, &llcp_sock->accept_queue, in llcp_sock_release()
624 accept_sk = &lsk->sk; in llcp_sock_release()
627 nfc_llcp_send_disconnect(lsk); in llcp_sock_release()
A Dllcp_core.c88 struct nfc_llcp_sock *lsk, *n; in nfc_llcp_socket_release() local
91 list_for_each_entry_safe(lsk, n, in nfc_llcp_socket_release()
94 accept_sk = &lsk->sk; in nfc_llcp_socket_release()
/linux/net/l2tp/
A Dl2tp_ip6.c452 struct l2tp_ip6_sock *lsk = l2tp_ip6_sk(sk); in l2tp_ip6_getname() local
459 if (!lsk->peer_conn_id) in l2tp_ip6_getname()
461 lsa->l2tp_conn_id = lsk->peer_conn_id; in l2tp_ip6_getname()
471 lsa->l2tp_conn_id = lsk->conn_id; in l2tp_ip6_getname()
A Dl2tp_ip.c381 struct l2tp_ip_sock *lsk = l2tp_ip_sk(sk); in l2tp_ip_getname() local
389 lsa->l2tp_conn_id = lsk->peer_conn_id; in l2tp_ip_getname()
396 lsa->l2tp_conn_id = lsk->conn_id; in l2tp_ip_getname()
/linux/net/smc/
A Daf_smc.c1711 struct sock *lsk = &lsmc->sk; in smc_clcsock_accept() local
1715 release_sock(lsk); in smc_clcsock_accept()
1716 new_sk = smc_sock_alloc(sock_net(lsk), NULL, lsk->sk_protocol); in smc_clcsock_accept()
1719 lsk->sk_err = ENOMEM; in smc_clcsock_accept()
1721 lock_sock(lsk); in smc_clcsock_accept()
1730 lock_sock(lsk); in smc_clcsock_accept()
1732 lsk->sk_err = -rc; in smc_clcsock_accept()
2560 struct sock *lsk = &lsmc->sk; in smc_tcp_listen_work() local
2564 lock_sock(lsk); in smc_tcp_listen_work()
2565 while (lsk->sk_state == SMC_LISTEN) { in smc_tcp_listen_work()
[all …]
/linux/include/uapi/linux/
A Dcdrom.h711 struct dvd_send_key lsk; member
/linux/drivers/cdrom/
A Dcdrom.c1642 setup_report_key(&cgc, ai->lsk.agid, 2); in dvd_do_auth()
1647 copy_key(ai->lsk.key, &buf[4]); in dvd_do_auth()

Completed in 60 milliseconds