Home
last modified time | relevance | path

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

123456789

/freebsd/contrib/llvm-project/clang/include/clang/Basic/
H A DBuiltinsMips.def29 BUILTIN(__builtin_mips_madd, "LLiLLiii", "nc")
30 BUILTIN(__builtin_mips_maddu, "LLiLLiUiUi", "nc")
31 BUILTIN(__builtin_mips_msub, "LLiLLiii", "nc")
32 BUILTIN(__builtin_mips_msubu, "LLiLLiUiUi", "nc")
40 BUILTIN(__builtin_mips_modsub, "iii", "nc")
42 BUILTIN(__builtin_mips_raddu_w_qb, "iV4Sc", "nc")
47 BUILTIN(__builtin_mips_precrq_qb_ph, "V4ScV2sV2s", "nc")
49 BUILTIN(__builtin_mips_precrq_ph_w, "V2sii", "nc")
51 BUILTIN(__builtin_mips_preceq_w_phl, "iV2s", "nc")
52 BUILTIN(__builtin_mips_preceq_w_phr, "iV2s", "nc")
[all …]
H A DBuiltinsLoongArchLASX.def15 TARGET_BUILTIN(__builtin_lasx_xvadd_b, "V32ScV32ScV32Sc", "nc", "lasx")
16 TARGET_BUILTIN(__builtin_lasx_xvadd_h, "V16sV16sV16s", "nc", "lasx")
17 TARGET_BUILTIN(__builtin_lasx_xvadd_w, "V8iV8iV8i", "nc", "lasx")
18 TARGET_BUILTIN(__builtin_lasx_xvadd_d, "V4LLiV4LLiV4LLi", "nc", "lasx")
19 TARGET_BUILTIN(__builtin_lasx_xvadd_q, "V4LLiV4LLiV4LLi", "nc", "lasx")
21 TARGET_BUILTIN(__builtin_lasx_xvsub_b, "V32ScV32ScV32Sc", "nc", "lasx")
22 TARGET_BUILTIN(__builtin_lasx_xvsub_h, "V16sV16sV16s", "nc", "lasx")
23 TARGET_BUILTIN(__builtin_lasx_xvsub_w, "V8iV8iV8i", "nc", "lasx")
24 TARGET_BUILTIN(__builtin_lasx_xvsub_d, "V4LLiV4LLiV4LLi", "nc", "lasx")
25 TARGET_BUILTIN(__builtin_lasx_xvsub_q, "V4LLiV4LLiV4LLi", "nc", "lasx")
[all …]
H A DBuiltinsLoongArchLSX.def15 TARGET_BUILTIN(__builtin_lsx_vadd_b, "V16ScV16ScV16Sc", "nc", "lsx")
16 TARGET_BUILTIN(__builtin_lsx_vadd_h, "V8sV8sV8s", "nc", "lsx")
17 TARGET_BUILTIN(__builtin_lsx_vadd_w, "V4iV4iV4i", "nc", "lsx")
18 TARGET_BUILTIN(__builtin_lsx_vadd_d, "V2LLiV2LLiV2LLi", "nc", "lsx")
19 TARGET_BUILTIN(__builtin_lsx_vadd_q, "V2LLiV2LLiV2LLi", "nc", "lsx")
21 TARGET_BUILTIN(__builtin_lsx_vsub_b, "V16ScV16ScV16Sc", "nc", "lsx")
22 TARGET_BUILTIN(__builtin_lsx_vsub_h, "V8sV8sV8s", "nc", "lsx")
23 TARGET_BUILTIN(__builtin_lsx_vsub_w, "V4iV4iV4i", "nc", "lsx")
24 TARGET_BUILTIN(__builtin_lsx_vsub_d, "V2LLiV2LLiV2LLi", "nc", "lsx")
25 TARGET_BUILTIN(__builtin_lsx_vsub_q, "V2LLiV2LLiV2LLi", "nc", "lsx")
[all …]
H A DBuiltinsAMDGPU.def28 BUILTIN(__builtin_amdgcn_dispatch_ptr, "v*4", "nc")
29 BUILTIN(__builtin_amdgcn_kernarg_segment_ptr, "v*4", "nc")
30 BUILTIN(__builtin_amdgcn_implicitarg_ptr, "v*4", "nc")
31 BUILTIN(__builtin_amdgcn_queue_ptr, "v*4", "nc")
33 BUILTIN(__builtin_amdgcn_workgroup_id_x, "Ui", "nc")
34 BUILTIN(__builtin_amdgcn_workgroup_id_y, "Ui", "nc")
35 BUILTIN(__builtin_amdgcn_workgroup_id_z, "Ui", "nc")
37 BUILTIN(__builtin_amdgcn_workitem_id_x, "Ui", "nc")
38 BUILTIN(__builtin_amdgcn_workitem_id_y, "Ui", "nc")
39 BUILTIN(__builtin_amdgcn_workitem_id_z, "Ui", "nc")
[all …]
H A DBuiltinsWebAssembly.def29 TARGET_BUILTIN(__builtin_wasm_tls_size, "z", "nc", "bulk-memory")
30 TARGET_BUILTIN(__builtin_wasm_tls_align, "z", "nc", "bulk-memory")
34 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")
[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")
36 BUILTIN(__builtin_arm_smulwb, "iii", "nc")
37 BUILTIN(__builtin_arm_smulwt, "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")
[all …]
/freebsd/sys/dev/ntb/
H A Dntb.c63 struct ntb_child *nc; in ntb_register_device() local
100 nc = malloc(sizeof(*nc), M_DEVBUF, M_WAITOK | M_ZERO); in ntb_register_device()
101 nc->function = i; in ntb_register_device()
102 nc->mwoff = mwu; in ntb_register_device()
103 nc->mwcnt = mw; in ntb_register_device()
104 nc->spadoff = spadu; in ntb_register_device()
105 nc->spadcnt = spad; in ntb_register_device()
106 nc->dboff = dbu; in ntb_register_device()
107 nc->dbcnt = db; in ntb_register_device()
108 nc->dbmask = (db == 0) ? 0 : (0xffffffffffffffff >> (64 - db)); in ntb_register_device()
[all …]
/freebsd/lib/libnvmf/
H A Dnvmf_transport.c113 struct nvmf_capsule *nc, *tc; in nvmf_free_qpair() local
115 TAILQ_FOREACH_SAFE(nc, &qp->nq_rx_capsules, nc_link, tc) { in nvmf_free_qpair()
116 TAILQ_REMOVE(&qp->nq_rx_capsules, nc, nc_link); in nvmf_free_qpair()
117 nvmf_free_capsule(nc); in nvmf_free_qpair()
127 struct nvmf_capsule *nc; in nvmf_allocate_command() local
129 nc = qp->nq_association->na_ops->allocate_capsule(qp); in nvmf_allocate_command()
130 if (nc == NULL) in nvmf_allocate_command()
133 nc->nc_qpair = qp; in nvmf_allocate_command()
134 nc->nc_qe_len = sizeof(struct nvme_command); in nvmf_allocate_command()
135 memcpy(&nc->nc_sqe, sqe, nc->nc_qe_len); in nvmf_allocate_command()
[all …]
H A Dnvmf_tcp.c55 struct nvmf_capsule nc; member
81 #define TASSOC(nc) ((struct nvmf_tcp_association *)(na)) argument
82 #define TCAP(nc) ((struct nvmf_tcp_capsule *)(nc)) argument
83 #define CTCAP(nc) ((const struct nvmf_tcp_capsule *)(nc)) argument
373 struct nvmf_capsule *nc; in nvmf_tcp_save_command_capsule() local
378 nc = nvmf_allocate_command(&qp->qp, &cmd->ccsqe); in nvmf_tcp_save_command_capsule()
379 if (nc == NULL) in nvmf_tcp_save_command_capsule()
382 tc = TCAP(nc); in nvmf_tcp_save_command_capsule()
394 struct nvmf_capsule *nc; in nvmf_tcp_save_response_capsule() local
399 nc = nvmf_allocate_response(&qp->qp, &rsp->rccqe); in nvmf_tcp_save_response_capsule()
[all …]
H A Dlibnvmf.h105 void nvmf_free_capsule(struct nvmf_capsule *nc);
106 int nvmf_capsule_append_data(struct nvmf_capsule *nc,
108 int nvmf_transmit_capsule(struct nvmf_capsule *nc);
110 const void *nvmf_capsule_sqe(const struct nvmf_capsule *nc);
111 const void *nvmf_capsule_cqe(const struct nvmf_capsule *nc);
132 uint8_t nvmf_validate_command_capsule(const struct nvmf_capsule *nc);
147 int nvmf_receive_controller_data(const struct nvmf_capsule *nc,
157 int nvmf_send_controller_data(const struct nvmf_capsule *nc,
165 void nvmf_init_cqe(void *cqe, const struct nvmf_capsule *nc,
172 int nvmf_send_response(const struct nvmf_capsule *nc, const void *cqe);
[all …]
/freebsd/sys/dev/nvmf/
H A Dnvmf_transport.c97 struct nvmf_capsule *nc; in nvmf_allocate_command() local
101 nc = qp->nq_ops->allocate_capsule(qp, how); in nvmf_allocate_command()
102 if (nc == NULL) in nvmf_allocate_command()
105 nc->nc_qpair = qp; in nvmf_allocate_command()
106 nc->nc_qe_len = sizeof(struct nvme_command); in nvmf_allocate_command()
107 memcpy(&nc->nc_sqe, sqe, nc->nc_qe_len); in nvmf_allocate_command()
110 nc->nc_sqe.fuse &= ~NVMEM(NVME_CMD_PSDT); in nvmf_allocate_command()
111 nc->nc_sqe.fuse |= NVMEF(NVME_CMD_PSDT, NVME_PSDT_SGL); in nvmf_allocate_command()
112 return (nc); in nvmf_allocate_command()
118 struct nvmf_capsule *nc; in nvmf_allocate_response() local
[all …]
H A Dnvmf_transport.h74 void nvmf_free_capsule(struct nvmf_capsule *nc);
75 int nvmf_capsule_append_data(struct nvmf_capsule *nc,
78 int nvmf_transmit_capsule(struct nvmf_capsule *nc);
79 void nvmf_abort_capsule_data(struct nvmf_capsule *nc, int error);
80 void *nvmf_capsule_sqe(struct nvmf_capsule *nc);
81 void *nvmf_capsule_cqe(struct nvmf_capsule *nc);
82 bool nvmf_sqhd_valid(struct nvmf_capsule *nc);
106 uint8_t nvmf_validate_command_capsule(struct nvmf_capsule *nc);
124 int nvmf_receive_controller_data(struct nvmf_capsule *nc,
150 u_int nvmf_send_controller_data(struct nvmf_capsule *nc,
H A Dnvmf_transport_internal.h37 void (*free_capsule)(struct nvmf_capsule *nc);
38 int (*transmit_capsule)(struct nvmf_capsule *nc);
39 uint8_t (*validate_command_capsule)(struct nvmf_capsule *nc);
42 size_t (*capsule_data_len)(const struct nvmf_capsule *nc);
43 int (*receive_controller_data)(struct nvmf_capsule *nc,
45 u_int (*send_controller_data)(struct nvmf_capsule *nc,
112 nvmf_capsule_received(struct nvmf_qpair *nq, struct nvmf_capsule *nc) in nvmf_capsule_received() argument
114 nq->nq_receive(nq->nq_receive_arg, nc); in nvmf_capsule_received()
/freebsd/tools/tools/nvmf/nvmfd/
H A Dio.c90 handle_get_log_page(struct io_controller *ioc, const struct nvmf_capsule *nc, in handle_get_log_page() argument
116 nvmf_send_controller_data(nc, buf, len); in handle_get_log_page()
124 nvmf_send_controller_data(nc, &ioc->hip, sizeof(ioc->hip)); in handle_get_log_page()
130 nvmf_send_controller_data(nc, &ioc->fp, sizeof(ioc->fp)); in handle_get_log_page()
138 nvmf_send_generic_error(nc, NVME_SC_INVALID_FIELD); in handle_get_log_page()
142 handle_io_identify_command(const struct nvmf_capsule *nc, in handle_io_identify_command() argument
154 nvmf_send_generic_error(nc, in handle_io_identify_command()
159 nvmf_send_controller_data(nc, &nsdata, sizeof(nsdata)); in handle_io_identify_command()
164 nvmf_send_generic_error(nc, NVME_SC_INVALID_FIELD); in handle_io_identify_command()
169 nvmf_send_controller_data(nc, &nslist, sizeof(nslist)); in handle_io_identify_command()
[all …]
H A Dcontroller.c61 handle_property_get(const struct controller *c, const struct nvmf_capsule *nc, in handle_property_get() argument
66 nvmf_init_cqe(&rsp, nc, 0); in handle_property_get()
93 nvmf_send_response(nc, &rsp); in handle_property_get()
96 nvmf_send_generic_error(nc, NVME_SC_INVALID_FIELD); in handle_property_get()
100 handle_property_set(struct controller *c, const struct nvmf_capsule *nc, in handle_property_set() argument
114 nvmf_send_success(nc); in handle_property_set()
117 nvmf_send_generic_error(nc, NVME_SC_INVALID_FIELD); in handle_property_set()
122 const struct nvmf_capsule *nc, const struct nvmf_fabric_cmd *fc) in handle_fabrics_command() argument
126 handle_property_get(c, nc, in handle_fabrics_command()
130 handle_property_set(c, nc, in handle_fabrics_command()
[all …]
H A Ddevices.c235 const struct nvmf_capsule *nc) in device_read() argument
244 nvmf_send_generic_error(nc, in device_read()
250 nvmf_send_generic_error(nc, NVME_SC_LBA_OUT_OF_RANGE); in device_read()
256 if (nvmf_capsule_data_len(nc) != len) { in device_read()
257 nvmf_send_generic_error(nc, NVME_SC_INVALID_FIELD); in device_read()
268 nvmf_send_generic_error(nc, in device_read()
275 nvmf_send_controller_data(nc, src, len); in device_read()
301 const struct nvmf_capsule *nc) in device_write() argument
311 nvmf_send_generic_error(nc, in device_write()
317 nvmf_send_generic_error(nc, NVME_SC_LBA_OUT_OF_RANGE); in device_write()
[all …]
/freebsd/usr.sbin/ctld/
H A Dnvmf_discovery.cc43 void handle_property_get(const struct nvmf_capsule *nc,
45 void handle_property_set(const struct nvmf_capsule *nc,
47 void handle_fabrics_command(const struct nvmf_capsule *nc,
49 void handle_identify_command(const struct nvmf_capsule *nc,
51 void handle_get_log_page_command(const struct nvmf_capsule *nc,
281 discovery_controller::handle_property_get(const struct nvmf_capsule *nc, in handle_property_get() argument
286 nvmf_init_cqe(&rsp, nc, 0); in handle_property_get()
313 nvmf_send_response(nc, &rsp); in handle_property_get()
316 nvmf_send_generic_error(nc, NVME_SC_INVALID_FIELD); in handle_property_get()
320 discovery_controller::handle_property_set(const struct nvmf_capsule *nc, in handle_property_set() argument
[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/sys/dev/nvmf/controller/
H A Dnvmft_controller.c551 struct nvmf_capsule *nc, const struct nvme_command *cmd) in handle_get_log_page() argument
580 status = nvmf_send_controller_data(nc, 0, m, len); in handle_get_log_page()
607 status = nvmf_send_controller_data(nc, 0, m, len); in handle_get_log_page()
624 status = nvmf_send_controller_data(nc, 0, m, len); in handle_get_log_page()
647 status = nvmf_send_controller_data(nc, 0, m, len); in handle_get_log_page()
659 nvmft_command_completed(ctrlr->admin, nc); in handle_get_log_page()
661 nvmft_send_generic_error(ctrlr->admin, nc, status); in handle_get_log_page()
662 nvmf_free_capsule(nc); in handle_get_log_page()
673 struct nvmf_capsule *nc, const struct nvme_command *cmd) in handle_identify_command() argument
681 data_len = nvmf_capsule_data_len(nc); in handle_identify_command()
[all …]
H A Dnvmft_qpair.c45 struct nvmf_capsule *nc, uint8_t sc_status);
68 nvmft_receive_capsule(void *arg, struct nvmf_capsule *nc) in nvmft_receive_capsule() argument
75 cmd = nvmf_capsule_sqe(nc); in nvmft_receive_capsule()
79 nvmf_free_capsule(nc); in nvmft_receive_capsule()
83 sc_status = nvmf_validate_command_capsule(nc); in nvmft_receive_capsule()
85 _nvmft_send_generic_error(qp, nc, sc_status); in nvmft_receive_capsule()
86 nvmf_free_capsule(nc); in nvmft_receive_capsule()
92 _nvmft_send_generic_error(qp, nc, NVME_SC_COMMAND_ID_CONFLICT); in nvmft_receive_capsule()
93 nvmf_free_capsule(nc); in nvmft_receive_capsule()
98 nvmft_handle_admin_command(ctrlr, nc); in nvmft_receive_capsule()
[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:\
65 :ty=floppy:se#512:nt#2:rm#300:ns#18:nc#82:\
70 :ty=floppy:se#512:nt#2:rm#300:ns#21:nc#82:\
78 :ty=floppy:se#512:nt#8:rm#300:ns#32:nc#963:\
[all …]
/freebsd/tests/sys/netpfil/pf/
H A Dsctp.sh63 echo "foo" | jexec ${j}a nc --sctp -N -l 1234 &
68 out=$(jexec ${j}b nc --sctp -N -w 3 192.0.2.1 1234)
79 echo "foo" | jexec ${j}a nc --sctp -N -l 1234 &
82 out=$(jexec ${j}b nc --sctp -N -w 3 192.0.2.1 1234)
88 echo "foo" | jexec ${j}a nc --sctp -N -l 1235 &
91 out=$(jexec ${j}b nc --sctp -N -w 3 192.0.2.1 1235)
97 out=$(jexec ${j}b nc --sctp -N -w 3 -p 1234 192.0.2.1 1235)
138 echo "foo" | jexec ${j}a nc -6 --sctp -N -l 1234 &
143 out=$(jexec ${j}b nc --sctp -N -w 3 2001:db8::a 1234)
154 echo "foo" | jexec ${j}a nc -6 --sctp -N -l 1234 &
[all …]
/freebsd/contrib/mandoc/
H A Dman_validate.c297 struct roff_node *nc; in post_SH() local
300 nc = n->child; in post_SH()
303 if ((nc = n->prev) != NULL && nc->tok == ROFF_br) { in post_SH()
304 mandoc_msg(MANDOCERR_PAR_SKIP, nc->line, nc->pos, in post_SH()
305 "%s before first %s", roff_name[nc->tok], in post_SH()
307 roff_node_delete(man, nc); in post_SH()
317 if (nc != NULL && nc in post_SH()
[all...]
/freebsd/contrib/arm-optimized-routines/math/tools/
H A Dremez.jl738 nc, dc, e1 = try_e(e0)
743 return nc, dc
752 nc, dc, e2 = try_e(e1)
760 nc, dc, enew = try_e(emid)
769 return nc, dc
826 (nc, dc) = ratfn_leastsquares(f, grid, n, d, w)
828 ratfn_to_string(nc, dc))
849 approx_y = ratfn_eval(nc, dc, x)
867 return nc, dc, max_err, extrema
872 (nc, dc) = ratfn_equal_deviation(f, map(x->x[1], extrema),
[all …]
/freebsd/lib/libc/stdlib/
H A Dradixsort.c126 static int count[256], nc, bmin; in r_sort_a() local
145 if (nc == 0) { in r_sort_a()
152 nc++; in r_sort_a()
155 if (sp + nc > s + SIZE) { /* Get more stack. */ in r_sort_a()
166 if (nc == 1 && count[bmin] == n) { in r_sort_a()
168 nc = count[bmin] = 0; in r_sort_a()
187 for (cp = count + bmin; nc > 0; cp++) { in r_sort_a()
198 nc--; in r_sort_a()
225 static int count[256], nc, bmin; in r_sort_b() local
241 if (nc == 0) { in r_sort_b()
[all …]

123456789