evgeny
38c9f229bc
- u_async.c: process immediate_queue BEFORE epoll_wait in uasync_poll - stcp_link.c: defensive NULL etcp_conn/etcp_link in stcp_link_close - utun_instance.c: move stcp_server_list_destroy_all to Phase J (before ETCP), add deferred drain in both Phase J and L - stcp.h/c: STCP_HS_ENC_CLIENT 6→38, STCP_HS_ENC_SERVER 7→39, exchange ed25519_pubkey in both handshake directions - etcp_connections.c: copy peer_ed25519 from STCP to ETCP_CONN in etcp_link_enter_ready_tcp; guard link->etcp in tcp_link_close_cb - chat_sync.c: fix lk->conn NULL dereference for TCP links - test_stcp.c: update stcp_server_create/stcp_client_connect callsites - tools/chat_tcp_test: change transport udp→tcp
113 lines
4.1 KiB
C
113 lines
4.1 KiB
C
/* Copyright (c) 2014, Cisco Systems, INC
|
|
Written by XiangMingZhu WeiZhou MinPeng YanWang
|
|
|
|
Redistribution and use in source and binary forms, with or without
|
|
modification, are permitted provided that the following conditions
|
|
are met:
|
|
|
|
- Redistributions of source code must retain the above copyright
|
|
notice, this list of conditions and the following disclaimer.
|
|
|
|
- Redistributions in binary form must reproduce the above copyright
|
|
notice, this list of conditions and the following disclaimer in the
|
|
documentation and/or other materials provided with the distribution.
|
|
|
|
THIS SOFTWARE IS PROVIDED BY THE COPYRIGHT HOLDERS AND CONTRIBUTORS
|
|
``AS IS'' AND ANY EXPRESS OR IMPLIED WARRANTIES, INCLUDING, BUT NOT
|
|
LIMITED TO, THE IMPLIED WARRANTIES OF MERCHANTABILITY AND FITNESS FOR
|
|
A PARTICULAR PURPOSE ARE DISCLAIMED. IN NO EVENT SHALL THE COPYRIGHT OWNER
|
|
OR CONTRIBUTORS BE LIABLE FOR ANY DIRECT, INDIRECT, INCIDENTAL, SPECIAL,
|
|
EXEMPLARY, OR CONSEQUENTIAL DAMAGES (INCLUDING, BUT NOT LIMITED TO,
|
|
PROCUREMENT OF SUBSTITUTE GOODS OR SERVICES; LOSS OF USE, DATA, OR
|
|
PROFITS; OR BUSINESS INTERRUPTION) HOWEVER CAUSED AND ON ANY THEORY OF
|
|
LIABILITY, WHETHER IN CONTRACT, STRICT LIABILITY, OR TORT (INCLUDING
|
|
NEGLIGENCE OR OTHERWISE) ARISING IN ANY WAY OUT OF THE USE OF THIS
|
|
SOFTWARE, EVEN IF ADVISED OF THE POSSIBILITY OF SUCH DAMAGE.
|
|
*/
|
|
|
|
#if !defined(X86CPU_H)
|
|
# define X86CPU_H
|
|
|
|
# if defined(OPUS_X86_MAY_HAVE_SSE)
|
|
# define MAY_HAVE_SSE(name) name ## _sse
|
|
# else
|
|
# define MAY_HAVE_SSE(name) name ## _c
|
|
# endif
|
|
|
|
# if defined(OPUS_X86_MAY_HAVE_SSE2)
|
|
# define MAY_HAVE_SSE2(name) name ## _sse2
|
|
# else
|
|
# define MAY_HAVE_SSE2(name) name ## _c
|
|
# endif
|
|
|
|
# if defined(OPUS_X86_MAY_HAVE_SSE4_1)
|
|
# define MAY_HAVE_SSE4_1(name) name ## _sse4_1
|
|
# else
|
|
# define MAY_HAVE_SSE4_1(name) name ## _c
|
|
# endif
|
|
|
|
# if defined(OPUS_X86_MAY_HAVE_AVX2)
|
|
# define MAY_HAVE_AVX2(name) name ## _avx2
|
|
# else
|
|
# define MAY_HAVE_AVX2(name) name ## _c
|
|
# endif
|
|
|
|
# if defined(OPUS_HAVE_RTCD) && \
|
|
((defined(OPUS_X86_MAY_HAVE_SSE) && !defined(OPUS_X86_PRESUME_SSE)) || \
|
|
(defined(OPUS_X86_MAY_HAVE_SSE2) && !defined(OPUS_X86_PRESUME_SSE2)) || \
|
|
(defined(OPUS_X86_MAY_HAVE_SSE4_1) && !defined(OPUS_X86_PRESUME_SSE4_1)) || \
|
|
(defined(OPUS_X86_MAY_HAVE_AVX2) && !defined(OPUS_X86_PRESUME_AVX2)))
|
|
int opus_select_arch(void);
|
|
# endif
|
|
|
|
# if defined(OPUS_X86_MAY_HAVE_SSE2)
|
|
# include "opus_defines.h"
|
|
|
|
/*MOVD should not impose any alignment restrictions, but the C standard does,
|
|
and UBSan will report errors if we actually make unaligned accesses.
|
|
Use this to work around those restrictions (which should hopefully all get
|
|
optimized to a single MOVD instruction).
|
|
GCC implemented _mm_loadu_si32() since GCC 11; HOWEVER, there is a bug!
|
|
https://gcc.gnu.org/bugzilla/show_bug.cgi?id=99754
|
|
LLVM implemented _mm_loadu_si32() since Clang 8.0, however the
|
|
__clang_major__ version number macro is unreliable, as vendors
|
|
(specifically, Apple) will use different numbering schemes than upstream.
|
|
Clang's advice is "use feature detection", but they do not provide feature
|
|
detection support for specific SIMD functions.
|
|
We follow the approach from the SIMDe project and instead detect unrelated
|
|
features that should be available in the version we want (see
|
|
<https://github.com/simd-everywhere/simde/blob/master/simde/simde-detect-clang.h>).*/
|
|
# if defined(__clang__)
|
|
# if __has_warning("-Wextra-semi-stmt") || \
|
|
__has_builtin(__builtin_rotateleft32)
|
|
# define OPUS_CLANG_8 (1)
|
|
# endif
|
|
# endif
|
|
# if !defined(_MSC_VER) && !OPUS_GNUC_PREREQ(11,3) && !defined(OPUS_CLANG_8)
|
|
# include <string.h>
|
|
# include <emmintrin.h>
|
|
|
|
# ifdef _mm_loadu_si32
|
|
# undef _mm_loadu_si32
|
|
# endif
|
|
# define _mm_loadu_si32 WORKAROUND_mm_loadu_si32
|
|
static inline __m128i WORKAROUND_mm_loadu_si32(void const* mem_addr) {
|
|
int val;
|
|
memcpy(&val, mem_addr, sizeof(val));
|
|
return _mm_cvtsi32_si128(val);
|
|
}
|
|
# elif defined(_MSC_VER)
|
|
/* MSVC needs this for _mm_loadu_si32 */
|
|
# include <immintrin.h>
|
|
# endif
|
|
|
|
# define OP_CVTEPI8_EPI32_M32(x) \
|
|
(_mm_cvtepi8_epi32(_mm_loadu_si32(x)))
|
|
|
|
# define OP_CVTEPI16_EPI32_M64(x) \
|
|
(_mm_cvtepi16_epi32(_mm_loadl_epi64((__m128i *)(void*)(x))))
|
|
|
|
# endif
|
|
|
|
#endif
|