Return to accel_neon.cpp CVS log

Up to [Isaki's NoNo m68k/m88k emulator] / nono / vm

nono 1.5.0

//
// nono
// Copyright (C) 2024 nono project
// Licensed under nono-license.txt
//

//
// NEON
//

#include "videoctlr.h"
#include <arm_neon.h>

// コントラスト (1-254) を適用。dst サイズでクリップする。
// (ちなみに _gen は 1265 usec)
/*static*/ void
VideoCtlrDevice::RenderContrast_neon(BitmapRGBX& dst, const BitmapRGBX& src,
	uint32 contrast)
{
	uint8x8_t vcont = vdup_n_u8(contrast);

	// 今のところ幅は 2ピクセルで割り切れる。
	uint width = dst.GetWidth();
	for (uint y = 0, yend = dst.GetHeight(); y < yend; y++) {
		const uint32 *s32 = (const uint32 *)src.GetRowPtr(y);
		uint32 *d32 = (uint32 *)dst.GetRowPtr(y);
		uint32 *d32end = d32 + width;
		for (; d32 < d32end; ) {
			// 2ピクセルずつ処理する。
			// 614 usec

			uint8x8_t  vsrc = vld1_u8((const uint8 *)s32);
			uint16x8_t vmul = vmull_u8(vsrc, vcont);
			uint8x8_t  vres = vrshrn_n_u16(vmul, 8);
			vst1_u8((uint8 *)d32, vres);
			s32 += 2;
			d32 += 2;
		}
	}
}

This archive runs on limited infrastructure. Preserving old code on modern bandwidth. Automated agents are requested to crawl responsibly.