Use SSE also in VBE video output

Author: maxdev1

applications/windowserver/src/video/vbe_video_output.cpp

@@ -21,6 +21,7 @@
 #include "vbe_video_output.hpp"
 #include <libvbedriver/vbedriver.hpp>
 #include <stdio.h>
+#include <immintrin.h>
 
 bool g_vbe_video_output::initializeWithSettings(uint32_t width, uint32_t height, uint32_t bits)
 {
@@ -37,17 +38,25 @@ void g_vbe_video_output::blit(g_rectangle invalid, g_rectangle sourceSize, g_col
 	uint16_t bpp = videoModeInformation.bpp;
 	uint8_t* position = ((uint8_t*) videoModeInformation.lfb) + (invalid.y * videoModeInformation.bpsl);
 
-	uint32_t right = invalid.x + invalid.width;
-	uint32_t bottom = invalid.y + invalid.height;
+	int right = invalid.x + invalid.width;
+	int bottom = invalid.y + invalid.height;
 
 	if(bpp == 32)
 	{
 		for(int y = invalid.y; y < bottom; y++)
 		{
+			auto sourceRow = &source[y * sourceSize.width];
+
 			auto position4 = (uint32_t*) position;
-			for(int x = invalid.x; x < right; x++)
+			int x = invalid.x;
+			for(; x < right - 4; x += 4)
+			{
+				__m128i data = _mm_loadu_si128((__m128i*) &sourceRow[x]);
+				_mm_storeu_si128((__m128i*) &position4[x], data);
+			}
+			for(; x < right; x++)
 			{
-				position4[x] = source[y * sourceSize.width + x];
+				position4[x] = sourceRow[x];
 			}
 			position += videoModeInformation.bpsl;
 		}