Home
last modified time | relevance | path

Searched refs:nc (Results 1 – 25 of 215) sorted by relevance

123456789

/freebsd/contrib/llvm-project/clang/include/clang/Basic/
H A DBuiltinsMips.def29 BUILTIN(__builtin_mips_madd, "LLiLLiii", "nc")
31 BUILTIN(__builtin_mips_msub, "LLiLLiii", "nc")
40 BUILTIN(__builtin_mips_modsub, "iii", "nc")
69 BUILTIN(__builtin_mips_shra_r_w, "iii", "nc")
82 BUILTIN(__builtin_mips_mult, "LLiii", "nc")
114 BUILTIN(__builtin_mips_bitrev, "ii", "nc")
132 BUILTIN(__builtin_mips_addqh_w, "iii", "nc")
302 BUILTIN(__builtin_msa_bnz_h, "iV8Us", "nc")
303 BUILTIN(__builtin_msa_bnz_w, "iV4Ui", "nc")
323 BUILTIN(__builtin_msa_bz_h, "iV8Us", "nc")
[all …]
H A DBuiltinsLoongArchLASX.def15 TARGET_BUILTIN(__builtin_lasx_xvadd_b, "V32cV32cV32c", "nc", "lasx")
16 TARGET_BUILTIN(__builtin_lasx_xvadd_h, "V16sV16sV16s", "nc", "lasx")
17 TARGET_BUILTIN(__builtin_lasx_xvadd_w, "V8iV8iV8i", "nc", "lasx")
21 TARGET_BUILTIN(__builtin_lasx_xvsub_b, "V32cV32cV32c", "nc", "lasx")
22 TARGET_BUILTIN(__builtin_lasx_xvsub_h, "V16sV16sV16s", "nc", "lasx")
23 TARGET_BUILTIN(__builtin_lasx_xvsub_w, "V8iV8iV8i", "nc", "lasx")
29 TARGET_BUILTIN(__builtin_lasx_xvaddi_wu, "V8iV8iIUi", "nc", "lasx")
37 TARGET_BUILTIN(__builtin_lasx_xvneg_b, "V32cV32c", "nc", "lasx")
38 TARGET_BUILTIN(__builtin_lasx_xvneg_h, "V16sV16s", "nc", "lasx")
39 TARGET_BUILTIN(__builtin_lasx_xvneg_w, "V8iV8i", "nc", "lasx")
[all …]
H A DBuiltinsLoongArchLSX.def15 TARGET_BUILTIN(__builtin_lsx_vadd_b, "V16cV16cV16c", "nc", "lsx")
16 TARGET_BUILTIN(__builtin_lsx_vadd_h, "V8sV8sV8s", "nc", "lsx")
17 TARGET_BUILTIN(__builtin_lsx_vadd_w, "V4iV4iV4i", "nc", "lsx")
21 TARGET_BUILTIN(__builtin_lsx_vsub_b, "V16cV16cV16c", "nc", "lsx")
22 TARGET_BUILTIN(__builtin_lsx_vsub_h, "V8sV8sV8s", "nc", "lsx")
23 TARGET_BUILTIN(__builtin_lsx_vsub_w, "V4iV4iV4i", "nc", "lsx")
37 TARGET_BUILTIN(__builtin_lsx_vneg_b, "V16cV16c", "nc", "lsx")
38 TARGET_BUILTIN(__builtin_lsx_vneg_h, "V8sV8s", "nc", "lsx")
39 TARGET_BUILTIN(__builtin_lsx_vneg_w, "V4iV4i", "nc", "lsx")
952 TARGET_BUILTIN(__builtin_lsx_bz_h, "iV8Us", "nc", "lsx")
[all …]
H A DBuiltinsSystemZ.def35 TARGET_BUILTIN(__builtin_s390_lcbb, "UivC*Ii", "nc", "vector")
53 TARGET_BUILTIN(__builtin_s390_vuphb, "V8SsV16Sc", "nc", "vector")
54 TARGET_BUILTIN(__builtin_s390_vuphh, "V4SiV8Ss", "nc", "vector")
56 TARGET_BUILTIN(__builtin_s390_vuplb, "V8SsV16Sc", "nc", "vector")
57 TARGET_BUILTIN(__builtin_s390_vuplhw, "V4SiV8Ss", "nc", "vector")
60 TARGET_BUILTIN(__builtin_s390_vuplhh, "V4UiV8Us", "nc", "vector")
63 TARGET_BUILTIN(__builtin_s390_vupllh, "V4UiV8Us", "nc", "vector")
97 TARGET_BUILTIN(__builtin_s390_vclzh, "V8UsV8Us", "nc", "vector")
98 TARGET_BUILTIN(__builtin_s390_vclzf, "V4UiV4Ui", "nc", "vector")
101 TARGET_BUILTIN(__builtin_s390_vctzh, "V8UsV8Us", "nc", "vector")
[all …]
H A DBuiltinsAMDGPU.def88 BUILTIN(__builtin_amdgcn_rcp, "dd", "nc")
89 BUILTIN(__builtin_amdgcn_rcpf, "ff", "nc")
90 BUILTIN(__builtin_amdgcn_sqrt, "dd", "nc")
91 BUILTIN(__builtin_amdgcn_sqrtf, "ff", "nc")
92 BUILTIN(__builtin_amdgcn_rsq, "dd", "nc")
93 BUILTIN(__builtin_amdgcn_rsqf, "ff", "nc")
96 BUILTIN(__builtin_amdgcn_sinf, "ff", "nc")
97 BUILTIN(__builtin_amdgcn_cosf, "ff", "nc")
98 BUILTIN(__builtin_amdgcn_logf, "ff", "nc")
99 BUILTIN(__builtin_amdgcn_exp2f, "ff", "nc")
[all …]
H A DBuiltinsWebAssembly.def34 BUILTIN(__builtin_wasm_min_f32, "fff", "nc")
35 BUILTIN(__builtin_wasm_max_f32, "fff", "nc")
36 BUILTIN(__builtin_wasm_min_f64, "ddd", "nc")
37 BUILTIN(__builtin_wasm_max_f64, "ddd", "nc")
49 BUILTIN(__builtin_wasm_trunc_s_i32_f32, "if", "nc")
50 BUILTIN(__builtin_wasm_trunc_u_i32_f32, "if", "nc")
51 BUILTIN(__builtin_wasm_trunc_s_i32_f64, "id", "nc")
52 BUILTIN(__builtin_wasm_trunc_u_i32_f64, "id", "nc")
53 BUILTIN(__builtin_wasm_trunc_s_i64_f32, "LLif", "nc")
54 BUILTIN(__builtin_wasm_trunc_u_i64_f32, "LLif", "nc")
[all …]
H A DBuiltinsLoongArchBase.def16 TARGET_BUILTIN(__builtin_loongarch_cacop_w, "viUii", "nc", "32bit")
17 TARGET_BUILTIN(__builtin_loongarch_dbar, "vIUi", "nc", "")
18 TARGET_BUILTIN(__builtin_loongarch_ibar, "vIUi", "nc", "")
19 TARGET_BUILTIN(__builtin_loongarch_movfcsr2gr, "UiIUi", "nc", "f")
21 TARGET_BUILTIN(__builtin_loongarch_break, "vIUi", "nc", "")
22 TARGET_BUILTIN(__builtin_loongarch_syscall, "vIUi", "nc", "")
23 TARGET_BUILTIN(__builtin_loongarch_cpucfg, "UiUi", "nc", "")
36 TARGET_BUILTIN(__builtin_loongarch_csrrd_w, "UiIUi", "nc", "")
43 TARGET_BUILTIN(__builtin_loongarch_iocsrrd_b, "UiUi", "nc", "")
44 TARGET_BUILTIN(__builtin_loongarch_iocsrrd_h, "UiUi", "nc", "")
[all …]
H A DBuiltinsRISCV.def19 TARGET_BUILTIN(__builtin_riscv_orc_b_32, "UiUi", "nc", "zbb")
21 TARGET_BUILTIN(__builtin_riscv_clz_32, "UiUi", "nc", "zbb|xtheadbb")
23 TARGET_BUILTIN(__builtin_riscv_ctz_32, "UiUi", "nc", "zbb")
24 TARGET_BUILTIN(__builtin_riscv_ctz_64, "UiUWi", "nc", "zbb,64bit")
41 TARGET_BUILTIN(__builtin_riscv_brev8_32, "UiUi", "nc", "zbkb")
64 TARGET_BUILTIN(__builtin_riscv_sha256sig0, "UiUi", "nc", "zknh")
65 TARGET_BUILTIN(__builtin_riscv_sha256sig1, "UiUi", "nc", "zknh")
66 TARGET_BUILTIN(__builtin_riscv_sha256sum0, "UiUi", "nc", "zknh")
67 TARGET_BUILTIN(__builtin_riscv_sha256sum1, "UiUi", "nc", "zknh")
85 TARGET_BUILTIN(__builtin_riscv_sm3p0, "UiUi", "nc", "zksh")
[all …]
H A DBuiltinsARM.def32 BUILTIN(__builtin_arm_smulbb, "iii", "nc")
33 BUILTIN(__builtin_arm_smulbt, "iii", "nc")
34 BUILTIN(__builtin_arm_smultb, "iii", "nc")
35 BUILTIN(__builtin_arm_smultt, "iii", "nc")
40 BUILTIN(__builtin_arm_qadd, "iii", "nc")
41 BUILTIN(__builtin_arm_qsub, "iii", "nc")
42 BUILTIN(__builtin_arm_qdbl, "ii", "nc")
43 BUILTIN(__builtin_arm_ssat, "iiUi", "nc")
61 BUILTIN(__builtin_arm_sel, "iii", "nc")
82 BUILTIN(__builtin_arm_qasx, "iii", "nc")
[all …]
/freebsd/sys/dev/ntb/
H A Dntb.c100 nc = malloc(sizeof(*nc), M_DEVBUF, M_WAITOK | M_ZERO); in ntb_register_device()
115 device_set_ivars(nc->dev, nc); in ntb_register_device()
116 *cpp = nc; in ntb_register_device()
186 printf("-%d", nc->mwoff + nc->mwcnt - 1); in ntb_print_child()
191 printf("-%d", nc->spadoff + nc->spadcnt - 1); in ntb_print_child()
196 printf("-%d", nc->dboff + nc->dbcnt - 1); in ntb_print_child()
227 for (nc = *cpp; nc != NULL; nc = nc->next) { in ntb_link_event()
230 nc->ctx_ops->link_event(nc->ctx); in ntb_link_event()
242 for (nc = *cpp; nc != NULL; nc = nc->next) { in ntb_db_event()
245 nc->ctx_ops->db_event(nc->ctx, vec); in ntb_db_event()
[all …]
/freebsd/lib/libnvmf/
H A Dnvmf_transport.c130 if (nc == NULL) in nvmf_allocate_command()
133 nc->nc_qpair = qp; in nvmf_allocate_command()
135 memcpy(&nc->nc_sqe, sqe, nc->nc_qe_len); in nvmf_allocate_command()
140 return (nc); in nvmf_allocate_command()
149 if (nc == NULL) in nvmf_allocate_response()
152 nc->nc_qpair = qp; in nvmf_allocate_response()
154 memcpy(&nc->nc_cqe, cqe, nc->nc_qe_len); in nvmf_allocate_response()
155 return (nc); in nvmf_allocate_response()
167 nc->nc_data = buf; in nvmf_capsule_append_data()
176 nc->nc_qpair->nq_association->na_ops->free_capsule(nc); in nvmf_free_capsule()
[all …]
H A Dnvmf_tcp.c80 #define TCAP(nc) ((struct nvmf_tcp_capsule *)(nc)) argument
81 #define CTCAP(nc) ((const struct nvmf_tcp_capsule *)(nc)) argument
377 if (nc == NULL) in nvmf_tcp_save_command_capsule()
380 tc = TCAP(nc); in nvmf_tcp_save_command_capsule()
398 if (nc == NULL) in nvmf_tcp_save_response_capsule()
402 tc = TCAP(nc); in nvmf_tcp_save_response_capsule()
1147 nc = calloc(1, sizeof(*nc)); in tcp_allocate_capsule()
1148 return (&nc->nc); in tcp_allocate_capsule()
1173 if (nc->nc_data_len != 0 && nc->nc_send_data && in tcp_transmit_command()
1196 nc->nc_data : NULL, use_icd ? nc->nc_data_len : 0); in tcp_transmit_command()
[all …]
H A Dlibnvmf.h102 void nvmf_free_capsule(struct nvmf_capsule *nc);
103 int nvmf_capsule_append_data(struct nvmf_capsule *nc,
105 int nvmf_transmit_capsule(struct nvmf_capsule *nc);
107 const void *nvmf_capsule_sqe(const struct nvmf_capsule *nc);
108 const void *nvmf_capsule_cqe(const struct nvmf_capsule *nc);
139 int nvmf_receive_controller_data(const struct nvmf_capsule *nc,
149 int nvmf_send_controller_data(const struct nvmf_capsule *nc,
157 void nvmf_init_cqe(void *cqe, const struct nvmf_capsule *nc,
184 int nvmf_send_generic_error(const struct nvmf_capsule *nc,
188 int nvmf_send_success(const struct nvmf_capsule *nc);
[all …]
H A Dnvmf_controller.c38 nvmf_init_cqe(&cpl, nc, status); in nvmf_simple_response()
46 struct nvmf_capsule *nc; in nvmf_controller_receive_capsule() local
51 error = nvmf_receive_capsule(qp, &nc); in nvmf_controller_receive_capsule()
55 sc_status = nvmf_validate_command_capsule(nc); in nvmf_controller_receive_capsule()
57 nvmf_send_generic_error(nc, sc_status); in nvmf_controller_receive_capsule()
58 nvmf_free_capsule(nc); in nvmf_controller_receive_capsule()
62 *ncp = nc; in nvmf_controller_receive_capsule()
69 struct nvmf_qpair *qp = nc->nc_qpair; in nvmf_controller_transmit_response()
74 nc->nc_cqe.sqhd = htole16(qp->nq_sqhd); in nvmf_controller_transmit_response()
76 nc->nc_cqe.sqhd = 0; in nvmf_controller_transmit_response()
[all …]
/freebsd/sys/dev/nvmf/
H A Dnvmf_transport.c102 if (nc == NULL) in nvmf_allocate_command()
105 nc->nc_qpair = qp; in nvmf_allocate_command()
107 memcpy(&nc->nc_sqe, sqe, nc->nc_qe_len); in nvmf_allocate_command()
112 return (nc); in nvmf_allocate_command()
123 if (nc == NULL) in nvmf_allocate_response()
128 memcpy(&nc->nc_cqe, cqe, nc->nc_qe_len); in nvmf_allocate_response()
129 return (nc); in nvmf_allocate_response()
151 nc->nc_qpair->nq_ops->free_capsule(nc); in nvmf_free_capsule()
157 return (nc->nc_qpair->nq_ops->transmit_capsule(nc)); in nvmf_transmit_capsule()
192 return (nc->nc_qpair->nq_ops->validate_command_capsule(nc)); in nvmf_validate_command_capsule()
[all …]
H A Dnvmf_transport.h73 void nvmf_free_capsule(struct nvmf_capsule *nc);
74 int nvmf_capsule_append_data(struct nvmf_capsule *nc,
77 int nvmf_transmit_capsule(struct nvmf_capsule *nc);
78 void nvmf_abort_capsule_data(struct nvmf_capsule *nc, int error);
79 void *nvmf_capsule_sqe(struct nvmf_capsule *nc);
80 void *nvmf_capsule_cqe(struct nvmf_capsule *nc);
90 uint8_t nvmf_validate_command_capsule(struct nvmf_capsule *nc);
108 int nvmf_receive_controller_data(struct nvmf_capsule *nc,
134 u_int nvmf_send_controller_data(struct nvmf_capsule *nc,
H A Dnvmf_transport_internal.h30 void (*free_capsule)(struct nvmf_capsule *nc);
31 int (*transmit_capsule)(struct nvmf_capsule *nc);
32 uint8_t (*validate_command_capsule)(struct nvmf_capsule *nc);
35 size_t (*capsule_data_len)(const struct nvmf_capsule *nc);
36 int (*receive_controller_data)(struct nvmf_capsule *nc,
38 u_int (*send_controller_data)(struct nvmf_capsule *nc,
105 nvmf_capsule_received(struct nvmf_qpair *nq, struct nvmf_capsule *nc) in nvmf_capsule_received() argument
107 nq->nq_receive(nq->nq_receive_arg, nc); in nvmf_capsule_received()
/freebsd/usr.sbin/nvmfd/
H A Dio.c242 nvmf_send_success(nc); in handle_set_features()
273 nvmf_send_success(nc); in admin_command()
325 nvmf_send_success(nc); in handle_io_fabrics_command()
445 nvmf_free_capsule(nc); in handle_io_commands()
517 nvmf_free_capsule(nc); in connect_admin_qpair()
524 nvmf_free_capsule(nc); in connect_admin_qpair()
600 nvmf_free_capsule(nc); in connect_io_qpair()
606 nvmf_free_capsule(nc); in connect_io_qpair()
626 nc = NULL; in io_socket_thread()
657 if (nc != NULL) in io_socket_thread()
[all …]
H A Dcontroller.c66 nvmf_init_cqe(&rsp, nc, 0); in handle_property_get()
93 nvmf_send_response(nc, &rsp); in handle_property_get()
114 nvmf_send_success(nc); in handle_property_set()
126 handle_property_get(c, nc, in handle_fabrics_command()
130 handle_property_set(c, nc, in handle_fabrics_command()
176 struct nvmf_capsule *nc; in controller_handle_admin_commands() local
187 cmd = nvmf_capsule_sqe(nc); in controller_handle_admin_commands()
199 nvmf_free_capsule(nc); in controller_handle_admin_commands()
203 if (cb(nc, cmd, cb_arg)) { in controller_handle_admin_commands()
204 nvmf_free_capsule(nc); in controller_handle_admin_commands()
[all …]
H A Ddevices.c235 const struct nvmf_capsule *nc) in device_read() argument
244 nvmf_send_generic_error(nc, in device_read()
256 if (nvmf_capsule_data_len(nc) != len) { in device_read()
268 nvmf_send_generic_error(nc, in device_read()
301 const struct nvmf_capsule *nc) in device_write() argument
311 nvmf_send_generic_error(nc, in device_write()
323 if (nvmf_capsule_data_len(nc) != len) { in device_write()
346 nvmf_send_generic_error(nc, in device_write()
352 nvmf_send_success(nc); in device_write()
362 nvmf_send_generic_error(nc, in device_flush()
[all …]
/freebsd/tools/diag/dumpvfscache/
H A Ddumpvfscache.c72 struct namecache *nc; in main() local
84 nc = malloc(sizeof *nc + NAME_MAX); in main()
97 kvm_read(kvm, p, nc, sizeof *nc + NAME_MAX); in main()
98 kvm_read(kvm, (u_long)nc->nc_dvp, &vn, sizeof vn); in main()
99 nc->nc_name[nc->nc_nlen] = '\0'; in main()
100 for (j=k=kn=0;nc->nc_name[j];j++) { in main()
101 k+= nc->nc_name[j]; in main()
103 kn+= nc->nc_name[j]; in main()
108 kn = wlpsacrc(nc->nc_name,nc->nc_nlen); in main()
117 i,nc->nc_dvp, k, nc->nc_vp, vn.v_id, nc->nc_name); in main()
[all …]
/freebsd/sbin/bsdlabel/
H A Ddisktab25 :ty=floppy:se#512:nt#2:rm#300:ns#9:nc#40:\
30 :ty=floppy:se#512:nt#2:rm#300:ns#9:nc#80:\
35 :ty=floppy:se#512:nt#2:rm#360:ns#15:nc#80:\
40 :ty=floppy:se#512:nt#2:rm#300:ns#18:nc#80:\
45 :ty=floppy:se#512:nt#2:rm#300:ns#36:nc#80:\
55 :ty=floppy:se#512:nt#2:rm#300:ns#10:nc#80:\
60 :ty=floppy:se#512:nt#2:rm#300:ns#10:nc#82:\
175 :ns#2880:nc#1:\
180 :ns#5760:nc#1:\
185 :ns#8640:nc#1:\
[all …]
/freebsd/sys/dev/nvmf/controller/
H A Dnvmft_controller.c631 nvmf_free_capsule(nc); in handle_get_log_page()
657 nvmf_free_capsule(nc); in handle_identify_command()
706 nvmf_free_capsule(nc); in handle_identify_command()
756 nvmf_free_capsule(nc); in handle_set_features()
783 nvmf_free_capsule(nc); in handle_set_features()
934 nvmf_free_capsule(nc); in handle_admin_fabrics_command()
950 nvmf_free_capsule(nc); in nvmft_handle_admin_command()
980 nvmf_free_capsule(nc); in nvmft_handle_admin_command()
984 nvmf_free_capsule(nc); in nvmft_handle_admin_command()
994 nvmf_free_capsule(nc); in nvmft_handle_admin_command()
[all …]
H A Dnvmft_qpair.c43 struct nvmf_capsule *nc, uint8_t sc_status);
72 cmd = nvmf_capsule_sqe(nc); in nvmft_receive_capsule()
76 nvmf_free_capsule(nc); in nvmft_receive_capsule()
80 sc_status = nvmf_validate_command_capsule(nc); in nvmft_receive_capsule()
82 _nvmft_send_generic_error(qp, nc, sc_status); in nvmft_receive_capsule()
83 nvmf_free_capsule(nc); in nvmft_receive_capsule()
90 nvmf_free_capsule(nc); in nvmft_receive_capsule()
95 nvmft_handle_admin_command(ctrlr, nc); in nvmft_receive_capsule()
97 nvmft_handle_io_command(qp, qp->qid, nc); in nvmft_receive_capsule()
250 nvmft_init_cqe(&cpl, nc, status); in nvmft_send_error()
[all …]
/freebsd/tests/sys/netpfil/pf/
H A Dsctp.sh65 echo "foo" | jexec ${j}a nc --sctp -N -l 1234 &
70 out=$(jexec ${j}b nc --sctp -N -w 3 192.0.2.1 1234)
81 echo "foo" | jexec ${j}a nc --sctp -N -l 1234 &
84 out=$(jexec ${j}b nc --sctp -N -w 3 192.0.2.1 1234)
90 echo "foo" | jexec ${j}a nc --sctp -N -l 1235 &
93 out=$(jexec ${j}b nc --sctp -N -w 3 192.0.2.1 1235)
139 echo "foo" | jexec ${j}a nc -6 --sctp -N -l 1234 &
155 echo "foo" | jexec ${j}a nc -6 --sctp -N -l 1234 &
212 echo "foo" | jexec ${j}a nc --sctp -N -l 1234 &
436 echo "foo" | jexec ${j}c nc --sctp -N -l 1234 &
[all …]

123456789