Home
last modified time | relevance | path

Searched refs:val (Results 1 – 25 of 77) sorted by relevance

1234

/spdk/lib/util/
H A Dbase64_neon.c88 ret.val[0] = vld1q_u8(p + 0); in load_64byte_table()
89 ret.val[1] = vld1q_u8(p + 16); in load_64byte_table()
90 ret.val[2] = vld1q_u8(p + 32); in load_64byte_table()
91 ret.val[3] = vld1q_u8(p + 48); in load_64byte_table()
108 res.val[0] = vshrq_n_u8(str.val[0], 2); in base64_encode_neon64()
109 res.val[1] = vandq_u8(vorrq_u8(vshrq_n_u8(str.val[1], 4), vshlq_n_u8(str.val[0], 4)), in base64_encode_neon64()
111 res.val[2] = vandq_u8(vorrq_u8(vshrq_n_u8(str.val[2], 6), vshlq_n_u8(str.val[1], 2)), in base64_encode_neon64()
113 res.val[3] = vandq_u8(str.val[2], vdupq_n_u8(0x3F)); in base64_encode_neon64()
120 res.val[0] = vqtbl4q_u8(tbl_enc, res.val[0]); in base64_encode_neon64()
121 res.val[1] = vqtbl4q_u8(tbl_enc, res.val[1]); in base64_encode_neon64()
[all …]
H A Dcrc32.c14 uint32_t val; in crc32_table_init() local
17 val = i; in crc32_table_init()
19 if (val & 1) { in crc32_table_init()
20 val = (val >> 1) ^ polynomial_reflect; in crc32_table_init()
22 val = (val >> 1); in crc32_table_init()
25 table->table[i] = val; in crc32_table_init()
H A Dcpuset.c144 int val, i, n; in spdk_cpuset_fmt() local
158 val = set->cpus[n]; in spdk_cpuset_fmt()
161 if ((val & 0xf0) != 0) { in spdk_cpuset_fmt()
162 *(ptr++) = hex[(val & 0xf0) >> 4]; in spdk_cpuset_fmt()
164 *(ptr++) = hex[val & 0x0f]; in spdk_cpuset_fmt()
167 val = set->cpus[i]; in spdk_cpuset_fmt()
168 *(ptr++) = hex[(val & 0xf0) >> 4]; in spdk_cpuset_fmt()
169 *(ptr++) = hex[val & 0x0f]; in spdk_cpuset_fmt()
180 static const int8_t val[256] = { in hex_value() local
188 return val[c] - 1; in hex_value()
[all …]
H A Dstring.c397 long val; in spdk_strtol() local
406 val = strtol(nptr, &endptr, base); in spdk_strtol()
411 } else if (errno == ERANGE && (val == LONG_MAX || val == LONG_MIN)) { in spdk_strtol()
414 } else if (errno != 0 && val == 0) { in spdk_strtol()
417 } else if (val < 0) { in spdk_strtol()
422 return val; in spdk_strtol()
428 long long val; in spdk_strtoll() local
437 val = strtoll(nptr, &endptr, base); in spdk_strtoll()
442 } else if (errno == ERANGE && (val == LLONG_MAX || val == LLONG_MIN)) { in spdk_strtoll()
445 } else if (errno != 0 && val == 0) { in spdk_strtoll()
[all …]
/spdk/include/spdk/
H A Djson.h112 typedef int (*spdk_json_decode_fn)(const struct spdk_json_val *val, void *out);
142 int spdk_json_decode_bool(const struct spdk_json_val *val, void *out);
143 int spdk_json_decode_uint8(const struct spdk_json_val *val, void *out);
144 int spdk_json_decode_uint16(const struct spdk_json_val *val, void *out);
145 int spdk_json_decode_int32(const struct spdk_json_val *val, void *out);
146 int spdk_json_decode_uint32(const struct spdk_json_val *val, void *out);
147 int spdk_json_decode_uint64(const struct spdk_json_val *val, void *out);
148 int spdk_json_decode_string(const struct spdk_json_val *val, void *out);
149 int spdk_json_decode_uuid(const struct spdk_json_val *val, void *out);
164 size_t spdk_json_val_len(const struct spdk_json_val *val);
[all …]
H A Dmmio.h35 spdk_mmio_write_1(volatile uint8_t *addr, uint8_t val) in spdk_mmio_write_1() argument
38 *addr = val; in spdk_mmio_write_1()
49 spdk_mmio_write_2(volatile uint16_t *addr, uint16_t val) in spdk_mmio_write_2() argument
52 *addr = val; in spdk_mmio_write_2()
63 spdk_mmio_write_4(volatile uint32_t *addr, uint32_t val) in spdk_mmio_write_4() argument
66 *addr = val; in spdk_mmio_write_4()
72 uint64_t val; in spdk_mmio_read_8() local
78 val = *addr; in spdk_mmio_read_8()
85 val = addr32[0]; in spdk_mmio_read_8()
86 val |= (uint64_t)addr32[1] << 32; in spdk_mmio_read_8()
[all …]
/spdk/lib/json/
H A Djson_util.c14 spdk_json_val_len(const struct spdk_json_val *val) in spdk_json_val_len() argument
16 if (val == NULL) { in spdk_json_val_len()
20 if (val->type == SPDK_JSON_VAL_ARRAY_BEGIN || val->type == SPDK_JSON_VAL_OBJECT_BEGIN) { in spdk_json_val_len()
21 return val->len + 2; in spdk_json_val_len()
28 spdk_json_strequal(const struct spdk_json_val *val, const char *str) in spdk_json_strequal() argument
32 if (val->type != SPDK_JSON_VAL_STRING && val->type != SPDK_JSON_VAL_NAME) { in spdk_json_strequal()
37 if (val->len != len) { in spdk_json_strequal()
41 return memcmp(val->start, str, len) == 0; in spdk_json_strequal()
45 spdk_json_strdup(const struct spdk_json_val *val) in spdk_json_strdup() argument
50 if (val->type != SPDK_JSON_VAL_STRING && val->type != SPDK_JSON_VAL_NAME) { in spdk_json_strdup()
[all …]
H A Djson_write.c182 spdk_json_write_bool(struct spdk_json_write_ctx *w, bool val) in spdk_json_write_bool() argument
185 if (val) { in spdk_json_write_bool()
193 spdk_json_write_uint8(struct spdk_json_write_ctx *w, uint8_t val) in spdk_json_write_uint8() argument
199 count = snprintf(buf, sizeof(buf), "%" PRIu8, val); in spdk_json_write_uint8()
205 spdk_json_write_uint16(struct spdk_json_write_ctx *w, uint16_t val) in spdk_json_write_uint16() argument
211 count = snprintf(buf, sizeof(buf), "%" PRIu16, val); in spdk_json_write_uint16()
217 spdk_json_write_int32(struct spdk_json_write_ctx *w, int32_t val) in spdk_json_write_int32() argument
223 count = snprintf(buf, sizeof(buf), "%" PRId32, val); in spdk_json_write_int32()
229 spdk_json_write_uint32(struct spdk_json_write_ctx *w, uint32_t val) in spdk_json_write_uint32() argument
235 count = snprintf(buf, sizeof(buf), "%" PRIu32, val); in spdk_json_write_uint32()
[all …]
H A Djson_parse.c16 static const int8_t val[256] = { in hex_value() local
24 return val[c] - 1; in hex_value()
32 uint32_t val; in json_decode_string_escape_unicode() local
57 val = v0 | (v1 << 4) | (v2 << 8) | (v3 << 12); in json_decode_string_escape_unicode()
61 if (!utf16_valid_surrogate_low(val)) { in json_decode_string_escape_unicode()
66 val = utf16_decode_surrogate_pair(surrogate_high, val); in json_decode_string_escape_unicode()
67 } else if (utf16_valid_surrogate_high(val)) { in json_decode_string_escape_unicode()
68 surrogate_high = val; in json_decode_string_escape_unicode()
79 } else if (utf16_valid_surrogate_low(val)) { in json_decode_string_escape_unicode()
95 rc = utf8_encode_unsafe(out, val); in json_decode_string_escape_unicode()
[all …]
/spdk/test/unit/lib/
H A Djson_mock.c15 DEFINE_STUB(spdk_json_write_bool, int, (struct spdk_json_write_ctx *w, bool val), 0);
16 DEFINE_STUB(spdk_json_write_uint8, int, (struct spdk_json_write_ctx *w, uint8_t val), 0);
17 DEFINE_STUB(spdk_json_write_uint16, int, (struct spdk_json_write_ctx *w, uint16_t val), 0);
18 DEFINE_STUB(spdk_json_write_int32, int, (struct spdk_json_write_ctx *w, int32_t val), 0);
19 DEFINE_STUB(spdk_json_write_uint32, int, (struct spdk_json_write_ctx *w, uint32_t val), 0);
20 DEFINE_STUB(spdk_json_write_int64, int, (struct spdk_json_write_ctx *w, int64_t val), 0);
21 DEFINE_STUB(spdk_json_write_uint64, int, (struct spdk_json_write_ctx *w, uint64_t val), 0);
22 DEFINE_STUB(spdk_json_write_string, int, (struct spdk_json_write_ctx *w, const char *val), 0);
23 DEFINE_STUB(spdk_json_write_string_raw, int, (struct spdk_json_write_ctx *w, const char *val,
39 bool val), 0);
[all …]
/spdk/test/unit/lib/util/string.c/
H A Dstring_ut.c250 long int val; in test_strtol() local
263 val = spdk_strtol(val1, 10); in test_strtol()
264 CU_ASSERT(val == -EINVAL); in test_strtol()
268 val = spdk_strtol(str, 10); in test_strtol()
269 CU_ASSERT(val == -ERANGE); in test_strtol()
273 val = spdk_strtol(str, 10); in test_strtol()
274 CU_ASSERT(val == -ERANGE); in test_strtol()
278 val = spdk_strtol(str, 10); in test_strtol()
279 CU_ASSERT(val == -ERANGE); in test_strtol()
283 val = spdk_strtol(str, 10); in test_strtol()
[all …]
/spdk/lib/iscsi/
H A Dparam.c38 free(param->val); in iscsi_param_free()
102 const char *val, const char *list, int type) in iscsi_param_add() argument
107 key, val, list, type); in iscsi_param_add()
125 param->val = xstrdup(val); in iscsi_param_add()
144 const char *val) in iscsi_param_set() argument
148 SPDK_DEBUGLOG(iscsi, "set %s=%s\n", key, val); in iscsi_param_set()
155 free(param->val); in iscsi_param_set()
157 param->val = xstrdup(val); in iscsi_param_set()
163 iscsi_param_set_int(struct iscsi_param *params, const char *key, uint32_t val) in iscsi_param_set_int() argument
168 SPDK_DEBUGLOG(iscsi, "set %s=%d\n", key, val); in iscsi_param_set_int()
[all …]
H A Dparam.h29 char *val; member
40 const char *val, const char *list, int type);
42 const char *val);
43 int iscsi_param_set_int(struct iscsi_param *params, const char *key, uint32_t val);
48 const char *val);
/spdk/module/bdev/error/
H A Dvbdev_error_rpc.c14 rpc_error_bdev_decode_io_type(const struct spdk_json_val *val, void *out) in rpc_error_bdev_decode_io_type() argument
18 if (spdk_json_strequal(val, "read") == true) { in rpc_error_bdev_decode_io_type()
20 } else if (spdk_json_strequal(val, "write") == true) { in rpc_error_bdev_decode_io_type()
22 } else if (spdk_json_strequal(val, "flush") == true) { in rpc_error_bdev_decode_io_type()
24 } else if (spdk_json_strequal(val, "unmap") == true) { in rpc_error_bdev_decode_io_type()
26 } else if (spdk_json_strequal(val, "all") == true) { in rpc_error_bdev_decode_io_type()
28 } else if (spdk_json_strequal(val, "clear") == true) { in rpc_error_bdev_decode_io_type()
39 rpc_error_bdev_decode_error_type(const struct spdk_json_val *val, void *out) in rpc_error_bdev_decode_error_type() argument
43 if (spdk_json_strequal(val, "failure") == true) { in rpc_error_bdev_decode_error_type()
45 } else if (spdk_json_strequal(val, "pending") == true) { in rpc_error_bdev_decode_error_type()
[all …]
/spdk/module/event/subsystems/nvmf/
H A Dnvmf_rpc.c52 decode_admin_passthru(const struct spdk_json_val *val, void *out) in decode_admin_passthru() argument
56 if (spdk_json_decode_object(val, admin_passthru_decoder, in decode_admin_passthru()
67 decode_discovery_filter(const struct spdk_json_val *val, void *out) in decode_discovery_filter() argument
71 char *tokens = spdk_json_strdup(val); in decode_discovery_filter()
131 nvmf_decode_poll_groups_mask(const struct spdk_json_val *val, void *out) in nvmf_decode_poll_groups_mask()
133 char *mask = spdk_json_strdup(val); in nvmf_decode_poll_groups_mask()
164 decode_digest(const struct spdk_json_val *val, void *out) in decode_digest()
170 rc = spdk_json_decode_string(val, &digest); in decode_digest()
186 decode_digest_array(const struct spdk_json_val *val, void *out) in decode_digest_array()
193 return spdk_json_decode_array(val, decode_diges in decode_digest_array()
130 nvmf_decode_poll_groups_mask(const struct spdk_json_val * val,void * out) nvmf_decode_poll_groups_mask() argument
163 decode_digest(const struct spdk_json_val * val,void * out) decode_digest() argument
185 decode_digest_array(const struct spdk_json_val * val,void * out) decode_digest_array() argument
196 decode_dhgroup(const struct spdk_json_val * val,void * out) decode_dhgroup() argument
218 decode_dhgroup_array(const struct spdk_json_val * val,void * out) decode_dhgroup_array() argument
[all...]
/spdk/test/app/stub/
H A Dstub.c141 long int val; in main()
166 val = spdk_strtol(optarg, 10); in main()
167 if (val < 0) { in main()
173 opts.shm_id = val; in main()
176 opts.mem_channel = val; in main()
179 opts.main_core = val; in main()
182 opts.mem_size = val; in main()
185 g_sleep_time = val; in main()
188 g_io_queue_size = val; in main()
140 long int val; main() local
/spdk/module/bdev/nvme/
H A Dnvme_rpc.c198 rpc_decode_cmd_type(const struct spdk_json_val *val, void *out) in rpc_decode_cmd_type() argument
202 if (spdk_json_strequal(val, "admin") == true) { in rpc_decode_cmd_type()
204 } else if (spdk_json_strequal(val, "io") == true) { in rpc_decode_cmd_type()
215 rpc_decode_data_direction(const struct spdk_json_val *val, void *out) in rpc_decode_data_direction() argument
219 if (spdk_json_strequal(val, "h2c") == true) { in rpc_decode_data_direction()
221 } else if (spdk_json_strequal(val, "c2h") == true) { in rpc_decode_data_direction()
232 rpc_decode_cmdbuf(const struct spdk_json_val *val, void *out) in rpc_decode_cmdbuf() argument
239 rc = spdk_json_decode_string(val, &text); in rpc_decode_cmdbuf()
241 return val->type == SPDK_JSON_VAL_STRING ? -ENOMEM : -EINVAL; in rpc_decode_cmdbuf()
271 rpc_decode_data(const struct spdk_json_val *val, void *out) in rpc_decode_data() argument
[all …]
/spdk/scripts/
H A Dgenconfig.py19 val = m.group(3).strip() variable
20 args[var] = val
32 val = default variable
34 val = args[var] variable
36 if val.lower() == 'y':
41 strval = val.replace('"', '\"')
/spdk/lib/jsonrpc/
H A Djsonrpc_client.c10 capture_version(const struct spdk_json_val *val, void *out) in capture_version() argument
14 if (spdk_json_strequal(val, "2.0") != true) { in capture_version()
18 *vptr = val; in capture_version()
23 capture_id(const struct spdk_json_val *val, void *out) in capture_id() argument
27 if (val->type != SPDK_JSON_VAL_STRING && val->type != SPDK_JSON_VAL_NUMBER) { in capture_id()
31 *vptr = val; in capture_id()
36 capture_any(const struct spdk_json_val *val, void *out) in capture_any() argument
40 *vptr = val; in capture_any()
/spdk/test/event/reactor_perf/
H A Dreactor_perf.c78 long int val; in main() local
92 val = spdk_strtol(optarg, 10); in main()
93 if (val < 0) { in main()
99 g_queue_depth = val; in main()
102 g_time_in_sec = val; in main()
/spdk/include/spdk_internal/
H A Dutf.h213 utf16_valid_surrogate_high(uint32_t val) in utf16_valid_surrogate_high() argument
215 return val >= 0xD800 && val <= 0xDBFF; in utf16_valid_surrogate_high()
219 utf16_valid_surrogate_low(uint32_t val) in utf16_valid_surrogate_low() argument
221 return val >= 0xDC00 && val <= 0xDFFF; in utf16_valid_surrogate_low()
/spdk/test/nvme/connect_stress/
H A Dconnect_stress.c102 long int val; in parse_args() local
110 val = spdk_strtol(optarg, 10); in parse_args()
111 if (val < 0) { in parse_args()
113 return val; in parse_args()
117 env_opts->shm_id = val; in parse_args()
120 env_opts->mem_size = val; in parse_args()
123 g_time_in_sec = val; in parse_args()
/spdk/lib/conf/
H A Dconf.c21 struct spdk_conf_value *val; member
94 if (ip->val != NULL) { in free_conf_item()
95 free_all_conf_value(ip->val); in free_conf_item()
312 if (ip->val == NULL) { in append_cf_value()
313 ip->val = vp; in append_cf_value()
317 for (last = ip->val; last->next != NULL; last = last->next) in append_cf_value()
352 vp = ip->val; in spdk_conf_section_get_nmval()
377 vp = ip->val; in spdk_conf_section_get_nval()
435 char *val; in parse_line() local
510 ip->val = NULL; in parse_line()
[all …]
/spdk/test/scheduler/
H A Dcgroups.sh84 local val=$3
88 if [[ -n $val ]]; then
89 echo "$val" > "$sysfs_cgroup/$cgroup/$attr"
178 local cgroup_path=$1 attr=$2 val=$3
181 _set_cgroup_attr_top_bottom "${cgroup_path%/*}" "$attr" "$val"
185 echo "$val" > "$cgroup_path/$attr"
/spdk/module/accel/error/
H A Daccel_error_rpc.c12 rpc_accel_error_decode_opcode(const struct spdk_json_val *val, void *out) in rpc_accel_error_decode_opcode() argument
18 rc = spdk_json_decode_string(val, &opstr); in rpc_accel_error_decode_opcode()
38 rpc_accel_error_decode_type(const struct spdk_json_val *val, void *out) in rpc_accel_error_decode_type() argument
44 rc = spdk_json_decode_string(val, &typestr); in rpc_accel_error_decode_type()

1234