You've already forked FFmpeg
mirror of
https://github.com/FFmpeg/FFmpeg.git
synced 2025-11-23 21:54:53 +02:00
b7fc195e7a
GCC/Clang is smart enough to emit minss/maxss the same way as these functions. The only theoretical benefit was in x86_32, where x87 floats are used, but the penalty of making the clipping opaque to the compiler's scheduler plus moving values from mmx regs to xmm and back will offset any potential speedup. x86_32 builds targetting anything made in the last two decades and a half should use -msse -mfp=sse anyway. Signed-off-by: James Almer <jamrial@gmail.com>
120 lines
3.3 KiB
C
120 lines
3.3 KiB
C
/*
|
|
* Copyright (c) 2015 James Almer
|
|
*
|
|
* This file is part of FFmpeg.
|
|
*
|
|
* FFmpeg is free software; you can redistribute it and/or
|
|
* modify it under the terms of the GNU Lesser General Public
|
|
* License as published by the Free Software Foundation; either
|
|
* version 2.1 of the License, or (at your option) any later version.
|
|
*
|
|
* FFmpeg is distributed in the hope that it will be useful,
|
|
* but WITHOUT ANY WARRANTY; without even the implied warranty of
|
|
* MERCHANTABILITY or FITNESS FOR A PARTICULAR PURPOSE. See the GNU
|
|
* Lesser General Public License for more details.
|
|
*
|
|
* You should have received a copy of the GNU Lesser General Public
|
|
* License along with FFmpeg; if not, write to the Free Software
|
|
* Foundation, Inc., 51 Franklin Street, Fifth Floor, Boston, MA 02110-1301 USA
|
|
*/
|
|
|
|
#ifndef AVUTIL_X86_INTMATH_H
|
|
#define AVUTIL_X86_INTMATH_H
|
|
|
|
#include <stdint.h>
|
|
#include <stdlib.h>
|
|
#if HAVE_FAST_CLZ
|
|
#if defined(_MSC_VER)
|
|
#include <intrin.h>
|
|
#elif defined(__INTEL_COMPILER)
|
|
#include <immintrin.h>
|
|
#endif
|
|
#endif
|
|
#include "config.h"
|
|
|
|
#if HAVE_FAST_CLZ
|
|
#if (defined(__INTEL_COMPILER) && (__INTEL_COMPILER>=1216)) || defined(_MSC_VER)
|
|
# if defined(__INTEL_COMPILER)
|
|
# define ff_log2(x) (_bit_scan_reverse((x)|1))
|
|
# else
|
|
# define ff_log2 ff_log2_x86
|
|
static av_always_inline av_const int ff_log2_x86(unsigned int v)
|
|
{
|
|
unsigned long n;
|
|
_BitScanReverse(&n, v|1);
|
|
return n;
|
|
}
|
|
# endif
|
|
# define ff_log2_16bit av_log2
|
|
|
|
#if defined(__INTEL_COMPILER) || (defined(_MSC_VER) && (_MSC_VER >= 1700) && \
|
|
(defined(__BMI__) || !defined(__clang__)))
|
|
# define ff_ctz(v) _tzcnt_u32(v)
|
|
|
|
# if ARCH_X86_64
|
|
# define ff_ctzll(v) _tzcnt_u64(v)
|
|
# else
|
|
# define ff_ctzll ff_ctzll_x86
|
|
static av_always_inline av_const int ff_ctzll_x86(long long v)
|
|
{
|
|
return ((uint32_t)v == 0) ? _tzcnt_u32((uint32_t)(v >> 32)) + 32 : _tzcnt_u32((uint32_t)v);
|
|
}
|
|
# endif
|
|
#endif /* _MSC_VER */
|
|
|
|
#endif /* __INTEL_COMPILER */
|
|
|
|
#endif /* HAVE_FAST_CLZ */
|
|
|
|
#if defined(__GNUC__)
|
|
|
|
/* Our generic version of av_popcount is faster than GCC's built-in on
|
|
* CPUs that don't support the popcnt instruction.
|
|
*/
|
|
#if defined(__POPCNT__)
|
|
#define av_popcount __builtin_popcount
|
|
#if ARCH_X86_64
|
|
#define av_popcount64 __builtin_popcountll
|
|
#endif
|
|
|
|
#endif /* __POPCNT__ */
|
|
|
|
#if defined(__BMI2__)
|
|
|
|
#if AV_GCC_VERSION_AT_LEAST(5,1)
|
|
#if defined(ASSERT_LEVEL) && ASSERT_LEVEL >= 2
|
|
#define av_zero_extend av_zero_extend_bmi2
|
|
static av_always_inline av_const unsigned av_zero_extend_bmi2(unsigned a, unsigned p)
|
|
{
|
|
if (p > 31) abort();
|
|
return __builtin_ia32_bzhi_si(a, p);
|
|
}
|
|
#else
|
|
#define av_zero_extend __builtin_ia32_bzhi_si
|
|
#endif
|
|
#elif HAVE_INLINE_ASM
|
|
/* GCC releases before 5.1.0 have a broken bzhi builtin, so for those we
|
|
* implement it using inline assembly
|
|
*/
|
|
#define av_zero_extend av_zero_extend_bmi2
|
|
static av_always_inline av_const unsigned av_zero_extend_bmi2(unsigned a, unsigned p)
|
|
{
|
|
#if defined(ASSERT_LEVEL) && ASSERT_LEVEL >= 2
|
|
if (p > 31) abort();
|
|
#endif
|
|
if (av_builtin_constant_p(p))
|
|
return a & ((1U << p) - 1);
|
|
else {
|
|
unsigned x;
|
|
__asm__ ("bzhi %2, %1, %0 \n\t" : "=r"(x) : "rm"(a), "r"(p));
|
|
return x;
|
|
}
|
|
}
|
|
#endif /* AV_GCC_VERSION_AT_LEAST */
|
|
|
|
#endif /* __BMI2__ */
|
|
|
|
#endif /* __GNUC__ */
|
|
|
|
#endif /* AVUTIL_X86_INTMATH_H */
|