| /f-stack/freebsd/mips/nlm/hal/ |
| H A D | xaui.h | 40 #define XAUI_CONFIG0(block) NAE_REG(block, 4, 0x00) argument 41 #define XAUI_CONFIG1(block) NAE_REG(block, 4, 0x01) argument 42 #define XAUI_CONFIG2(block) NAE_REG(block, 4, 0x02) argument 43 #define XAUI_CONFIG3(block) NAE_REG(block, 4, 0x03) argument 49 #define XAUI_REVISION_LVL(block) NAE_REG(block, 4, 0x0b) argument 50 #define XAUI_MII_MGMT_CMD(block) NAE_REG(block, 4, 0x10) argument 52 #define XAUI_MII_MGMT_CFG(block) NAE_REG(block, 4, 0x12) argument 55 #define XAUI_STATS_MLR(block) NAE_REG(block, 4, 0x1f) argument 56 #define XAUI_STATS_TR64(block) NAE_REG(block, 4, 0x20) argument 60 #define XAUI_STATS_TR1K(block) NAE_REG(block, 4, 0x24) argument [all …]
|
| H A D | sgmii.h | 42 #define SGMII_MAC_CONF1(block, i) NAE_REG(block, i, 0x00) argument 43 #define SGMII_MAC_CONF2(block, i) NAE_REG(block, i, 0x01) argument 44 #define SGMII_IPG_IFG(block, i) NAE_REG(block, i, 0x02) argument 45 #define SGMII_HLF_DUP(block, i) NAE_REG(block, i, 0x03) argument 46 #define SGMII_MAX_FRAME(block, i) NAE_REG(block, i, 0x04) argument 47 #define SGMII_TEST(block, i) NAE_REG(block, i, 0x07) argument 48 #define SGMII_MIIM_CONF(block, i) NAE_REG(block, i, 0x08) argument 49 #define SGMII_MIIM_CMD(block, i) NAE_REG(block, i, 0x09) argument 53 #define SGMII_MIIM_IND(block, i) NAE_REG(block, i, 0x0d) argument 54 #define SGMII_IO_CTRL(block, i) NAE_REG(block, i, 0x0e) argument [all …]
|
| H A D | interlaken.h | 41 #define ILK_TX_CONTROL(block) NAE_REG(block, 5, 0x00) argument 42 #define ILK_TX_RATE_LIMIT(block) NAE_REG(block, 5, 0x01) argument 43 #define ILK_TX_META_CTRL(block) NAE_REG(block, 5, 0x02) argument 44 #define ILK_RX_CTRL(block) NAE_REG(block, 5, 0x03) argument 45 #define ILK_RX_STATUS1(block) NAE_REG(block, 5, 0x04) argument 46 #define ILK_RX_STATUS2(block) NAE_REG(block, 5, 0x05) argument 48 #define ILK_STATUS3(block) NAE_REG(block, 5, 0x07) argument 49 #define ILK_RX_FC_TMAP0(block) NAE_REG(block, 5, 0x08) argument 50 #define ILK_RX_FC_TMAP1(block) NAE_REG(block, 5, 0x09) argument 51 #define ILK_RX_FC_TMAP2(block) NAE_REG(block, 5, 0x0a) argument [all …]
|
| /f-stack/dpdk/lib/librte_acl/ |
| H A D | tb_mem.c | 26 block = calloc(1, size + sizeof(*pool->block)); in tb_pool() 34 block->pool = pool; in tb_pool() 36 block->next = pool->block; in tb_pool() 37 pool->block = block; in tb_pool() 43 block->size = size - (block->mem - ptr); in tb_pool() 45 return block; in tb_pool() 57 block = pool->block; in tb_alloc() 58 if (block == NULL || block->size < size) { in tb_alloc() 62 ptr = block->mem; in tb_alloc() 73 for (block = pool->block; block != NULL; block = next) { in tb_free_pool() [all …]
|
| /f-stack/freebsd/contrib/octeon-sdk/ |
| H A D | cvmx-nand.c | 1753 pd0 ^= (block[i] ^ (block[i] >> 2) ^ (block[i] >> 4) ^ (block[i] >> 6)) & 1; in cvmx_nand_compute_boot_ecc() 1755 pd0 ^= ((block[i] ^ (block[i] >> 1) ^ (block[i] >> 4) ^ (block[i] >> 5)) & 1) << 1; in cvmx_nand_compute_boot_ecc() 1757 pd0 ^= ((block[i] ^ (block[i] >> 1) ^ (block[i] >> 2) ^ (block[i] >> 3)) & 1) << 2; in cvmx_nand_compute_boot_ecc() 1793 pd1 ^= ((block[i] ^ (block[i] >> 1) ^ (block[i] >> 2) ^ in cvmx_nand_compute_boot_ecc() 1794 (block[i] >> 3) ^ (block[i] >> 4) ^ (block[i] >> 5) ^ in cvmx_nand_compute_boot_ecc() 1799 pd1 ^= (((block[i] >> 1) ^ (block[i] >> 3) ^ (block[i] >> 5) ^ (block[i] >> 7)) & 1) << 5; in cvmx_nand_compute_boot_ecc() 1839 pd2 ^= ((block[i] ^ (block[i] >> 1) ^ (block[i] >> 2) ^ in cvmx_nand_compute_boot_ecc() 1840 (block[i] >> 3) ^ (block[i] >> 4) ^ (block[i] >> 5) ^ in cvmx_nand_compute_boot_ecc() 1869 pd0 ^= (block[i] ^ (block[i] >> 2) ^ (block[i] >> 4) ^ (block[i] >> 6)) & 1; in cvmx_nand_correct_boot_ecc() 1871 pd0 ^= ((block[i] ^ (block[i] >> 1) ^ (block[i] >> 4) ^ (block[i] >> 5)) & 1) << 1; in cvmx_nand_correct_boot_ecc() [all …]
|
| /f-stack/freebsd/crypto/rijndael/ |
| H A D | rijndael-api-fst.c | 87 uint8_t block[16], iv[4][4]; in rijndael_blockEncrypt() local 161 block); in rijndael_blockEncrypt() 187 explicit_bzero(block, sizeof(block)); in rijndael_blockEncrypt() 227 for (cp = block + 16 - padLen; cp < block + 16; cp++) in rijndael_padEncrypt() 260 explicit_bzero(block, sizeof(block)); in rijndael_padEncrypt() 334 block); in rijndael_blockDecrypt() 360 explicit_bzero(block, sizeof(block)); in rijndael_blockDecrypt() 367 uint8_t block[16]; in rijndael_padDecrypt() local 394 padLen = block[15]; in rijndael_padDecrypt() 428 padLen = block[15]; in rijndael_padDecrypt() [all …]
|
| /f-stack/freebsd/mips/nlm/dev/net/ |
| H A D | mdio.c | 64 NAE_REG(block, intf_type, (INT_MDIO_CTRL + bus * 4))); in nlm_int_gmac_mdio_read() 67 NAE_REG(block, intf_type, (INT_MDIO_CTRL + bus*4)), in nlm_int_gmac_mdio_read() 72 NAE_REG(block, intf_type, (INT_MDIO_CTRL + bus * 4)), in nlm_int_gmac_mdio_read() 77 NAE_REG(block, intf_type, (INT_MDIO_CTRL + bus * 4)), in nlm_int_gmac_mdio_read() 87 NAE_REG(block, intf_type, (INT_MDIO_CTRL + bus * 4)), in nlm_int_gmac_mdio_read() 117 NAE_REG(block, intf_type, (INT_MDIO_CTRL + bus*4)), in nlm_int_gmac_mdio_write() 180 nlm_gmac_mdio_read(uint64_t nae_base, int bus, int block, in nlm_gmac_mdio_read() argument 193 NAE_REG(block, intf_type, in nlm_gmac_mdio_read() 207 NAE_REG(block, intf_type, (EXT_G0_MDIO_CTRL+bus*4)), in nlm_gmac_mdio_read() 254 NAE_REG(block, intf_type, in nlm_gmac_mdio_write() [all …]
|
| H A D | xaui.c | 49 int block, lane_ctrl, reg; in nlm_xaui_pcs_init() local 63 block = 7; in nlm_xaui_pcs_init() 77 NAE_REG(block, LANE_CFG, LANE_CFG_CPLX_0_1), in nlm_xaui_pcs_init() 93 NAE_REG(block, LANE_CFG, LANE_CFG_CPLX_2_3), in nlm_xaui_pcs_init() 98 for (block = 0; block < 4; block++) { in nlm_xaui_pcs_init() 99 if ((xaui_cplx_mask & (1 << block)) == 0) in nlm_xaui_pcs_init() 106 block, lane_ctrl, PHYMODE_XAUI); in nlm_xaui_pcs_init() 108 xlp_ax_nae_lane_reset_txpll(nae_base, block, in nlm_xaui_pcs_init() 114 for (block = 0; block < 4; block++) { in nlm_xaui_pcs_init() 115 if ((xaui_cplx_mask & (1 << block)) == 0) in nlm_xaui_pcs_init() [all …]
|
| /f-stack/freebsd/contrib/libsodium/src/libsodium/crypto_secretstream/xchacha20poly1305/ |
| H A D | secretstream_xchacha20poly1305.c | 131 sodium_memzero(block, sizeof block); in crypto_secretstream_xchacha20poly1305_push() 136 memset(block, 0, sizeof block); in crypto_secretstream_xchacha20poly1305_push() 137 block[0] = tag; in crypto_secretstream_xchacha20poly1305_push() 139 crypto_stream_chacha20_ietf_xor_ic(block, block, sizeof block, in crypto_secretstream_xchacha20poly1305_push() 142 out[0] = block[0]; in crypto_secretstream_xchacha20poly1305_push() 207 sodium_memzero(block, sizeof block); in crypto_secretstream_xchacha20poly1305_pull() 213 memset(block, 0, sizeof block); in crypto_secretstream_xchacha20poly1305_pull() 214 block[0] = in[0]; in crypto_secretstream_xchacha20poly1305_pull() 215 crypto_stream_chacha20_ietf_xor_ic(block, block, sizeof block, in crypto_secretstream_xchacha20poly1305_pull() 217 tag = block[0]; in crypto_secretstream_xchacha20poly1305_pull() [all …]
|
| /f-stack/freebsd/contrib/libsodium/src/libsodium/crypto_generichash/blake2b/ref/ |
| H A D | blake2b-compress-ssse3.c | 42 const uint64_t m0 = ((uint64_t *) block)[0]; in blake2b_compress_ssse3() 43 const uint64_t m1 = ((uint64_t *) block)[1]; in blake2b_compress_ssse3() 44 const uint64_t m2 = ((uint64_t *) block)[2]; in blake2b_compress_ssse3() 45 const uint64_t m3 = ((uint64_t *) block)[3]; in blake2b_compress_ssse3() 46 const uint64_t m4 = ((uint64_t *) block)[4]; in blake2b_compress_ssse3() 47 const uint64_t m5 = ((uint64_t *) block)[5]; in blake2b_compress_ssse3() 48 const uint64_t m6 = ((uint64_t *) block)[6]; in blake2b_compress_ssse3() 49 const uint64_t m7 = ((uint64_t *) block)[7]; in blake2b_compress_ssse3() 50 const uint64_t m8 = ((uint64_t *) block)[8]; in blake2b_compress_ssse3() 51 const uint64_t m9 = ((uint64_t *) block)[9]; in blake2b_compress_ssse3() [all …]
|
| H A D | blake2b-compress-sse41.c | 36 const uint8_t block[BLAKE2B_BLOCKBYTES]) in blake2b_compress_sse41() 48 const __m128i m0 = LOADU(block + 00); in blake2b_compress_sse41() 49 const __m128i m1 = LOADU(block + 16); in blake2b_compress_sse41() 50 const __m128i m2 = LOADU(block + 32); in blake2b_compress_sse41() 51 const __m128i m3 = LOADU(block + 48); in blake2b_compress_sse41() 52 const __m128i m4 = LOADU(block + 64); in blake2b_compress_sse41() 53 const __m128i m5 = LOADU(block + 80); in blake2b_compress_sse41() 54 const __m128i m6 = LOADU(block + 96); in blake2b_compress_sse41() 55 const __m128i m7 = LOADU(block + 112); in blake2b_compress_sse41()
|
| /f-stack/freebsd/contrib/libsodium/src/libsodium/crypto_stream/salsa2012/ref/ |
| H A D | stream_salsa2012_ref.c | 18 unsigned char block[64]; in crypto_stream_salsa2012() local 47 crypto_core_salsa2012(block, in, kcopy, NULL); in crypto_stream_salsa2012() 49 c[i] = block[i]; in crypto_stream_salsa2012() 52 sodium_memzero(block, sizeof block); in crypto_stream_salsa2012() 64 unsigned char block[64]; in crypto_stream_salsa2012_xor() local 82 crypto_core_salsa2012(block, in, kcopy, NULL); in crypto_stream_salsa2012_xor() 84 c[i] = m[i] ^ block[i]; in crypto_stream_salsa2012_xor() 97 crypto_core_salsa2012(block, in, kcopy, NULL); in crypto_stream_salsa2012_xor() 99 c[i] = m[i] ^ block[i]; in crypto_stream_salsa2012_xor() 102 sodium_memzero(block, sizeof block); in crypto_stream_salsa2012_xor()
|
| /f-stack/freebsd/contrib/libsodium/src/libsodium/crypto_stream/salsa208/ref/ |
| H A D | stream_salsa208_ref.c | 18 unsigned char block[64]; in crypto_stream_salsa208() local 47 crypto_core_salsa208(block, in, kcopy, NULL); in crypto_stream_salsa208() 49 c[i] = block[i]; in crypto_stream_salsa208() 52 sodium_memzero(block, sizeof block); in crypto_stream_salsa208() 64 unsigned char block[64]; in crypto_stream_salsa208_xor() local 82 crypto_core_salsa208(block, in, kcopy, NULL); in crypto_stream_salsa208_xor() 84 c[i] = m[i] ^ block[i]; in crypto_stream_salsa208_xor() 97 crypto_core_salsa208(block, in, kcopy, NULL); in crypto_stream_salsa208_xor() 99 c[i] = m[i] ^ block[i]; in crypto_stream_salsa208_xor() 102 sodium_memzero(block, sizeof block); in crypto_stream_salsa208_xor()
|
| /f-stack/freebsd/contrib/libsodium/src/libsodium/crypto_stream/salsa20/ref/ |
| H A D | salsa20_ref.c | 23 unsigned char block[64]; in stream_ref() local 52 crypto_core_salsa20(block, in, kcopy, NULL); in stream_ref() 54 c[i] = block[i]; in stream_ref() 57 sodium_memzero(block, sizeof block); in stream_ref() 69 unsigned char block[64]; in stream_ref_xor_ic() local 88 crypto_core_salsa20(block, in, kcopy, NULL); in stream_ref_xor_ic() 90 c[i] = m[i] ^ block[i]; in stream_ref_xor_ic() 103 crypto_core_salsa20(block, in, kcopy, NULL); in stream_ref_xor_ic() 105 c[i] = m[i] ^ block[i]; in stream_ref_xor_ic() 108 sodium_memzero(block, sizeof block); in stream_ref_xor_ic()
|
| /f-stack/app/redis-5.0.5/deps/lua/src/ |
| H A D | lmem.c | 46 void *luaM_growaux_ (lua_State *L, void *block, int *size, size_t size_elems, in luaM_growaux_() argument 60 newblock = luaM_reallocv(L, block, *size, newsize, size_elems); in luaM_growaux_() 76 void *luaM_realloc_ (lua_State *L, void *block, size_t osize, size_t nsize) { in luaM_realloc_() argument 78 lua_assert((osize == 0) == (block == NULL)); in luaM_realloc_() 79 block = (*g->frealloc)(g->ud, block, osize, nsize); in luaM_realloc_() 80 if (block == NULL && nsize > 0) in luaM_realloc_() 82 lua_assert((nsize == 0) == (block == NULL)); in luaM_realloc_() 84 return block; in luaM_realloc_()
|
| /f-stack/freebsd/contrib/libb2/ |
| H A D | blake2b.c | 278 uint8_t block[BLAKE2B_BLOCKBYTES]; in blake2b_init_key() local 279 memset( block, 0, BLAKE2B_BLOCKBYTES ); in blake2b_init_key() 280 memcpy( block, key, keylen ); in blake2b_init_key() 300 const __m128i m0 = LOADU( block + 00 ); in blake2b_compress() 301 const __m128i m1 = LOADU( block + 16 ); in blake2b_compress() 302 const __m128i m2 = LOADU( block + 32 ); in blake2b_compress() 303 const __m128i m3 = LOADU( block + 48 ); in blake2b_compress() 304 const __m128i m4 = LOADU( block + 64 ); in blake2b_compress() 305 const __m128i m5 = LOADU( block + 80 ); in blake2b_compress() 306 const __m128i m6 = LOADU( block + 96 ); in blake2b_compress() [all …]
|
| H A D | blake2s.c | 263 uint8_t block[BLAKE2S_BLOCKBYTES]; in blake2s_init_key() local 264 memset( block, 0, BLAKE2S_BLOCKBYTES ); in blake2s_init_key() 265 memcpy( block, key, keylen ); in blake2s_init_key() 266 blake2s_update( S, block, BLAKE2S_BLOCKBYTES ); in blake2s_init_key() 289 const __m128i m0 = LOADU( block + 00 ); in blake2s_compress() 290 const __m128i m1 = LOADU( block + 16 ); in blake2s_compress() 291 const __m128i m2 = LOADU( block + 32 ); in blake2s_compress() 292 const __m128i m3 = LOADU( block + 48 ); in blake2s_compress() 294 const uint32_t m0 = ( ( uint32_t * )block )[ 0]; in blake2s_compress() 295 const uint32_t m1 = ( ( uint32_t * )block )[ 1]; in blake2s_compress() [all …]
|
| /f-stack/freebsd/mips/nlm/ |
| H A D | board.c | 287 switch (block) { in nlm_board_get_phyaddr() 457 for (block = 0; block < naep->nblocks; block++) { in nlm_setup_xlp_board() 463 blockp->block = block; in nlm_setup_xlp_board() 470 if ((!evp && !svp) && ((block == 2) || (block == 3))) in nlm_setup_xlp_board() 473 if (block == 4) { in nlm_setup_xlp_board() 480 naep->sgmiimask |= (1 << block); in nlm_setup_xlp_board() 486 naep->ilmask |= (1 << block); in nlm_setup_xlp_board() 496 naep->xauimask |= (1 << block); in nlm_setup_xlp_board() 511 if (svp || (block == 4)) in nlm_setup_xlp_board() 516 portp->block = block; in nlm_setup_xlp_board() [all …]
|
| /f-stack/app/redis-5.0.5/deps/jemalloc/src/ |
| H A D | base.c | 169 pages_huge(block, block->size); in base_auto_thp_switch() 174 block = block->next; in base_auto_thp_switch() 272 if (block == NULL) { in base_block_alloc() 296 block->next = NULL; in base_block_alloc() 300 return block; in base_block_alloc() 321 if (block == NULL) { in base_extent_alloc() 325 base->blocks = block; in base_extent_alloc() 355 if (block == NULL) { in base_new() 368 base_unmap(tsdn, extent_hooks, ind, block, block->size); in base_new() 401 next = block->next; in base_delete() [all …]
|
| /f-stack/freebsd/crypto/armv8/ |
| H A D | armv8_crypto_wrap.c | 160 uint8x16_t block; in armv8_aes_crypt_xts_block() local 162 block = vld1q_u8(from) ^ *tweak; in armv8_aes_crypt_xts_block() 165 block = armv8_aes_enc(rounds - 1, key_schedule, block); in armv8_aes_crypt_xts_block() 167 block = armv8_aes_dec(rounds - 1, key_schedule, block); in armv8_aes_crypt_xts_block() 169 vst1q_u8(to, block ^ *tweak); in armv8_aes_crypt_xts_block() 249 uint8_t block[AES_BLOCK_LEN]; in armv8_aes_encrypt_gcm() local 272 memset(block, 0, sizeof(block)); in armv8_aes_encrypt_gcm() 298 memset(block, 0, sizeof(block)); in armv8_aes_encrypt_gcm() 335 uint8_t block[AES_BLOCK_LEN]; in armv8_aes_decrypt_gcm() local 357 memset(block, 0, sizeof(block)); in armv8_aes_decrypt_gcm() [all …]
|
| /f-stack/dpdk/drivers/event/opdl/ |
| H A D | opdl_ring.h | 229 bool block); 255 const void *entries, uint32_t num_entries, bool block); 281 void *entries, uint32_t num_entries, bool block); 312 uint32_t num_entries, uint32_t *seq, bool block, bool atomic); 336 uint32_t num_entries, void *arg, bool block); 368 uint32_t num_entries, uint32_t *seq, bool block, 404 uint32_t num_entries, uint32_t *seq, bool block); 434 bool block); 464 bool block);
|
| /f-stack/freebsd/contrib/openzfs/module/lua/ |
| H A D | lmem.c | 45 void *luaM_growaux_ (lua_State *L, void *block, int *size, size_t size_elems, in luaM_growaux_() argument 59 newblock = luaM_reallocv(L, block, *size, newsize, size_elems); in luaM_growaux_() 74 void *luaM_realloc_ (lua_State *L, void *block, size_t osize, size_t nsize) { in luaM_realloc_() argument 77 size_t realosize = (block) ? osize : 0; in luaM_realloc_() 78 lua_assert((realosize == 0) == (block == NULL)); in luaM_realloc_() 83 newblock = (*g->frealloc)(g->ud, block, osize, nsize); in luaM_realloc_() 89 newblock = (*g->frealloc)(g->ud, block, osize, nsize); /* try again */ in luaM_realloc_()
|
| /f-stack/freebsd/contrib/xz-embedded/linux/lib/xz/ |
| H A D | xz_dec_stream.c | 105 } block; member 251 || s->block.uncompressed in dec_block() 267 != s->block.compressed) in dec_block() 276 + s->block.compressed; in dec_block() 287 s->block.hash.uncompressed += s->block.uncompressed; in dec_block() 290 sizeof(s->block.hash), s->block.hash.crc32); in dec_block() 292 ++s->block.count; in dec_block() 564 s->block.compressed = 0; in dec_block_header() 565 s->block.uncompressed = 0; in dec_block_header() 662 ++s->block.compressed; in dec_main() [all …]
|
| /f-stack/freebsd/contrib/device-tree/Bindings/powerpc/fsl/ |
| H A D | mpic-msgr.txt | 10 block. The type shall be <string-list> and the value shall be of the form 15 message register block's addressable register space. The type shall be 25 - mpic-msgr-receive-mask: Specifies what registers in the containing block 29 be <u32>. If not present, then all of the message registers in the block 34 An alias should be created for every message register block. They are not 37 'mpic-msgr-block<n>', where <n> is an integer specifying the block's number. 47 mpic_msgr_block0: mpic-msgr-block@41400 { 50 // Message registers 0 and 2 in this block can receive interrupts on 56 mpic_msgr_block1: mpic-msgr-block@42400 { 59 // Message registers 0 and 2 in this block can receive interrupts on
|
| /f-stack/dpdk/doc/guides/sample_app_ug/ |
| H A D | compiling.rst | 14 .. code-block:: console 20 .. code-block:: console 26 .. code-block:: console 45 .. code-block:: console 51 .. code-block:: console 57 .. code-block:: console 73 .. code-block:: console 81 .. code-block:: console
|